deleted NPP_VERSION and NPP_HAVE_COMPLEX_TYPE macros, because last NPP supports compl...

diff --git a/modules/gpu/src/arithm.cpp b/modules/gpu/src/arithm.cpp
index 0c2da068a73ea4765731693b976509b5531b5b7f..2c6b3a9f03935d141ca0c6236afc0e2ec4c36845 100644 (file)
--- a/modules/gpu/src/arithm.cpp
+++ b/modules/gpu/src/arithm.cpp
@@ -96,12 +96,6 @@ cv::gpu::GpuMat cv::gpu::operator ^ (const GpuMat&, const GpuMat&) { throw_nogpu
 \r
 #else /* !defined (HAVE_CUDA) */\r
 \r
-#define NPP_VERSION (10 * NPP_VERSION_MAJOR + NPP_VERSION_MINOR)\r
-\r
-#if (defined(_WIN32) || defined(_WIN64)) && (NPP_VERSION >= 32)\r
-#   define NPP_HAVE_COMPLEX_TYPE\r
-#endif\r
-\r
 ////////////////////////////////////////////////////////////////////////\r
 // add subtract multiply divide\r
 \r
@@ -120,11 +114,7 @@ namespace
     {\r
         CV_DbgAssert(src1.size() == src2.size() && src1.type() == src2.type());\r
 \r
-#if NPP_VERSION >= 32\r
         CV_Assert(src1.type() == CV_8UC1 || src1.type() == CV_8UC4 || src1.type() == CV_32SC1 || src1.type() == CV_32FC1);\r
-#else\r
-        CV_Assert(src1.type() == CV_8UC1 || src1.type() == CV_8UC4 || src1.type() == CV_32FC1);\r
-#endif\r
 \r
         dst.create( src1.size(), src1.type() );\r
 \r
@@ -144,13 +134,11 @@ namespace
                 src2.ptr<Npp8u>(), src2.step,\r
                 dst.ptr<Npp8u>(), dst.step, sz, 0) );\r
             break;\r
-#if NPP_VERSION >= 32\r
         case CV_32SC1:\r
             nppSafeCall( npp_func_32sc1(src1.ptr<Npp32s>(), src1.step,\r
                 src2.ptr<Npp32s>(), src2.step,\r
                 dst.ptr<Npp32s>(), dst.step, sz) );\r
             break;\r
-#endif\r
         case CV_32FC1:\r
             nppSafeCall( npp_func_32fc1(src1.ptr<Npp32f>(), src1.step,\r
                 src2.ptr<Npp32f>(), src2.step,\r
@@ -167,13 +155,11 @@ namespace
         typedef NppStatus (*func_ptr)(const Npp32f *pSrc, int nSrcStep, Npp32f nValue, Npp32f *pDst,\r
                                       int nDstStep, NppiSize oSizeROI);\r
     };\r
-#ifdef NPP_HAVE_COMPLEX_TYPE\r
     template<> struct NppArithmScalarFunc<2>\r
     {\r
         typedef NppStatus (*func_ptr)(const Npp32fc *pSrc, int nSrcStep, Npp32fc nValue, Npp32fc *pDst,\r
                                       int nDstStep, NppiSize oSizeROI);\r
     };\r
-#endif\r
 \r
     template<int SCN, typename NppArithmScalarFunc<SCN>::func_ptr func> struct NppArithmScalar;\r
     template<typename NppArithmScalarFunc<1>::func_ptr func> struct NppArithmScalar<1, func>\r
@@ -189,7 +175,6 @@ namespace
             nppSafeCall( func(src.ptr<Npp32f>(), src.step, (Npp32f)sc[0], dst.ptr<Npp32f>(), dst.step, sz) );\r
         }\r
     };\r
-#ifdef NPP_HAVE_COMPLEX_TYPE\r
     template<typename NppArithmScalarFunc<2>::func_ptr func> struct NppArithmScalar<2, func>\r
     {\r
         static void calc(const GpuMat& src, const Scalar& sc, GpuMat& dst)\r
@@ -207,119 +192,66 @@ namespace
             nppSafeCall( func(src.ptr<Npp32fc>(), src.step, nValue, dst.ptr<Npp32fc>(), dst.step, sz) );\r
         }\r
     };\r
