詳解CUDA核函數及運行時參數

核函數是GPU每個thread上運行的程序。必須通過__gloabl__函數類型限定符定義。形式如下：

? ? ? ? ? ? ? ? __global__ void kernel(param list){ ?}

核函數只能在主機端調用，調用時必須申明執行參數。調用形式如下：

? ? ? ? ? ? ? ??Kernel<<<Dg,Db, Ns, S>>>(param list);

<<<>>>運算符內是核函數的執行參數，告訴編譯器運行時如何啟動核函數，用于說明內核函數中的線程數量，以及線程是如何組織的。

<<<>>>運算符對kernel函數完整的執行配置參數形式是<<<Dg, Db, Ns, S>>>

• 參數Dg用于定義整個grid的維度和尺寸，即一個grid有多少個block。為dim3類型。Dim3 Dg(Dg.x, Dg.y, 1)表示grid中每行有Dg.x個block，每列有Dg.y個block，第三維恒為1(目前一個核函數只有一個grid)。整個grid中共有Dg.x*Dg.y個block，其中Dg.x和Dg.y最大值為65535。

• 參數Db用于定義一個block的維度和尺寸，即一個block有多少個thread。為dim3類型。Dim3 Db(Db.x, Db.y, Db.z)表示整個block中每行有Db.x個thread，每列有Db.y個thread，高度為Db.z。Db.x和Db.y最大值為512，Db.z最大值為62。 一個block中共有Db.x*Db.y*Db.z個thread。計算能力為1.0,1.1的硬件該乘積的最大值為768，計算能力為1.2,1.3的硬件支持的最大值為1024。

• 參數Ns是一個可選參數，用于設置每個block除了靜態分配的shared Memory以外，最多能動態分配的shared memory大小，單位為byte。不需要動態分配時該值為0或省略不寫。

• 參數S是一個cudaStream_t類型的可選參數，初始值為零，表示該核函數處在哪個流之中。

總結

以上是生活随笔為你收集整理的详解CUDA核函数及运行时参数的全部內容，希望文章能夠幫你解決所遇到的問題。

如果覺得生活随笔網站內容還不錯，歡迎將生活随笔推薦給好友。