__device__修飾子の範囲

Question

http://docs.nvidia.com/cuda/cuda-c-programming-guide/#device-variable-qualifierには、__device_修飾子変数に「アプリケーションの有効期間」があることが示されています。これはカーネルを意味しますか？複数のカーネルがある場合、CUDAはどの変数がどのカーネルに属しているかをどのように知ることができますか？

私は宣言した場合はそのような__device_変数：

void someHOSTfunction() { 
    __device__ int var; 
    // Launch kernel etc... 
} 

が、それは「ローカル」であるにも関わらず、まだ別の関数から起動カーネルからアクセス可能であることをまだグローバル意味で「VAR」ですsomeHOSTfunction（）のスタック上にあり、いくつかのHOSTfunction（）が返ってくるとスコープ（？）になりますか？

__device__ int var; 
void someHOSTfunction() { 
    // Launch kernel etc... 
} 

ここで、varはグローバル変数です。しかし、それは他の翻訳単位からもアクセス可能であることを意味します。これはおそらくそれを防ぐためには機能しません：

static __device__ int var; 
void someHOSTfunction() { 
    // Launch kernel etc... 
} 

これを行う適切な方法はありますか？

Answer 1

この：

void someHOSTfunction() { 
    __device__ int var; 
    // Launch kernel etc... 
} 

はCUDAでは違法です。 A __device__変数宣言は関数本体の中では許されません。そうしようとすると、コンパイラはエラーを出します。翻訳単位のスコープで宣言する必要があります。制限はすべての機能に適用され、__host__または__device__となります。

異なる静的に宣言された変数が異なるカーネルに必要な場合は、それぞれに異なる変数名を使用します。あるいは、ランタイムに割り当てられた変数を使用して、それをカーネルの引数として渡すか、テンプレートパラメータ変数などを使用します。しかし、あなたが言うことは、今日存在するCUDAでは不可能です。