一个简单的C++ class 封装CUDA的demo，里面涉及到了texture的使用，希望对他的CUDA学习有帮助：
下面是代码 1. 调用class的sample.cu 文件这里没多少好解释的，就是直接生产一个cuda的class实例，然后调用各个方法 * sample.cu
* This is a example of the CUDA program.
* 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 */
int main(int argc, char* argv[])
{
cuda_class cudaA;
if(!cudaA.InitCUDA()) {
return 0;
}
float host_data[22] = {0};
float host_result[11] ={0};
for (int i = 0; i < 22; i++)
{
host_data[i] = i;
}
cudaA.InitTexture(host_data, 11, 2);
cudaA.MallocMemA(11);
unsigned int timer = 0;
CUT_SAFE_CALL( cutCreateTimer( &timer));
CUT_SAFE_CALL( cutStartTimer( timer));
cudaA.DoWork();
CUDA_SAFE_CALL( cudaThreadSynchronize() );
CUT_SAFE_CALL( cutStopTimer( timer));
printf("Processing time: %f (ms)\n", cutGetTimerValue( timer));
CUT_SAFE_CALL( cutDeleteTimer( timer));
cudaA.TranslateResult(host_result);
cudaA.ReleaseMem();
for (int i = 0; i < 11; i++)
{
printf("%f \n", host_result[i]);
}
CUT_EXIT(argc, argv);
return 0;
}
2. 两个class 文件 * cuda_class.h
* This is a example of the CUDA program.
* author: zhao.kaiyong(at)gmail.com
* http://www.comp.hkbu.edu.hk/~kyzhao/
#ifndef __CUDA_CLASS_H__
#define __CUDA_CLASS_H__
#include <cutil.h>
class cuda_class
{
public:
cuda_class(void);
~cuda_class(void);
int InitCUDA();
int MallocMemA(int len);
int InitTexture(float* init_data,int w, int h);
int DoWork();
int TranslateResult(float* out_data);
int ReleaseMem();
int ReleaseTex();
private:
float *device_result;
cudaArray* device_tex;
int m_ret_len;
};
#endif // __CUDA_CLASS_H__
* cuda_class.cu
* This is a example of the CUDA program.
* 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__ static void HelloCUDA(float* result, int num)
{
int i = 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)
{
}
int cuda_class::InitCUDA()
{
/* Init CUDA */
#if __DEVICE_EMULATION__
return true;
#else
int count = 0;
int i = 0;
cudaGetDeviceCount(&count);
if(count == 0) {
fprintf(stderr, "There is no device.\n");
return false;
}
for(i = 0; i < count; i++) {
cudaDeviceProp prop;
if(cudaGetDeviceProperties(∝, i) == cudaSuccess) {
if(prop.major >= 1) {
break;
}
}
}
if(i == count) {
fprintf(stderr, "There is no device supporting CUDA.\n");
return false;
}
cudaSetDevice(i);
printf("CUDA initialized.\n");
return true;
#endif
}
int cuda_class::MallocMemA(int len)
{
m_ret_len = len;
CUDA_SAFE_CALL( cudaMalloc((void**) &device_result, sizeof(float) * m_ret_len));
return 1;
}
int cuda_class::DoWork()
{
HelloCUDA<<<1, 1, 0>>>(device_result, m_ret_len);
CUT_CHECK_ERROR("Kernel execution failed\n");
return 1;
}
int cuda_class::TranslateResult(float * out_data)
{
CUDA_SAFE_CALL( cudaMemcpy(out_data, device_result, sizeof(float) * m_ret_len, cudaMemcpyDeviceToHost));
return 1;
}
int cuda_class::ReleaseMem()
{
CUDA_SAFE_CALL( cudaFree(device_result));
CUDA_SAFE_CALL( cudaFreeArray(device_tex));
CUDA_SAFE_CALL( cudaUnbindTexture(tex));
return 1;
}
int cuda_class::InitTexture(float* init_data, int w, int h)
{
cudaChannelFormatDesc channelDesc = 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));
return 1;
}
这里需要做个解释，现在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比较迷茫的朋友有一些帮忙.
责任编辑：小草
