common.hpp

00001 /*M///////////////////////////////////////////////////////////////////////////////////////
00002 //
00003 //  IMPORTANT: READ BEFORE DOWNLOADING, COPYING, INSTALLING OR USING.
00004 //
00005 //  By downloading, copying, installing or using the software you agree to this license.
00006 //  If you do not agree to this license, do not download, install,
00007 //  copy or use the software.
00008 //
00009 //
00010 //                           License Agreement
00011 //                For Open Source Computer Vision Library
00012 //
00013 // Copyright (C) 2000-2008, Intel Corporation, all rights reserved.
00014 // Copyright (C) 2009, Willow Garage Inc., all rights reserved.
00015 // Third party copyrights are property of their respective owners.
00016 //
00017 // Redistribution and use in source and binary forms, with or without modification,
00018 // are permitted provided that the following conditions are met:
00019 //
00020 //   * Redistribution's of source code must retain the above copyright notice,
00021 //     this list of conditions and the following disclaimer.
00022 //
00023 //   * Redistribution's in binary form must reproduce the above copyright notice,
00024 //     this list of conditions and the following disclaimer in the documentation
00025 //     and/or other materials provided with the distribution.
00026 //
00027 //   * The name of the copyright holders may not be used to endorse or promote products
00028 //     derived from this software without specific prior written permission.
00029 //
00030 // This software is provided by the copyright holders and contributors "as is" and
00031 // any express or implied warranties, including, but not limited to, the implied
00032 // warranties of merchantability and fitness for a particular purpose are disclaimed.
00033 // In no event shall the Intel Corporation or contributors be liable for any direct,
00034 // indirect, incidental, special, exemplary, or consequential damages
00035 // (including, but not limited to, procurement of substitute goods or services;
00036 // loss of use, data, or profits; or business interruption) however caused
00037 // and on any theory of liability, whether in contract, strict liability,
00038 // or tort (including negligence or otherwise) arising in any way out of
00039 // the use of this software, even if advised of the possibility of such damage.
00040 //
00041 //M*/
00042 
00043 #ifndef __OPENCV_CUDA_COMMON_HPP__
00044 #define __OPENCV_CUDA_COMMON_HPP__
00045 
00046 #include <cuda_runtime.h>
00047 #include "opencv2/core/cuda_types.hpp "
00048 #include "opencv2/core/cvdef.h"
00049 #include "opencv2/core/base.hpp"
00050 
00051 /** @file
00052  * @deprecated Use @ref cudev instead.
00053  */
00054 
00055 //! @cond IGNORED
00056 
00057 #ifndef CV_PI_F
00058     #ifndef CV_PI
00059         #define CV_PI_F 3.14159265f
00060     #else
00061         #define CV_PI_F ((float)CV_PI)
00062     #endif
00063 #endif
00064 
00065 namespace cv { namespace cuda {
00066     static inline void checkCudaError(cudaError_t err, const char* file, const int line, const char* func)
00067     {
00068         if (cudaSuccess != err)
00069             cv::error(cv::Error::GpuApiCallError, cudaGetErrorString(err), func, file, line);
00070     }
00071 }}
00072 
00073 #ifndef cudaSafeCall
00074     #define cudaSafeCall(expr)  cv::cuda::checkCudaError(expr, __FILE__, __LINE__, CV_Func)
00075 #endif
00076 
00077 namespace cv { namespace cuda
00078 {
00079     template <typename T> static inline bool isAligned(const T* ptr, size_t size)
00080     {
00081         return reinterpret_cast<size_t>(ptr) % size == 0;
00082     }
00083 
00084     static inline bool isAligned(size_t step, size_t size)
00085     {
00086         return step % size == 0;
00087     }
00088 }}
00089 
00090 namespace cv { namespace cuda
00091 {
00092     namespace device
00093     {
00094         __host__ __device__ __forceinline__ int divUp(int total, int grain)
00095         {
00096             return (total + grain - 1) / grain;
00097         }
00098 
00099         template<class T> inline void bindTexture(const textureReference* tex, const PtrStepSz<T>& img)
00100         {
00101             cudaChannelFormatDesc desc = cudaCreateChannelDesc<T>();
00102             cudaSafeCall( cudaBindTexture2D(0, tex, img.ptr(), &desc, img.cols, img.rows, img.step) );
00103         }
00104     }
00105 }}
00106 
00107 //! @endcond
00108 
00109 #endif // __OPENCV_CUDA_COMMON_HPP__
00110