mirror/CMake
1
0
Fork 0
mirror of https://github.com/Kitware/CMake.git synced 2026-01-06 21:59:54 -06:00
Code Issues Packages Projects Releases Wiki Activity

CUDA: Update all tests to support NPPIF CUDA 13 deprecations

Browse Source
This commit is contained in:
Robert Maynard
2025-09-23 14:00:35 -04:00
committed by Brad King
parent 503ab73ee4
commit f25982c422
4 changed files with 48 additions and 12 deletions
Download Patch File Download Diff File Expand all files Collapse all files

15
Tests/Cuda/SharedRuntimePlusToolkit/nppif.cpp
View File

@@ -69,9 +69,18 @@ EXPORT int nppif_main()
return 1;
}
// copy src to dst
NppStatus ret =
nppiFilterRow_8u_C1R(d_pSrc, nSrcStep, d_pDst, nDstStep, oROI, d_pKernel,
nMaskSize, nAnchor, nDivisor);
NppStatus ret;
#if CUDART_VERSION >= 13000
NppStreamContext context;
context.hStream = 0; // execute on the default stream
ret =
nppiFilterRow_8u_C1R_Ctx(d_pSrc, nSrcStep, d_pDst, nDstStep, oROI,
d_pKernel, nMaskSize, nAnchor, nDivisor, context);
#else
ret = nppiFilterRow_8u_C1R(d_pSrc, nSrcStep, d_pDst, nDstStep, oROI,
d_pKernel, nMaskSize, nAnchor, nDivisor);
#endif
assert(ret == NPP_NO_ERROR);
Npp8u* h_imgres = new Npp8u[dimgpix];
err = cudaMemcpy(h_imgres, d_pDst, dimgsize, cudaMemcpyDeviceToHost);

15
Tests/Cuda/StaticRuntimePlusToolkit/nppif.cpp
View File

@@ -69,9 +69,18 @@ EXPORT int nppif_main()
return 1;
}
// copy src to dst
NppStatus ret =
nppiFilterRow_8u_C1R(d_pSrc, nSrcStep, d_pDst, nDstStep, oROI, d_pKernel,
nMaskSize, nAnchor, nDivisor);
NppStatus ret;
#if CUDART_VERSION >= 13000
NppStreamContext context;
context.hStream = 0; // execute on the default stream
ret =
nppiFilterRow_8u_C1R_Ctx(d_pSrc, nSrcStep, d_pDst, nDstStep, oROI,
d_pKernel, nMaskSize, nAnchor, nDivisor, context);
#else
ret = nppiFilterRow_8u_C1R(d_pSrc, nSrcStep, d_pDst, nDstStep, oROI,
d_pKernel, nMaskSize, nAnchor, nDivisor);
#endif
assert(ret == NPP_NO_ERROR);
Npp8u* h_imgres = new Npp8u[dimgpix];
err = cudaMemcpy(h_imgres, d_pDst, dimgsize, cudaMemcpyDeviceToHost);

15
Tests/CudaOnly/SharedRuntimePlusToolkit/nppif.cu
View File

@@ -69,9 +69,18 @@ EXPORT int nppif_main()
return 1;
}
// copy src to dst
NppStatus ret =
nppiFilterRow_8u_C1R(d_pSrc, nSrcStep, d_pDst, nDstStep, oROI, d_pKernel,
nMaskSize, nAnchor, nDivisor);
NppStatus ret;
#if CUDART_VERSION >= 13000
NppStreamContext context;
context.hStream = 0; // execute on the default stream
ret =
nppiFilterRow_8u_C1R_Ctx(d_pSrc, nSrcStep, d_pDst, nDstStep, oROI,
d_pKernel, nMaskSize, nAnchor, nDivisor, context);
#else
ret = nppiFilterRow_8u_C1R(d_pSrc, nSrcStep, d_pDst, nDstStep, oROI,
d_pKernel, nMaskSize, nAnchor, nDivisor);
#endif
assert(ret == NPP_NO_ERROR);
Npp8u* h_imgres = new Npp8u[dimgpix];
err = cudaMemcpy(h_imgres, d_pDst, dimgsize, cudaMemcpyDeviceToHost);

15
Tests/CudaOnly/StaticRuntimePlusToolkit/nppif.cu
View File

@@ -69,9 +69,18 @@ EXPORT int nppif_main()
return 1;
}
// copy src to dst
NppStatus ret =
nppiFilterRow_8u_C1R(d_pSrc, nSrcStep, d_pDst, nDstStep, oROI, d_pKernel,
nMaskSize, nAnchor, nDivisor);
NppStatus ret;
#if CUDART_VERSION >= 13000
NppStreamContext context;
context.hStream = 0; // execute on the default stream
ret =
nppiFilterRow_8u_C1R_Ctx(d_pSrc, nSrcStep, d_pDst, nDstStep, oROI,
d_pKernel, nMaskSize, nAnchor, nDivisor, context);
#else
ret = nppiFilterRow_8u_C1R(d_pSrc, nSrcStep, d_pDst, nDstStep, oROI,
d_pKernel, nMaskSize, nAnchor, nDivisor);
#endif
assert(ret == NPP_NO_ERROR);
Npp8u* h_imgres = new Npp8u[dimgpix];
err = cudaMemcpy(h_imgres, d_pDst, dimgsize, cudaMemcpyDeviceToHost);