在C++ class 中使用CUDA（包含texutre 2d的使用）

洛欣發表於2009-11-17
原文網址 : http://blog.itpub.net/22785983/viewspace-619849/
C++

晚上熬夜寫了一個簡單的C++ class 封裝CUDA的demo，裡面涉及到了texture的使用，希望對他的CUDA學習有幫助：
下面是三部分的程式碼
1. 呼叫class的sample.cu 檔案這裡沒多少好解釋的，就是直接生產一個cuda的class例項，然後呼叫各個方法

  1. /********************************************************************
  2. *  sample.cu
  3. *  This is a example of the CUDA program.
  4. *  author: zhao.kaiyong(at)gmail.com
  5. *  http://www.comp.hkbu.edu.hk/~kyzhao/
  6. *********************************************************************/
  8. #include 
  9. #include 
  10. #include 
  11. #include 
  12. #include "cuda_class.h"
  14. /************************************************************************/
  15. /* HelloCUDA                                                            */
  16. /************************************************************************/
  17. int main(int argc, char* argv[])
  18. {
  19.     cuda_class cudaA;
  21.     if(!cudaA.InitCUDA()) {
  22.         return 0;
  23.     }
  25.     float   host_data[22] = {0};
  26.     float   host_result[11] ={0};
  28.     for (int i = 0; i 
  29.     {
  30.         host_data[i] = i;
  31.     }
  33.     cudaA.InitTexture(host_data, 11, 2);
  34.     cudaA.Malloc垃圾廣告(11);
  36.     unsigned int timer = 0;
  37.     CUT_SAFE_CALL( cutCreateTimer( &timer));
  38.     CUT_SAFE_CALL( cutStartTimer( timer));
  40.     cudaA.DoWork();
  42.     CUDA_SAFE_CALL( cudaThreadSynchronize() );
  43.     CUT_SAFE_CALL( cutStopTimer( timer));
  44.     printf("Processing time: %f (ms)\n", cutGetTimerValue( timer));
  45.     CUT_SAFE_CALL( cutDeleteTimer( timer));
  47.     cudaA.TranslateResult(host_result);
  48.     cudaA.ReleaseMem();
  50.     for (int i = 0; i 
  51.     {
  52.         printf("%f \n", host_result[i]);
  53.     }
  57.     CUT_EXIT(argc, argv);
  59.     return 0;
  60. }


2. 兩個class 檔案

  1. /********************************************************************
  2. *  cuda_class.h
  3. *  This is a example of the CUDA program.
  4. *  author: zhao.kaiyong(at)gmail.com
  5. *  http://www.comp.hkbu.edu.hk/~kyzhao/
  6. *********************************************************************/
  7. #ifndef __CUDA_CLASS_H__
  8. #define __CUDA_CLASS_H__
  11. #include 
  13. class cuda_class
  14. {
  15. public:
  16.     cuda_class(void);
  17.     ~cuda_class(void);
  19.     int InitCUDA();
  20.     int Malloc垃圾廣告(int len);
  21.     int InitTexture(float* init_data,int w, int h);
  22.     int DoWork();
  24.     int TranslateResult(float* out_data);
  26.     int ReleaseMem();
  27.     int ReleaseTex();
  29. private:
  30.     float   *device_result;
  31.     cudaArray* device_tex;
  33.     int m_ret_len;
  34. };
  36. #endif // __CUDA_CLASS_H__
  1. /********************************************************************
  2. *  cuda_class.cu
  3. *  This is a example of the CUDA program.
  4. *  author: zhao.kaiyong(at)gmail.com
  5. *  http://www.comp.hkbu.edu.hk/~kyzhao/
  6. *********************************************************************/
  7. #include "cuda_class.h"
  8. #include 
  9. #include 
  10. #include 
  11. #include 
  13. texture<float, 2, cudaReadModeElementType> tex;
  15. /************************************************************************/
  16. /* Example                                                              */
  17. /************************************************************************/
  18. __global__ static void HelloCUDA(float* result, int num)
  19. {
  20.     int i = 0;
  21.     for(i = 0; i 
  22.         result[i] = tex2D(tex,(float) i,0) + tex2D(tex,(float)i,1);
  23.     }
  24. }
  26. cuda_class::cuda_class(void)
  27. {
  28. }
  30. cuda_class::~cuda_class(void)
  31. {
  32. }
  34. int cuda_class::InitCUDA()
  35. {
  36.     /************************************************************************/
  37.     /* Init CUDA                                                            */
  38.     /************************************************************************/
  39. #if __DEVICE_EMULATION__
  41.     return true;
  43. #else
  45.     int count = 0;
  46.     int i = 0;
  48.     cudaGetDeviceCount(&count);
  49.     if(count == 0) {
  50.         fprintf(stderr, "There is no device.\n");
  51.         return false;
  52.     }
  54.     for(i = 0; i 
  55.         cudaDeviceProp prop;
  56.         if(cudaGetDeviceProperties(∝, i) == cudaSuccess) {
  57.             if(prop.major >= 1) {
  58.                 break;
  59.             }
  60.         }
  61.     }
  62.     if(i == count) {
  63.         fprintf(stderr, "There is no device supporting CUDA.\n");
  64.         return false;
  65.     }
  66.     cudaSetDevice(i);
  68.     printf("CUDA initialized.\n");
  69.     return true;
  71. #endif
  72. }
  74. int cuda_class::Malloc垃圾廣告(int len)
  75. {
  76.     m_ret_len = len;
  77.     CUDA_SAFE_CALL( cudaMalloc((void**) &device_result, sizeof(float) * m_ret_len));
  78.     return 1;
  79. }
  81. int cuda_class::DoWork()
  82. {
  83.     HelloCUDA<<<1, 1, 0>>>(device_result, m_ret_len);
  84.     CUT_CHECK_ERROR("Kernel execution failed\n");
  85.     return 1;
  86. }
  89. int cuda_class::TranslateResult(float * out_data)
  90. {
  91.     CUDA_SAFE_CALL( cudaMemcpy(out_data, device_result, sizeof(float) * m_ret_len, cudaMemcpyDeviceToHost));
  92.     return 1;
  93. }
  95. int cuda_class::ReleaseMem()
  96. {
  97.     CUDA_SAFE_CALL( cudaFree(device_result));
  98.     CUDA_SAFE_CALL( cudaFreeArray(device_tex));
  99.     CUDA_SAFE_CALL( cudaUnbindTexture(tex));
  100.     return 1;
  101. }
  103. int cuda_class::InitTexture(float* init_data, int w, int h)
  104. {
  105.     cudaChannelFormatDesc channelDesc = cudaCreateChannelDesc<float>();
  107.     CUDA_SAFE_CALL( cudaMallocArray(&device_tex, &channelDesc, w, h));
  108.     CUDA_SAFE_CALL( cudaMemcpyToArray(device_tex, 0, 0, init_data, sizeof(float)* w*h , cudaMemcpyHostToDevice));
  109.     CUDA_SAFE_CALL( cudaBindTextureToArray(tex, device_tex, channelDesc));
  110.     return 1;
  111. }

這裡需要做個解釋，現在CUDA的cu檔案是可以直接按照c++方式編譯的，這個得在nvcc的編譯選項裡面可以設定為--host-compilation C++,在預設的情況下，以前2.0版本以前都是按照C格式編譯檔案，現在都是會按照C++方式編譯檔案，所以這裡可以直接用cu檔案來寫Class。

在編譯的時候，需要加上/MTd（debug), /MT(Release)版本，這裡是告訴xcompiler選項，支援C++的runtime庫，不然會有一些lib 訪問衝突。

下面是下載整個工程的下載連線：不過release版本編譯選項沒設定，這就留給大家自己熟悉環境吧~~不要問我怎麼設定……
http://download.csdn.net/user/OpenHero
cuda_cpp_class_texture_demo.rar

應該對C++和texture比較迷茫的朋友有一些幫忙.
原文

來自 “ ITPUB部落格 ” ，連結：http://blog.itpub.net/22785983/viewspace-619849/，如需轉載，請註明出處，否則將追究法律責任。

相關文章