CUDA：メモリ修飾子の不正な組み合わせ

Question

I次のコードを持っている：

main.cu：

#include "class.h" 
int main() {} 

class.h：

class Class { 
    __global__ 
    void Function() {}; 
}; 

私はコマンドを使用してこのコードをコンパイルnvcc -c main.cu -o main.o、次のエラーが表示されます。

class.h(3): warning: inline qualifier ignored for "global" function 
class.h(3): error: illegal combination of memory qualifiers 

これらのエラーのそれぞれについて質問があります。なぜそれが関数のための修飾子__global__を "無視"するのですか？この文脈で__global__メモリ修飾子が不正なのはなぜですか？私はしかし、私の機能は私の知る限り、静的なメンバーではないdocumentation

その

E.2.10.2. Function Members 
Static member functions cannot be __global__ functions. 

で読みました。 __global__行を削除するとコンパイルでき、__global__とvoid Function();行をmain.cuに移動することもできます。これが実際に許可されていない場合、CUDAはこの制限を強制するのはなぜですか？構造化されたコードを維持しながらこれを回避する方法は何ですか？

明らかに、GPUカーネルを作成できる関数を持つクラスを作成する方法は他にありません。カーネルはmain.cuのグローバル関数からしか作成できないようです。私はCUDAのプログラミングをかなり新しくしているので、私には明らかではないかもしれないいくつかのCUDAの慣習を見逃しているかもしれません。このような場合は、教えてください私は適切なプログラミングの練習に追いつくことができますので。

Answer 1

CUDAカーネルをOOP形式で使用したいと考えています。これがそうであった場合は、以下のクラス構造は、動作するはずです：

// myclass.h 
class MyClass { 
    public: 
     void call_kernel(...); 
}; 

// myclass.cu 
__global__ 
void my_kernel(...) { 
    // do some work 
} 

void MyClass::call_kernel() { 
    // prepare data for the kernel, e.g. allocating memory, copying from host to device, etc. 

    // run kernel 
    my_kernel <<<...>>>(...); 

    // copy results from device to host, clean up, etc. 
} 

カーネルコードを含む複数のクラスを持っている場合、そのソースコードファイルはすべて.cu拡張子を使用する必要があり、そしてあなたがseparate compilationを有効にする必要がありますのでご注意ください。