-#endif\r
 }\r
 \r
 void cv::gpu::add(const GpuMat& src1, const GpuMat& src2, GpuMat& dst)\r
 {\r
-#if NPP_VERSION >= 32\r
     nppArithmCaller(src1, src2, dst, nppiAdd_8u_C1RSfs, nppiAdd_8u_C4RSfs, nppiAdd_32s_C1R, nppiAdd_32f_C1R);\r
-#else\r
-    nppArithmCaller(src1, src2, dst, nppiAdd_8u_C1RSfs, nppiAdd_8u_C4RSfs, 0, nppiAdd_32f_C1R);\r
-#endif\r
 }\r
 \r
 void cv::gpu::subtract(const GpuMat& src1, const GpuMat& src2, GpuMat& dst)\r
 {\r
-#if NPP_VERSION >= 32\r
     nppArithmCaller(src2, src1, dst, nppiSub_8u_C1RSfs, nppiSub_8u_C4RSfs, nppiSub_32s_C1R, nppiSub_32f_C1R);\r
-#else\r
-    nppArithmCaller(src2, src1, dst, nppiSub_8u_C1RSfs, nppiSub_8u_C4RSfs, 0, nppiSub_32f_C1R);\r
-#endif\r
 }\r
 \r
 void cv::gpu::multiply(const GpuMat& src1, const GpuMat& src2, GpuMat& dst)\r
 {\r
-#if NPP_VERSION >= 32\r
     nppArithmCaller(src1, src2, dst, nppiMul_8u_C1RSfs, nppiMul_8u_C4RSfs, nppiMul_32s_C1R, nppiMul_32f_C1R);\r
-#else\r
-    nppArithmCaller(src1, src2, dst, nppiMul_8u_C1RSfs, nppiMul_8u_C4RSfs, 0, nppiMul_32f_C1R);\r
-#endif\r
 }\r
 \r
 void cv::gpu::divide(const GpuMat& src1, const GpuMat& src2, GpuMat& dst)\r
 {\r
-#if NPP_VERSION >= 32\r
     nppArithmCaller(src2, src1, dst, nppiDiv_8u_C1RSfs, nppiDiv_8u_C4RSfs, nppiDiv_32s_C1R, nppiDiv_32f_C1R);\r
-#else\r
-    nppArithmCaller(src2, src1, dst, nppiDiv_8u_C1RSfs, nppiDiv_8u_C4RSfs, 0, nppiDiv_32f_C1R);\r
-#endif\r
 }\r
 \r
 void cv::gpu::add(const GpuMat& src, const Scalar& sc, GpuMat& dst)\r
 {\r
-#ifdef NPP_HAVE_COMPLEX_TYPE\r
     typedef void (*caller_t)(const GpuMat& src, const Scalar& sc, GpuMat& dst);\r
     static const caller_t callers[] = {0, NppArithmScalar<1, nppiAddC_32f_C1R>::calc, NppArithmScalar<2, nppiAddC_32fc_C1R>::calc};\r
 \r
     CV_Assert(src.type() == CV_32FC1 || src.type() == CV_32FC2);\r
 \r
     callers[src.channels()](src, sc, dst);\r
-#else\r
-#   if NPP_VERSION >= 32\r
-        CV_Assert(src.type() == CV_32FC1);\r
-        NppArithmScalar<1, nppiAddC_32f_C1R>::calc(src, sc, dst);\r
-#   else\r
-        CV_Assert(!"This function doesn't supported");\r
-#   endif\r
-#endif\r
 }\r
 \r
 void cv::gpu::subtract(const GpuMat& src, const Scalar& sc, GpuMat& dst)\r
 {\r
-#ifdef NPP_HAVE_COMPLEX_TYPE\r
     typedef void (*caller_t)(const GpuMat& src, const Scalar& sc, GpuMat& dst);\r
     static const caller_t callers[] = {0, NppArithmScalar<1, nppiSubC_32f_C1R>::calc, NppArithmScalar<2, nppiSubC_32fc_C1R>::calc};\r
 \r
     CV_Assert(src.type() == CV_32FC1 || src.type() == CV_32FC2);\r
 \r
     callers[src.channels()](src, sc, dst);\r
-#else\r
-#   if NPP_VERSION >= 32\r
-        CV_Assert(src.type() == CV_32FC1);\r
-        NppArithmScalar<1, nppiSubC_32f_C1R>::calc(src, sc, dst);\r
-#   else\r
-        CV_Assert(!"This function doesn't supported");\r
-#   endif\r
-#endif\r
 }\r
 \r
 void cv::gpu::multiply(const GpuMat& src, const Scalar& sc, GpuMat& dst)\r
 {\r
-#ifdef NPP_HAVE_COMPLEX_TYPE\r
     typedef void (*caller_t)(const GpuMat& src, const Scalar& sc, GpuMat& dst);\r
     static const caller_t callers[] = {0, NppArithmScalar<1, nppiMulC_32f_C1R>::calc, NppArithmScalar<2, nppiMulC_32fc_C1R>::calc};\r
 \r
     CV_Assert(src.type() == CV_32FC1 || src.type() == CV_32FC2);\r
 \r
     callers[src.channels()](src, sc, dst);\r
-#else\r
-#   if NPP_VERSION >= 32\r
-        CV_Assert(src.type() == CV_32FC1);\r
-        NppArithmScalar<1, nppiMulC_32f_C1R>::calc(src, sc, dst);\r
-#   else\r
-        CV_Assert(!"This function doesn't supported");\r
-#   endif\r
-#endif\r
 }\r
 \r
 void cv::gpu::divide(const GpuMat& src, const Scalar& sc, GpuMat& dst)\r
 {\r
-#ifdef NPP_HAVE_COMPLEX_TYPE\r
     typedef void (*caller_t)(const GpuMat& src, const Scalar& sc, GpuMat& dst);\r
     static const caller_t callers[] = {0, NppArithmScalar<1, nppiDivC_32f_C1R>::calc, NppArithmScalar<2, nppiDivC_32fc_C1R>::calc};\r
 \r
     CV_Assert(src.type() == CV_32FC1 || src.type() == CV_32FC2);\r
 \r
     callers[src.channels()](src, sc, dst);\r
-#else\r
-#   if NPP_VERSION >= 32\r
-        CV_Assert(src.type() == CV_32FC1);\r
-        NppArithmScalar<1, nppiDivC_32f_C1R>::calc(src, sc, dst);\r
-#   else\r
-        CV_Assert(!"This function doesn't supported");\r
-#   endif\r
-#endif\r
 }\r
 \r
 ////////////////////////////////////////////////////////////////////////\r
