| /external/opencv3/modules/cudalegacy/src/cuda/ |
| D | NCVPixelOperations.hpp | 51 template<> inline __host__ __device__ Ncv8u _pixMaxVal<Ncv8u>() {return UCHAR_MAX;} in _pixMaxVal()
61 template<> inline __host__ __device__ Ncv8u _pixMinVal<Ncv8u>() {return 0;} in _pixMinVal()
71 template<> struct TConvVec2Base<uchar1> {typedef Ncv8u TBase;};
72 template<> struct TConvVec2Base<uchar3> {typedef Ncv8u TBase;};
73 template<> struct TConvVec2Base<uchar4> {typedef Ncv8u TBase;};
90 template<> struct TConvBase2Vec<Ncv8u, 1> {typedef uchar1 TVec;};
91 template<> struct TConvBase2Vec<Ncv8u, 3> {typedef uchar3 TVec;};
92 template<> struct TConvBase2Vec<Ncv8u, 4> {typedef uchar4 TVec;};
107 …ame Tin> inline __host__ __device__ void _TDemoteClampZ(Tin &a, Ncv8u &out) {out = (Ncv8u)CLAMP_0_… in _TDemoteClampZ()
113 …me Tin> inline __host__ __device__ void _TDemoteClampNN(Tin &a, Ncv8u &out) {out = (Ncv8u)CLAMP_0_… in _TDemoteClampNN()
[all …]
|
| D | NCV.cu | 157 NCVStatus ncvDrawRects_8u_device(Ncv8u *d_dst, in ncvDrawRects_8u_device()
163 Ncv8u color, in ncvDrawRects_8u_device()
|
| D | NCVPyramid.cu | 195 T *d_src_line1 = (T *)((Ncv8u *)d_src + (2 * i + 0) * srcPitch); in kernelDownsampleX2()
196 T *d_src_line2 = (T *)((Ncv8u *)d_src + (2 * i + 1) * srcPitch); in kernelDownsampleX2()
197 T *d_dst_line = (T *)((Ncv8u *)d_dst + i * dstPitch); in kernelDownsampleX2()
273 T *d_src_line1 = (T *)((Ncv8u *)d_srcTop + yl * srcTopPitch); in kernelInterpolateFrom1()
274 T *d_src_line2 = (T *)((Ncv8u *)d_srcTop + yh * srcTopPitch); in kernelInterpolateFrom1()
275 T *d_dst_line = (T *)((Ncv8u *)d_dst + i * dstPitch); in kernelInterpolateFrom1()
366 Ncv8u numLayers,
|
| D | NPP_staging.cu | 54 texture<Ncv8u, 1, cudaReadModeElementType> tex8u;
230 inline __device__ Ncv8u readElem<Ncv8u>(Ncv8u *d_src, Ncv32u texOffs, Ncv32u srcStride, Ncv32u curE… in readElem()
337 cfdTex = cudaCreateChannelDesc<Ncv8u>(); in scanRowsWrapperDevice()
425 NCVStatus ncvSquaredIntegralImage_device(Ncv8u *d_src, Ncv32u srcStep, in ncvSquaredIntegralImage_device()
464 <true, Ncv8u, Ncv32u> in ncvSquaredIntegralImage_device()
495 NCVStatus ncvStat = ncvIntegralImage_device((Ncv8u*)NULL, roiSize.width, in nppiStIntegralGetSize_8u32u()
541 NCVStatus nppiStIntegral_8u32u_C1R(Ncv8u *d_src, Ncv32u srcStep, in nppiStIntegral_8u32u_C1R()
543 NcvSize32u roiSize, Ncv8u *pBuffer, in nppiStIntegral_8u32u_C1R()
558 NcvSize32u roiSize, Ncv8u *pBuffer, in nppiStIntegral_32f32f_C1R()
571 NCVStatus nppiStSqrIntegral_8u64u_C1R(Ncv8u *d_src, Ncv32u srcStep, in nppiStSqrIntegral_8u64u_C1R()
[all …]
|
| D | NCVHaarObjectDetection.cu | 1100 NCVVectorAlloc<Ncv8u> d_tmpBufCompact(gpuAllocator, szNppCompactTmpBuf); in ncvApplyHaarClassifierCascade_device()
1544 NCVStatus ncvDetectObjectsMultiScale_device(NCVMatrix<Ncv8u> &d_srcImg, in ncvDetectObjectsMultiScale_device()
1634 NCVVectorAlloc<Ncv8u> d_tmpIIbuf(gpuAllocator, std::max(szTmpBufIntegral, szTmpBufSqIntegral)); in ncvDetectObjectsMultiScale_device()
|
| /external/opencv3/modules/cudalegacy/test/ |
| D | TestIntegralImage.cpp | 97 if (sizeof(T_in) == sizeof(Ncv8u)) in process()
112 NCVVectorAlloc<Ncv8u> d_tmpBuf(*this->allocatorGPU.get(), bufSize); in process()
123 if (sizeof(T_in) == sizeof(Ncv8u)) in process()
125 ncvStat = nppiStIntegral_8u32u_C1R((Ncv8u *)d_img.ptr(), d_img.pitch(), in process()
147 if (sizeof(T_in) == sizeof(Ncv8u)) in process()
149 ncvStat = nppiStIntegral_8u32u_C1R_host((Ncv8u *)h_img.ptr(), h_img.pitch(), in process()
176 if (sizeof(T_in) == sizeof(Ncv8u)) in process()
214 template class TestIntegralImage<Ncv8u, Ncv32u>;
|
| D | TestDrawRects.cpp | 126 else if (sizeof(T) == sizeof(Ncv8u)) in process()
128 … ncvStat = ncvDrawRects_8u_device((Ncv8u *)d_img.ptr(), d_img.stride(), this->width, this->height, in process()
129 … (NcvRect32u *)d_rects.ptr(), this->numRects, (Ncv8u)this->color, 0); in process()
148 else if (sizeof(T) == sizeof(Ncv8u)) in process()
150 … ncvStat = ncvDrawRects_8u_host((Ncv8u *)h_img.ptr(), h_img.stride(), this->width, this->height, in process()
151 … (NcvRect32u *)h_rects.ptr(), this->numRects, (Ncv8u)this->color); in process()
193 template class TestDrawRects<Ncv8u>;
|
| D | main_nvidia.cpp | 76 void generateSquaredIntegralTests(NCVAutoTestLister &testLister, NCVTestSourceProvider<Ncv8u> &src, in generateSquaredIntegralTests()
97 void generateRectStdDevTests(NCVAutoTestLister &testLister, NCVTestSourceProvider<Ncv8u> &src, in generateRectStdDevTests()
217 else if (sizeof(T) == sizeof(Ncv8u)) in generateDrawRectsTests()
271 void generateHaarApplicationTests(NCVAutoTestLister &testLister, NCVTestSourceProvider<Ncv8u> &src, in generateHaarApplicationTests()
307 NCVTestSourceProvider<Ncv8u> testSrcRandom_8u(2010, 0, 255, 2048, 2048); in nvidia_NPPST_Integral_Image()
310 generateIntegralTests<Ncv8u, Ncv32u>(testListerII, testSrcRandom_8u, 2048, 2048); in nvidia_NPPST_Integral_Image()
323 NCVTestSourceProvider<Ncv8u> testSrcRandom_8u(2010, 0, 255, 2048, 2048); in nvidia_NPPST_Squared_Integral_Image()
337 NCVTestSourceProvider<Ncv8u> testSrcRandom_8u(2010, 0, 255, 2048, 2048); in nvidia_NPPST_RectStdDev()
424 NCVTestSourceProvider<Ncv8u> testSrcFacesVGA_8u(path + "group_1_640x480_VGA.pgm"); in nvidia_NCV_Haar_Cascade_Application()
452 NCVTestSourceProvider<Ncv8u> testSrcRandom_8u(2010, 0, 255, 2048, 2048); in nvidia_NCV_Visualization()
|
| D | TestIntegralImageSquared.cpp | 46 …alImageSquared::TestIntegralImageSquared(std::string testName_, NCVTestSourceProvider<Ncv8u> &src_, in TestIntegralImageSquared()
79 NCVMatrixAlloc<Ncv8u> d_img(*this->allocatorGPU.get(), this->width, this->height); in process()
81 NCVMatrixAlloc<Ncv8u> h_img(*this->allocatorCPU.get(), this->width, this->height); in process()
93 NCVVectorAlloc<Ncv8u> d_tmpBuf(*this->allocatorGPU.get(), bufSize); in process()
|
| D | TestIntegralImageSquared.h | 54 TestIntegralImageSquared(std::string testName, NCVTestSourceProvider<Ncv8u> &src,
66 NCVTestSourceProvider<Ncv8u> &src;
|
| D | TestHaarCascadeApplication.h | 54 TestHaarCascadeApplication(std::string testName, NCVTestSourceProvider<Ncv8u> &src,
67 NCVTestSourceProvider<Ncv8u> &src;
|
| D | TestRectStdDev.h | 54 TestRectStdDev(std::string testName, NCVTestSourceProvider<Ncv8u> &src,
67 NCVTestSourceProvider<Ncv8u> &src;
|
| D | TestRectStdDev.cpp | 46 TestRectStdDev::TestRectStdDev(std::string testName_, NCVTestSourceProvider<Ncv8u> &src_, in TestRectStdDev()
98 NCVMatrixAlloc<Ncv8u> d_img(*this->allocatorGPU.get(), this->width, this->height); in process()
100 NCVMatrixAlloc<Ncv8u> h_img(*this->allocatorCPU.get(), this->width, this->height); in process()
126 NCVVectorAlloc<Ncv8u> d_tmpBuf(*this->allocatorGPU.get(), bufSize); in process()
|
| D | TestHaarCascadeApplication.cpp | 85 …eApplication::TestHaarCascadeApplication(std::string testName_, NCVTestSourceProvider<Ncv8u> &src_, in TestHaarCascadeApplication()
169 NCVMatrixAlloc<Ncv8u> d_img(*this->allocatorGPU.get(), this->width, this->height); in process()
171 NCVMatrixAlloc<Ncv8u> h_img(*this->allocatorCPU.get(), this->width, this->height); in process()
206 …NCVVectorAlloc<Ncv8u> d_tmpIIbuf(*this->allocatorGPU.get(), std::max(szTmpBufIntegral, szTmpBufSqI… in process()
|
| D | TestCompact.cpp | 108 NCVVectorAlloc<Ncv8u> d_tmpBuf(*this->allocatorGPU.get(), bufSize); in process()
|
| /external/opencv3/modules/cudalegacy/include/opencv2/cudalegacy/ |
| D | NCV.hpp | 132 typedef unsigned char Ncv8u; typedef
139 Ncv8u x;
140 Ncv8u y;
141 Ncv8u width;
142 Ncv8u height;
144 …__host__ __device__ NcvRect8u(Ncv8u x_, Ncv8u y_, Ncv8u width_, Ncv8u height_) : x(x_), y(y_), wid… in NcvRect8u()
218 NCV_CT_ASSERT(sizeof(Ncv8u) == 1);
508 Ncv8u *allocBegin;
509 Ncv8u *begin;
510 Ncv8u *end;
[all …]
|
| D | NPP_staging.hpp | 701 NCVStatus nppiStIntegral_8u32u_C1R(Ncv8u *d_src, Ncv32u srcStep,
703 Ncv8u *pBuffer, Ncv32u bufSize, cudaDeviceProp &devProp);
713 Ncv8u *pBuffer, Ncv32u bufSize, cudaDeviceProp &devProp);
728 NCVStatus nppiStIntegral_8u32u_C1R_host(Ncv8u *h_src, Ncv32u srcStep,
769 NCVStatus nppiStSqrIntegral_8u64u_C1R(Ncv8u *d_src, Ncv32u srcStep,
771 Ncv8u *pBuffer, Ncv32u bufSize, cudaDeviceProp &devProp);
786 NCVStatus nppiStSqrIntegral_8u64u_C1R_host(Ncv8u *h_src, Ncv32u srcStep,
842 Ncv32u elemRemove, Ncv8u *pBuffer,
853 Ncv32s elemRemove, Ncv8u *pBuffer,
864 Ncv32f elemRemove, Ncv8u *pBuffer,
|
| D | NCVHaarObjectDetection.hpp | 87 ((NcvRect8u*)&(this->_ui2.x))->x = (Ncv8u)rectX; in setRect()
88 ((NcvRect8u*)&(this->_ui2.x))->y = (Ncv8u)rectY; in setRect()
89 ((NcvRect8u*)&(this->_ui2.x))->width = (Ncv8u)rectWidth; in setRect()
90 ((NcvRect8u*)&(this->_ui2.x))->height = (Ncv8u)rectHeight; in setRect()
360 CV_EXPORTS NCVStatus ncvDetectObjectsMultiScale_device(NCVMatrix<Ncv8u> &d_srcImg,
|
| D | NCVPyramid.hpp | 91 Ncv8u nLayers,
|
| /external/opencv3/modules/cudalegacy/src/ |
| D | NCV.cpp | 369 allocBegin = (Ncv8u *)malloc(capacity); in NCVMemStackAllocator()
377 allocBegin = (Ncv8u *)reusePtr; in NCVMemStackAllocator()
382 allocBegin = (Ncv8u *)(0x1); in NCVMemStackAllocator()
399 if (!bReusesMemory && (allocBegin != (Ncv8u *)(0x1))) in ~NCVMemStackAllocator()
530 seg.begin.ptr = (Ncv8u *)malloc(size); in alloc()
867 NCVStatus ncvDrawRects_8u_host(Ncv8u *h_dst, in ncvDrawRects_8u_host()
873 Ncv8u color) in ncvDrawRects_8u_host()
|
| /external/opencv3/samples/gpu/ |
| D | cascadeclassifier_nvidia_api.cpp | 102 NCVMatrixAlloc<Ncv8u> d_src(gpuAllocator, width, height); in process()
104 NCVMatrixAlloc<Ncv8u> h_src(cpuAllocator, width, height); in process()
|
| /external/opencv3/modules/cudaobjdetect/src/ |
| D | cascadeclassifier.cpp | 288 NCVMatrixAlloc<Ncv8u> d_src(gpuCounter, frameSize.width, frameSize.height); in calculateMemReqsAndAllocate()
289 NCVMatrixAlloc<Ncv8u> h_src(cpuCounter, frameSize.width, frameSize.height); in calculateMemReqsAndAllocate()
322 src_beg.ptr = (void*)src.ptr<Ncv8u>(); in process()
329 …NCVMatrixReuse<Ncv8u> d_src(src_seg, static_cast<int>(devProp.textureAlignment), src.cols, src.row… in process()
|