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

最新推荐文章于 2024-04-03 13:35:01 发布

iteye_702

最新推荐文章于 2024-04-03 13:35:01 发布

阅读量166

点赞数

文章标签： c/c++ python runtime

一直想写一下global内存访问的文章，但是最近的事情太多，哎昨天。。。，今天的一篇paper也被拒了~~哎--
不过收到一个朋友（ from this AVerMedia TECHNOLOGIES(Suzhou), Inc. ）求助邮，看得出来项目比较棘手，应该是对CUDA的使用有些不清楚；
晚上熬夜写了一个简单的C++ class 封装CUDA的demo，里面涉及到了texture的使用，希望对他的CUDA学习有帮助：
下面是三部分的代码
1. 调用class的sample.cu 文件这里没多少好解释的，就是直接生产一个cuda的class实例，然后调用各个方法

 
 /********************************************************************
* sample.cu
*ThisisaexampleoftheCUDAprogram.
*author:zhao.kaiyong(at)gmail.com
*http://www.comp.hkbu.edu.hk/~kyzhao/
 *********************************************************************/ 
 
 #include<stdio.h> 
 #include<stdlib.h> 
 #include<cuda_runtime.h> 
 #include<cutil.h> 
 #include"cuda_class.h" 
 /************************************************************************/ 
 /*HelloCUDA*/ 
 /************************************************************************/ 
 intmain(intargc,char*argv[]) 
{
cuda_classcudaA;
 if(!cudaA.InitCUDA()){ 
 return0; 
}
 floathost_data[22]={0}; 
 floathost_result[11]={0}; 
 for(inti=0;i<22;i++) 
{
host_data[i]=i;
}
cudaA.InitTexture(host_data,11,2);
cudaA.MallocMemA(11);
 unsignedinttimer=0; 
CUT_SAFE_CALL(cutCreateTimer(&timer));
CUT_SAFE_CALL(cutStartTimer(timer));
cudaA.DoWork();
CUDA_SAFE_CALL(cudaThreadSynchronize());
CUT_SAFE_CALL(cutStopTimer(timer));
 printf("Processingtime:%f(ms)/n",cutGetTimerValue(timer)); 
CUT_SAFE_CALL(cutDeleteTimer(timer));
cudaA.TranslateResult(host_result);
cudaA.ReleaseMem();
 for(inti=0;i<11;i++) 
{
 printf("%f/n",host_result[i]); 
}
CUT_EXIT(argc,argv);
 return0; 
}
 

