threadIdx, blockIdx, blockDim

Ogni thread esegue lo stesso codice, quindi deve chiedersi: quale elemento di dati mi spetta? CUDA risponde con delle variabili predefinite. 📍

All'interno di un kernel, threadIdx indica a un thread la sua posizione nel proprio block. Il primo thread di un block ha threadIdx.x uguale a 0.

La variabile blockIdx indica a un thread a quale block appartiene all'interno della grid. Anche la numerazione dei block inizia da 0.

È disponibile anche blockDim, cioè il numero di thread per block. Se ha avviato 256 thread, blockDim.x vale 256 per ogni thread.

Non deve mai impostare personalmente queste variabili. CUDA le valorizza per ogni thread nel momento in cui il kernel viene avviato.

Ognuna di queste variabili dispone dei campi x, y e z per gli avvii 1D, 2D o 3D. Per gli array semplici, di solito si usa solo il campo x.

Da solo, threadIdx si ripete in ogni block. Per ottenere una posizione univoca, deve combinare blockIdx e blockDim con threadIdx.

Con blockDim uguale a 4, il thread 2 del block 0 corrisponde all'elemento 2, mentre il thread 2 del block 1 corrisponde all'elemento 6. Il block sposta il punto di partenza.

Questi elementi predefiniti sono di sola lettura all'interno del kernel. Li consideri delle coordinate affidabili che descrivono esattamente la posizione del thread.

C'è un altro elemento utile: gridDim contiene il numero totale di block nella grid. È comodo quando deve elaborare più dati di quanti siano i thread.

Queste tre variabili sono gli elementi di base per calcolare un indice globale, cioè il modo in cui ogni thread individua il proprio elemento.

Scelga la variabile che svolge il compito indicato.

Ha conosciuto gli elementi predefiniti: threadIdx per la posizione nel block, blockIdx per il block e blockDim per la dimensione del block. Insieme individuano con precisione un thread. ✅