@@ -345,11 +277,7 @@ void cv::gpu::absdiff(const GpuMat& src1, const GpuMat& src2, GpuMat& dst)
 {\r
     CV_DbgAssert(src1.size() == src2.size() && src1.type() == src2.type());\r
 \r
-#if NPP_VERSION >= 32\r
     CV_Assert(src1.type() == CV_8UC1 || src1.type() == CV_8UC4 || src1.type() == CV_32SC1 || src1.type() == CV_32FC1);\r
-#else\r
-    CV_Assert(src1.type() == CV_8UC1 || src1.type() == CV_8UC4 || src1.type() == CV_32FC1);\r
-#endif\r
 \r
     dst.create( src1.size(), src1.type() );\r
 \r
@@ -369,13 +297,11 @@ void cv::gpu::absdiff(const GpuMat& src1, const GpuMat& src2, GpuMat& dst)
             src2.ptr<Npp8u>(), src2.step,\r
             dst.ptr<Npp8u>(), dst.step, sz) );\r
         break;\r
-#if NPP_VERSION >= 32\r
     case CV_32SC1:\r
         nppSafeCall( nppiAbsDiff_32s_C1R(src1.ptr<Npp32s>(), src1.step,\r
             src2.ptr<Npp32s>(), src2.step,\r
             dst.ptr<Npp32s>(), dst.step, sz) );\r
         break;\r
