wehub-resource-sync
82 lines
2.9 KiB
Plaintext
82 lines
2.9 KiB
Plaintext
/*
|
|
* SPDX-FileCopyrightText: Copyright (c) 1993-2024 NVIDIA CORPORATION & AFFILIATES. All rights reserved.
|
|
* SPDX-License-Identifier: Apache-2.0
|
|
*
|
|
* Licensed under the Apache License, Version 2.0 (the "License");
|
|
* you may not use this file except in compliance with the License.
|
|
* You may obtain a copy of the License at
|
|
*
|
|
* http://www.apache.org/licenses/LICENSE-2.0
|
|
*
|
|
* Unless required by applicable law or agreed to in writing, software
|
|
* distributed under the License is distributed on an "AS IS" BASIS,
|
|
* WITHOUT WARRANTIES OR CONDITIONS OF ANY KIND, either express or implied.
|
|
* See the License for the specific language governing permissions and
|
|
* limitations under the License.
|
|
*/
|
|
#include "common/kernels/kernel.h"
|
|
namespace nvinfer1
|
|
{
|
|
namespace plugin
|
|
{
|
|
template <typename T>
|
|
pluginStatus_t extractFgScores_gpu(cudaStream_t stream, int N, int A, int H, int W, const void* scores, void* fgScores)
|
|
{
|
|
// Copy all the objectness scores for one batch
|
|
size_t size = A * H * W * sizeof(T);
|
|
for (int n = 0; n < N; n++)
|
|
{
|
|
// Find out the starting pointer of the objectness scores in the input
|
|
size_t offset_ld = (n * 2 + 1) * A * H * W;
|
|
// Find out the starting pointer of the objectness scores in the output
|
|
size_t offset_st = n * A * H * W;
|
|
CSC(cudaMemcpyAsync(((T*) fgScores) + offset_st, ((T*) scores) + offset_ld, size, cudaMemcpyDeviceToDevice, stream), STATUS_FAILURE);
|
|
}
|
|
|
|
return STATUS_SUCCESS;
|
|
}
|
|
|
|
template <typename T>
|
|
pluginStatus_t extractFgScores_cpu(int N,
|
|
int A,
|
|
int H,
|
|
int W,
|
|
const void* scores,
|
|
void* fgScores)
|
|
{
|
|
size_t size = A * H * W * sizeof(T);
|
|
for (int n = 0; n < N; n++)
|
|
{
|
|
size_t offset_ld = (n * 2 + 1) * A * H * W;
|
|
size_t offset_st = n * A * H * W;
|
|
memcpy(((T*) fgScores) + offset_st, ((T*) scores) + offset_ld, size);
|
|
}
|
|
return STATUS_SUCCESS;
|
|
}
|
|
|
|
pluginStatus_t extractFgScores(cudaStream_t stream,
|
|
const int N,
|
|
const int A,
|
|
const int H,
|
|
const int W,
|
|
const DataType t_scores,
|
|
const DLayout_t l_scores,
|
|
const void* scores,
|
|
const DataType t_fgScores,
|
|
const DLayout_t l_fgScores,
|
|
void* fgScores)
|
|
{
|
|
if (l_fgScores != NCHW || l_scores != NCHW)
|
|
return STATUS_BAD_PARAM;
|
|
|
|
if (t_fgScores != DataType::kFLOAT)
|
|
return STATUS_BAD_PARAM;
|
|
|
|
if (t_scores != DataType::kFLOAT)
|
|
return STATUS_BAD_PARAM;
|
|
|
|
return extractFgScores_gpu<float>(stream, N, A, H, W, scores, fgScores);
|
|
}
|
|
} // namespace plugin
|
|
} // namespace nvinfer1
|