CUDA核函数
在GPU上执行的函数称为CUDA核函数(Kernel Function),核函数会被GPU上多个线程执行,我们可以在核函数中获取当前线程的ID。
// CUDA核函数的定义
__global__ void addKernel(int *c, const int *a, const int *b){
int i = threadIdx.x;
c[i] = a[i] + b[i];
}
// CUDA核函数调用
addKernel<<>>(c, a, b);
可以总结出CUDA核函数的使用方式:
使用关键字global来标识,在CPU上调用,在GPU上执行,返回值为void
使用<<< >>>来指定线程索引方式
核函数相对于CPU是异步的,在核函数执行完之前就会返回,这样CPU可以不用等待核函数的完成,继续执行后续代码
核函数不支持可变参数,不支持静态变量,不支持函数指针
线程配置
这是刚刚接触GPU编程最为困惑的地方,到底应该如何去索引GPU的线程?首先要对GPU中的基本概念有所了解,可参考另一篇文章《GPU中的基本概念》
在Host端核函数的调用方式为:
kernel<<>>(param list);
其中,
Dg:int型或者dim3类型(x,y,z),用于定义一个Grid中Block是如何组织的,如果是int型,则表示一维组织结构
<