-#endif\r
     case CV_32FC1:\r
         nppSafeCall( nppiAbsDiff_32f_C1R(src1.ptr<Npp32f>(), src1.step,\r
             src2.ptr<Npp32f>(), src2.step,\r
@@ -388,7 +314,6 @@ void cv::gpu::absdiff(const GpuMat& src1, const GpuMat& src2, GpuMat& dst)
 \r
 void cv::gpu::absdiff(const GpuMat& src, const Scalar& s, GpuMat& dst)\r
 {\r
-#if NPP_VERSION >= 32\r
     CV_Assert(src.type() == CV_32FC1);\r
 \r
     dst.create( src.size(), src.type() );\r
@@ -398,9 +323,6 @@ void cv::gpu::absdiff(const GpuMat& src, const Scalar& s, GpuMat& dst)
     sz.height = src.rows;\r
 \r
     nppSafeCall( nppiAbsDiffC_32f_C1R(src.ptr<Npp32f>(), src.step, dst.ptr<Npp32f>(), dst.step, sz, (Npp32f)s[0]) );\r
-#else\r
-    CV_Assert(!"This function doesn't supported");\r
-#endif\r
 }\r
 \r
 ////////////////////////////////////////////////////////////////////////\r
@@ -534,6 +456,8 @@ void cv::gpu::flip(const GpuMat& src, GpuMat& dst, int flipCode)
 \r
 Scalar cv::gpu::sum(const GpuMat& src)\r
 {\r
+    CV_Assert(!"disabled until fix crash");\r
+\r
     CV_Assert(src.type() == CV_8UC1 || src.type() == CV_8UC4);\r
 \r
     NppiSize sz;\r
@@ -541,8 +465,6 @@ Scalar cv::gpu::sum(const GpuMat& src)
     sz.height = src.rows;\r
 \r
     Scalar res;\r
-#if NPP_VERSION >= 32\r
-    CV_Assert(!"disabled until fix crash");\r
 \r
     int bufsz;\r
 \r
@@ -560,12 +482,6 @@ Scalar cv::gpu::sum(const GpuMat& src)
 \r
         nppSafeCall( nppiSum_8u_C4R(src.ptr<Npp8u>(), src.step, sz, buf.ptr<Npp32s>(), res.val) );\r
     }\r
-#else\r
-    if (src.type() == CV_8UC1)\r
-        nppSafeCall( nppiSum_8u_C1R(src.ptr<Npp8u>(), src.step, sz, res.val) );\r
-    else\r
-        nppSafeCall( nppiSum_8u_C4R(src.ptr<Npp8u>(), src.step, sz, res.val) );\r
-#endif\r
 \r
     return res;\r
 }\r
@@ -600,11 +516,7 @@ namespace
 \r
         Npp8u* cuMem;\r
 \r
-#if NPP_VERSION >= 32\r
         cuMem = nppsMalloc_8u(8);\r
-#else\r
-        cudaSafeCall( cudaMalloc((void**)&cuMem, 8 * sizeof(Npp8u)) );\r
-#endif\r
 \r
         nppSafeCall( nppiMinMax_8u_C4R(src.ptr<Npp8u>(), src.step, sz, cuMem, cuMem + 4) );\r
 \r
@@ -613,11 +525,7 @@ namespace
         if (maxVal)\r
             cudaMemcpy(maxVal, cuMem + 4, 4 * sizeof(Npp8u), cudaMemcpyDeviceToHost);\r
 \r
-#if NPP_VERSION >= 32\r
         nppsFree(cuMem);\r
-#else\r
-        cudaSafeCall( cudaFree(cuMem) );\r
-#endif\r
     }\r
 }\r
 \r
@@ -696,7 +604,6 @@ void cv::gpu::LUT(const GpuMat& src, const Mat& lut, GpuMat& dst)
 \r
 void cv::gpu::exp(const GpuMat& src, GpuMat& dst)\r
 {\r
-#if NPP_VERSION >= 32\r
     CV_Assert(src.type() == CV_32FC1);\r
 \r
     dst.create(src.size(), src.type());\r
@@ -706,9 +613,6 @@ void cv::gpu::exp(const GpuMat& src, GpuMat& dst)
     sz.height = src.rows;\r
 \r
     nppSafeCall( nppiExp_32f_C1R(src.ptr<Npp32f>(), src.step, dst.ptr<Npp32f>(), dst.step, sz) );\r
-#else\r
-    CV_Assert(!"This function doesn't supported");\r
-#endif\r
 }\r
 \r
 ////////////////////////////////////////////////////////////////////////\r
@@ -716,7 +620,6 @@ void cv::gpu::exp(const GpuMat& src, GpuMat& dst)
 \r
 void cv::gpu::log(const GpuMat& src, GpuMat& dst)\r
 {\r
-#if NPP_VERSION >= 32\r
     CV_Assert(src.type() == CV_32FC1);\r
 \r
     dst.create(src.size(), src.type());\r
@@ -726,15 +629,11 @@ void cv::gpu::log(const GpuMat& src, GpuMat& dst)
     sz.height = src.rows;\r
 \r
     nppSafeCall( nppiLn_32f_C1R(src.ptr<Npp32f>(), src.step, dst.ptr<Npp32f>(), dst.step, sz) );\r
-#else\r
-    CV_Assert(!"This function doesn't supported");\r
-#endif\r
 }\r
 \r
 ////////////////////////////////////////////////////////////////////////\r
 // NPP magnitide\r
 \r
