kernel block 과 thread

vectorAdd.cu 파일을 보다보니 느낌표가 똭!

// Invoke kernel     int N = 50000;     int threadsPerBlock = 256;     int blocksPerGrid = (N + threadsPerBlock - 1) / threadsPerBlock;     VecAdd<<<blocksPerGrid, threadsPerBlock>>>(d_A, d_B, d_C, N);

kernel 에서
앞은 Grid당 Block의 갯수
뒤는 Block당 thread의 갯수를 나타낸다.

솔찍히 단일 GPU를 쓴다면 grid는 저~~~언혀 고려하지 않아도 되는데
괜히 머리 아프게 grid랑 이상한 개념들을 다 이야기 하는 바람에 이해만 어려웠던 듯 하다.


아무튼,  Devicequery를 다시 보면
블럭당 쓰레드의 최대 갯수는 512 이고
그리드당 블럭의 최대 갯수는 3차원 배열로 512x512x64가 한계이다.

Device 0: "GeForce 8800 GT"   CUDA Driver Version:                           3.20   CUDA Runtime Version:                          3.10   CUDA Capability Major revision number:         1   CUDA Capability Minor revision number:         1   Total amount of global memory:                 536543232 bytes   Number of multiprocessors:                     14   Number of cores:                               112   Total amount of constant memory:               65536 bytes   Total amount of shared memory per block:       16384 bytes   Total number of registers available per block: 8192   Warp size:                                     32   Maximum number of threads per block:           512   Maximum sizes of each dimension of a block:    512 x 512 x 64   Maximum sizes of each dimension of a grid:     65535 x 65535 x 1    2011/01/02 - [Programming/openCL / CUDA] - deviceQuery on 8600GT 512MB + CUDA 하드웨어 구조

그런 이유로, 아래의 예제에서는 3차원 배열로 쓰레드를 구성한 총갯수가 512를 넘지 않으면 작동을 했던 것이다.

dim3 blocksPerGrid(1,1); dim3 threadsPerBlock(8,8,8); 이 코드는 8*8*8 = 512로 쓰레드의 최대 갯수를 넘지 않아 실행이 되지만 dim3 blocksPerGrid(1,1); dim3 threadsPerBlock(9,9,9); 이 코드는 9*9*9 = 729로 쓰레드의 최대 갯수를 넘어 실행이 되지 않고 오류가 발생한다.  2011/01/22 - [Programming/openCL / CUDA] - CUDA 관련 해외글

한줄요약 : 단일 그래픽 카드로 CUDA를 하면 grid는 잊자! 좀 꺼져줘!!!!