OpenGL de プログラミング

__global__関数はCPUからGPUで実行関数をコールするもの。
つまり、CUDA側の処理の開始点みたいなもの。

その書き方は次の通り

• 宣言や定義時には修飾子として「__global__」を付ける
• 呼び出す時には「<<<…　…>>>」を使って、「Grid数」や「Block数」を指定する

構文としては次のようになる

Func<<<Dg,Db,Ns,S>>>(parameter)

【例】

//------------- CUDAでの処理 ---------------//
__global__ void cuAddValue(float *gpuAryData)
{
	…　…
}

…　…

float *gpuAry;//GPUメモリ用

//GPU用にブロックとスレッドを用意
dim3 grid(100,1,1);//100個のグリッド
dim3 block(200,1,1);//200個のブロック
	
//グリッド100個、ブロック200個
cuAddValue<<<grid,block>>>(gpuAry);

dim3型。グリッドのサイズを指定する。（１グリッドあたりのブロックの数）
Dg.x * Dg.yが１グリッドあたりの総ブロック数となる。Dg.zは「１」。

dim3型。ブロックのサイズを指定する。（１ブロック当たりのスレッドの数）
Db.x*Db.y*Db.zが１ブロックあたりの総スレッド数となる。

size_t型。ブロック単位で動的に確保される共有メモリを指定する。
デフォルトは０。

cudaStream_t型。何らかのストリーム用。

__global__	カーネルを意味する。GPUで実行し、CPUからコールする
__device__	GPUでコールして、GPUで実行する
__host__	CPUでコールしてCPUで実行する