-#ifdef NPP_HAVE_COMPLEX_TYPE\r
 namespace\r
 {\r
     typedef NppStatus (*nppMagnitude_t)(const Npp32fc* pSrc, int nSrcStep, Npp32f* pDst, int nDstStep, NppiSize oSizeROI);\r
@@ -752,24 +651,15 @@ namespace
         nppSafeCall( func(src.ptr<Npp32fc>(), src.step, dst.ptr<Npp32f>(), dst.step, sz) );\r
     }\r
 }\r
-#endif\r
 \r
 void cv::gpu::magnitude(const GpuMat& src, GpuMat& dst)\r
 {\r
-#ifdef NPP_HAVE_COMPLEX_TYPE\r
     ::npp_magnitude(src, dst, nppiMagnitude_32fc32f_C1R);\r
-#else\r
-    CV_Assert(!"This function doesn't supported");\r
-#endif\r
 }\r
 \r
 void cv::gpu::magnitudeSqr(const GpuMat& src, GpuMat& dst)\r
 {\r
-#ifdef NPP_HAVE_COMPLEX_TYPE\r
     ::npp_magnitude(src, dst, nppiMagnitudeSqr_32fc32f_C1R);\r
-#else\r
-    CV_Assert(!"This function doesn't supported");\r
-#endif\r
 }\r
 \r
 ////////////////////////////////////////////////////////////////////////\r