2. 两个class 文件

 
 /********************************************************************
*cuda_class.h
*ThisisaexampleoftheCUDAprogram.
*author:zhao.kaiyong(at)gmail.com
*http://www.comp.hkbu.edu.hk/~kyzhao/
 *********************************************************************/ 
 #ifndef__CUDA_CLASS_H__ 
 #define__CUDA_CLASS_H__ 
 #include<cutil.h> 
 classcuda_class 
{
 public: 
 cuda_class(void); 
 ~cuda_class(void); 
 intInitCUDA(); 
 intMallocMemA(intlen); 
 intInitTexture(float*init_data,intw,inth); 
 intDoWork(); 
 intTranslateResult(float*out_data); 
 intReleaseMem(); 
 intReleaseTex(); 
 private: 
 float*device_result; 
cudaArray*device_tex;
 intm_ret_len; 
};
 #endif//__CUDA_CLASS_H__ 
 

 
 /********************************************************************
*cuda_class.cu
*ThisisaexampleoftheCUDAprogram.
*author:zhao.kaiyong(at)gmail.com
*http://www.comp.hkbu.edu.hk/~kyzhao/
 *********************************************************************/ 
 #include"cuda_class.h" 
 #include<stdio.h> 
 #include<stdlib.h> 
 #include<cuda_runtime.h> 
 #include<cutil.h> 
 texture<float,2,cudaReadModeElementType>tex; 
 /************************************************************************/ 
 /*Example*/ 
 /************************************************************************/ 
 __global__staticvoidHelloCUDA(float*result,intnum) 
{
 inti=0; 
 for(i=0;i<num;i++){ 
 result[i]=tex2D(tex,(float)i,0)+tex2D(tex,(float)i,1); 
}
}
 cuda_class::cuda_class(void) 
{
}
 cuda_class::~cuda_class(void) 
{
}
 intcuda_class::InitCUDA() 
{
 /************************************************************************/ 
 /*InitCUDA*/ 
 /************************************************************************/ 
 #if__DEVICE_EMULATION__ 
 returntrue; 
 #else 
 intcount=0; 
 inti=0; 
cudaGetDeviceCount(&count);
 if(count==0){ 
 fprintf(stderr,"Thereisnodevice./n"); 
 returnfalse; 
}
 for(i=0;i<count;i++){ 
cudaDevicePropprop;
 if(cudaGetDeviceProperties(∝,i)==cudaSuccess){ 
 if(prop.major>=1){ 
 break; 
}
}
}
 if(i==count){ 
 fprintf(stderr,"ThereisnodevicesupportingCUDA./n"); 
 returnfalse; 
}
cudaSetDevice(i);
 printf("CUDAinitialized./n"); 
 returntrue; 
 #endif 
}
 intcuda_class::MallocMemA(intlen) 
{
m_ret_len=len;
 CUDA_SAFE_CALL(cudaMalloc((void**)&device_result,sizeof(float)*m_ret_len)); 
 return1; 
}
 intcuda_class::DoWork() 
{
HelloCUDA<<<1,1,0>>>(device_result,m_ret_len);
 CUT_CHECK_ERROR("Kernelexecutionfailed/n"); 
 return1; 
}
 intcuda_class::TranslateResult(float*out_data) 
{
 CUDA_SAFE_CALL(cudaMemcpy(out_data,device_result,sizeof(float)*m_ret_len,cudaMemcpyDeviceToHost)); 
 return1; 
}
 intcuda_class::ReleaseMem() 
{
CUDA_SAFE_CALL(cudaFree(device_result));
CUDA_SAFE_CALL(cudaFreeArray(device_tex));
CUDA_SAFE_CALL(cudaUnbindTexture(tex));
 return1; 
}
 intcuda_class::InitTexture(float*init_data,intw,inth) 
{
 cudaChannelFormatDescchannelDesc=cudaCreateChannelDesc<float>(); 
CUDA_SAFE_CALL(cudaMallocArray(&device_tex,&channelDesc,w,h));
 CUDA_SAFE_CALL(cudaMemcpyToArray(device_tex,0,0,init_data,sizeof(float)*w*h,cudaMemcpyHostToDevice)); 
CUDA_SAFE_CALL(cudaBindTextureToArray(tex,device_tex,channelDesc));
 return1; 
}
 

这里需要做个解释，现在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比较迷茫的朋友有一些帮忙.

<meta http-equiv="Content-Type" content="text/html; charset=utf-8"> <meta name="ProgId" content="Word.Document"> <meta name="Generator" content="Microsoft Word 12"> <meta name="Originator" content="Microsoft Word 12"> <link rel="File-List" href="file:///C:%5CDOCUME%7E1%5Ckelvin%5CLOCALS%7E1%5CTemp%5Cmsohtmlclip1%5C01%5Cclip_filelist.xml"> <link rel="themeData" href="file:///C:%5CDOCUME%7E1%5Ckelvin%5CLOCALS%7E1%5CTemp%5Cmsohtmlclip1%5C01%5Cclip_themedata.thmx"> <link rel="colorSchemeMapping" href="file:///C:%5CDOCUME%7E1%5Ckelvin%5CLOCALS%7E1%5CTemp%5Cmsohtmlclip1%5C01%5Cclip_colorschememapping.xml"> <style>  </style>

iteye_702

关注

0
点赞
踩
0

收藏

觉得还不错? 一键收藏
0
评论
在C++ class 中使用CUDA（包含texutre 2d的使用）

一直想写一下global内存访问的文章，但是最近的事情太多，哎昨天。。。，今天的一篇paper也被拒了~~哎-- 不过收到一个朋友（from this AVerMedia TECHNOLOGIES(Suzhou), Inc. ）求助邮，看得出来项目比较棘手，应该是对CUDA的使用有些不清楚；晚上熬夜写了一个简单的C++ class 封装CUDA的demo，里面涉及到了texture的使用，希望对他...
复制链接

扫一扫