@@ -871,7 +761,7 @@ void cv::gpu::polarToCart(const GpuMat& magnitude, const GpuMat& angle, GpuMat&
 //////////////////////////////////////////////////////////////////////////////\r
 // Per-element bit-wise logical matrix operations\r
 \r
-namespace cv { namespace gpu { namespace mathfunc \r
+namespace cv { namespace gpu { namespace mathfunc\r
 {\r
     void bitwise_not_caller(int rows, int cols, const PtrStep src, int elemSize, PtrStep dst, cudaStream_t stream);\r
     void bitwise_not_caller(int rows, int cols, const PtrStep src, int elemSize, PtrStep dst, const PtrStep mask, cudaStream_t stream);\r
@@ -887,7 +777,7 @@ namespace cv { namespace gpu { namespace mathfunc
     void bitwise_bin_op(int rows, int cols, const PtrStep src1, const PtrStep src2, PtrStep dst, int elem_size, Mask mask, cudaStream_t stream);\r
 }}}\r
 \r
-namespace \r
+namespace\r
 {\r
     void bitwise_not_caller(const GpuMat& src, GpuMat& dst, cudaStream_t stream)\r
     {\r
@@ -951,7 +841,7 @@ namespace
 \r
 void cv::gpu::bitwise_not(const GpuMat& src, GpuMat& dst, const GpuMat& mask)\r
 {\r
-    if (mask.empty()) \r
+    if (mask.empty())\r
         ::bitwise_not_caller(src, dst, 0);\r
     else\r
         ::bitwise_not_caller(src, dst, mask, 0);\r

diff --git a/modules/gpu/src/graphcuts.cpp b/modules/gpu/src/graphcuts.cpp
index c538a458c7bb4754f28eb1213e1344ec5bfdfe3c..6c4883b5ad38749553082f83f415d37df8bbe867 100644 (file)
--- a/modules/gpu/src/graphcuts.cpp
+++ b/modules/gpu/src/graphcuts.cpp
@@ -48,11 +48,8 @@ void cv::gpu::graphcut(GpuMat&, GpuMat&, GpuMat&, GpuMat&, GpuMat&, GpuMat&, Gpu
 \r
 #else /* !defined (HAVE_CUDA) */\r
 \r
-#define NPP_VERSION (10 * NPP_VERSION_MAJOR + NPP_VERSION_MINOR)\r
-\r
 void cv::gpu::graphcut(GpuMat& terminals, GpuMat& leftTransp, GpuMat& rightTransp, GpuMat& top, GpuMat& bottom, GpuMat& labels, GpuMat& buf)\r
 {\r
-#if NPP_VERSION >= 32\r
     CV_Assert(leftTransp.type() == CV_32S && rightTransp.type() == CV_32S);\r
     CV_Assert(terminals.type() == CV_32S && bottom.type() == CV_32S && top.type() == CV_32S);\r
     CV_Assert(terminals.size() == leftTransp.size());\r
@@ -74,9 +71,6 @@ void cv::gpu::graphcut(GpuMat& terminals, GpuMat& leftTransp, GpuMat& rightTrans
 \r
     nppSafeCall( nppiGraphcut_32s8u(terminals.ptr<Npp32s>(), leftTransp.ptr<Npp32s>(), rightTransp.ptr<Npp32s>(), top.ptr<Npp32s>(), bottom.ptr<Npp32s>(),\r
         terminals.step, leftTransp.step, sznpp, labels.ptr<Npp8u>(), labels.step, buf.ptr<Npp8u>()) );\r
-#else\r
-    CV_Assert(!"This function doesn't supported");\r
-#endif\r
 }\r
 \r
 \r

diff --git a/modules/gpu/src/imgproc_gpu.cpp b/modules/gpu/src/imgproc_gpu.cpp
index 357b655019e6e0cecdd6ef43a9ae1221dee04d13..74f30144ab654e674994b51e01721b7131af5791 100644 (file)
--- a/modules/gpu/src/imgproc_gpu.cpp
+++ b/modules/gpu/src/imgproc_gpu.cpp
@@ -71,8 +71,6 @@ void cv::gpu::histRange(const GpuMat&, GpuMat*, const GpuMat*) { throw_nogpu();
 \r
 #else /* !defined (HAVE_CUDA) */\r
 \r
-#define NPP_VERSION (10 * NPP_VERSION_MAJOR + NPP_VERSION_MINOR)\r
-\r
 namespace cv { namespace gpu {  namespace imgproc\r
 {\r
     void remap_gpu_1c(const DevMem2D& src, const DevMem2Df& xmap, const DevMem2Df& ymap, DevMem2D dst);\r
@@ -579,7 +577,6 @@ void cv::gpu::rectStdDev(const GpuMat& src, const GpuMat& sqr, GpuMat& dst, cons
 \r
 void cv::gpu::Canny(const GpuMat& image, GpuMat& edges, double threshold1, double threshold2, int apertureSize)\r
 {\r
-#if NPP_VERSION >= 32\r
     CV_Assert(!"disabled until fix crash");\r
     CV_Assert(image.type() == CV_8UC1);\r
 \r
@@ -603,9 +600,6 @@ void cv::gpu::Canny(const GpuMat& image, GpuMat& edges, double threshold1, doubl
 \r
     nppSafeCall( nppiCanny_32f8u_C1R(srcDx.ptr<Npp32f>(), srcDx.step, srcDy.ptr<Npp32f>(), srcDy.step,\r
         edges.ptr<Npp8u>(), edges.step, sz, (Npp32f)threshold1, (Npp32f)threshold2, buf.ptr<Npp8u>()) );\r
-#else\r
-    CV_Assert(!"This function doesn't supported");\r
-#endif\r
 }\r
 \r
 ////////////////////////////////////////////////////////////////////////\r
@@ -789,18 +783,13 @@ namespace
 \r
 void cv::gpu::evenLevels(GpuMat& levels, int nLevels, int lowerLevel, int upperLevel)\r
 {\r
-#if NPP_VERSION >= 32\r
     Mat host_levels(1, nLevels, CV_32SC1);\r
     nppSafeCall( nppiEvenLevelsHost_32s(host_levels.ptr<Npp32s>(), nLevels, lowerLevel, upperLevel) );\r
     levels.upload(host_levels);\r
-#else\r
-    CV_Assert(!"This function doesn't supported");\r
-#endif\r
 }\r
 \r
 void cv::gpu::histEven(const GpuMat& src, GpuMat& hist, int histSize, int lowerLevel, int upperLevel)\r
 {\r
-#if NPP_VERSION >= 32\r
     CV_Assert(src.type() == CV_8UC1 || src.type() == CV_16UC1 || src.type() == CV_16SC1 );\r
 \r
     typedef void (*hist_t)(const GpuMat& src, GpuMat& hist, int levels, int lowerLevel, int upperLevel);\r
@@ -813,14 +802,10 @@ void cv::gpu::histEven(const GpuMat& src, GpuMat& hist, int histSize, int lowerL
     };\r
 \r
     hist_callers[src.depth()](src, hist, histSize, lowerLevel, upperLevel);\r
-#else\r
-    CV_Assert(!"This function doesn't supported");\r
-#endif\r
 }\r
 \r
 void cv::gpu::histEven(const GpuMat& src, GpuMat hist[4], int histSize[4], int lowerLevel[4], int upperLevel[4])\r
 {\r
-#if NPP_VERSION >= 32\r
     CV_Assert(src.type() == CV_8UC4 || src.type() == CV_16UC4 || src.type() == CV_16SC4 );\r
 \r
     typedef void (*hist_t)(const GpuMat& src, GpuMat hist[4], int levels[4], int lowerLevel[4], int upperLevel[4]);\r
@@ -833,14 +818,10 @@ void cv::gpu::histEven(const GpuMat& src, GpuMat hist[4], int histSize[4], int l
     };\r
 \r
     hist_callers[src.depth()](src, hist, histSize, lowerLevel, upperLevel);\r
-#else\r
-    CV_Assert(!"This function doesn't supported");\r
-#endif\r
 }\r
 \r
 void cv::gpu::histRange(const GpuMat& src, GpuMat& hist, const GpuMat& levels)\r
 {\r
-#if NPP_VERSION >= 32\r
     CV_Assert(src.type() == CV_8UC1 || src.type() == CV_16UC1 || src.type() == CV_16SC1 || src.type() == CV_32FC1);\r
 \r
     typedef void (*hist_t)(const GpuMat& src, GpuMat& hist, const GpuMat& levels);\r
@@ -855,14 +836,10 @@ void cv::gpu::histRange(const GpuMat& src, GpuMat& hist, const GpuMat& levels)
     };\r
 \r
     hist_callers[src.depth()](src, hist, levels);\r
-#else\r
-    CV_Assert(!"This function doesn't supported");\r
-#endif\r
 }\r
 \r
 void cv::gpu::histRange(const GpuMat& src, GpuMat hist[4], const GpuMat levels[4])\r
 {\r
-#if NPP_VERSION >= 32\r
     CV_Assert(src.type() == CV_8UC4 || src.type() == CV_16UC4 || src.type() == CV_16SC4 || src.type() == CV_32FC4);\r
 \r
     typedef void (*hist_t)(const GpuMat& src, GpuMat hist[4], const GpuMat levels[4]);\r
@@ -877,9 +854,6 @@ void cv::gpu::histRange(const GpuMat& src, GpuMat hist[4], const GpuMat levels[4
     };\r
 \r
     hist_callers[src.depth()](src, hist, levels);\r
-#else\r
-    CV_Assert(!"This function doesn't supported");\r
-#endif\r
 }\r
 \r
 #endif /* !defined (HAVE_CUDA) */\r

diff --git a/modules/gpu/src/matrix_operations.cpp b/modules/gpu/src/matrix_operations.cpp
index cebb6a3c5033034aefdbd4ec4947283ce37297fa..56377a27b81ab79ca57818e76b614cfe40479ac1 100644 (file)
--- a/modules/gpu/src/matrix_operations.cpp
+++ b/modules/gpu/src/matrix_operations.cpp
@@ -77,8 +77,6 @@ namespace cv
 \r
 #else /* !defined (HAVE_CUDA) */\r
 \r
-#define NPP_VERSION (10 * NPP_VERSION_MAJOR + NPP_VERSION_MINOR)\r
-\r
 namespace cv\r
 {\r
     namespace gpu\r
@@ -234,11 +232,7 @@ void cv::gpu::GpuMat::convertTo( GpuMat& dst, int rtype, double alpha, double be
                 {NppCvt<CV_8U, CV_16U, nppiConvert_8u16u_C1R>::cvt,convertToKernelCaller,convertToKernelCaller,NppCvt<CV_8U, CV_16U, nppiConvert_8u16u_C4R>::cvt},\r
                 {NppCvt<CV_8U, CV_16S, nppiConvert_8u16s_C1R>::cvt,convertToKernelCaller,convertToKernelCaller,NppCvt<CV_8U, CV_16S, nppiConvert_8u16s_C4R>::cvt},\r
                 {convertToKernelCaller,convertToKernelCaller,convertToKernelCaller,convertToKernelCaller},\r
-#if NPP_VERSION >= 32\r
                 {NppCvt<CV_8U, CV_32F, nppiConvert_8u32f_C1R>::cvt,convertToKernelCaller,convertToKernelCaller,convertToKernelCaller},\r
-#else\r
-                {convertToKernelCaller,convertToKernelCaller,convertToKernelCaller,convertToKernelCaller},\r
-#endif\r
                 {convertToKernelCaller,convertToKernelCaller,convertToKernelCaller,convertToKernelCaller},\r
                 {0,0,0,0}\r
             },\r
@@ -283,11 +277,7 @@ void cv::gpu::GpuMat::convertTo( GpuMat& dst, int rtype, double alpha, double be
                 {0,0,0,0}\r
             },\r
             {\r
-#if NPP_VERSION >= 32\r
                 {NppCvt<CV_32F, CV_8U, nppiConvert_32f8u_C1R>::cvt,convertToKernelCaller,convertToKernelCaller,convertToKernelCaller},\r
-#else\r
-                {convertToKernelCaller,convertToKernelCaller,convertToKernelCaller,convertToKernelCaller},\r
-#endif\r
                 {convertToKernelCaller,convertToKernelCaller,convertToKernelCaller,convertToKernelCaller},\r
                 {NppCvt<CV_32F, CV_16U, nppiConvert_32f16u_C1R>::cvt,convertToKernelCaller,convertToKernelCaller,convertToKernelCaller},\r
                 {NppCvt<CV_32F, CV_16S, nppiConvert_32f16s_C1R>::cvt,convertToKernelCaller,convertToKernelCaller,convertToKernelCaller},\r
@@ -431,26 +421,10 @@ GpuMat& GpuMat::setTo(const Scalar& s, const GpuMat& mask)
         {\r
             {NppSet<CV_8U, 1, nppiSet_8u_C1R>::set,kernelSet,kernelSet,NppSet<CV_8U, 4, nppiSet_8u_C4R>::set},\r
             {kernelSet,kernelSet,kernelSet,kernelSet},\r
-#if NPP_VERSION >= 32\r
             {NppSet<CV_16U, 1, nppiSet_16u_C1R>::set,kernelSet,kernelSet,NppSet<CV_16U, 4, nppiSet_16u_C4R>::set},\r
-#else\r
-            {kernelSet,kernelSet,kernelSet,kernelSet},\r
-#endif\r
-#if NPP_VERSION >= 32\r
             {NppSet<CV_16S, 1, nppiSet_16s_C1R>::set,kernelSet,kernelSet,NppSet<CV_16S, 4, nppiSet_16s_C4R>::set},\r
-#else\r
-            {kernelSet,kernelSet,kernelSet,kernelSet},\r
-#endif\r
-#if NPP_VERSION >= 32\r
             {NppSet<CV_32S, 1, nppiSet_32s_C1R>::set,kernelSet,kernelSet,NppSet<CV_32S, 4, nppiSet_32s_C4R>::set},\r
-#else\r
-            {NppSet<CV_32S, 1, nppiSet_32s_C1R>::set,kernelSet,kernelSet,kernelSet},\r
-#endif\r
-#if NPP_VERSION >= 32\r
             {NppSet<CV_32F, 1, nppiSet_32f_C1R>::set,kernelSet,kernelSet,NppSet<CV_32F, 4, nppiSet_32f_C4R>::set},\r
-#else\r
-            {NppSet<CV_32F, 1, nppiSet_32f_C1R>::set,kernelSet,kernelSet,kernelSet},\r
-#endif\r
             {kernelSet,kernelSet,kernelSet,kernelSet},\r
             {0,0,0,0}\r
         };\r
@@ -458,7 +432,6 @@ GpuMat& GpuMat::setTo(const Scalar& s, const GpuMat& mask)
     }\r
     else\r
     {\r
-#if NPP_VERSION >= 32\r
         typedef void (*set_caller_t)(GpuMat& src, const Scalar& s, const GpuMat& mask);\r
         static const set_caller_t set_callers[8][4] =\r
         {\r
@@ -472,9 +445,6 @@ GpuMat& GpuMat::setTo(const Scalar& s, const GpuMat& mask)
             {0,0,0,0}\r
         };\r
         set_callers[depth()][channels()-1](*this, s, mask);\r
-#else\r
-        kernelSetMask(*this, s, mask);\r
-#endif\r
     }\r
 \r
     return *this;\r