struct - CUDA: 構造体内の構造体の配列の割り当て

Question

私はこれらの構造体を持っています:

typedef struct neuron
{
float*  weights;
int n_weights;
}Neuron;


typedef struct neurallayer
{
Neuron *neurons;
int    n_neurons;
int    act_function;
}NLayer;

「NLayer」構造体には、任意の数の「Neuron」を含めることができます

この方法で、ホストから 5 つの「ニューロン」を持つ「NLayer」構造体を割り当てようとしました。

NLayer* nL;
int i;
int tmp=9;
cudaMalloc((void**)&nL,sizeof(NLayer));
cudaMalloc((void**)&nL->neurons,6*sizeof(Neuron));
for(i=0;i<5;i++)
    cudaMemcpy(&nL->neurons[i].n_weights,&tmp,sizeof(int),cudaMemcpyHostToDevice);

...次に、そのカーネルで「nL->neurons[0].n_weights」変数を変更しようとしました:

__global__ void test(NLayer* n)
           {
              n->neurons[0].n_weights=121;
           }

しかし、コンパイル時に nvcc は、カーネルの唯一の行に関連する「警告」を返します。

Warning: Cannot tell what pointer points to, assuming global memory space

カーネルが作業を終了すると、構造体に到達できなくなります。

割り当て中に何か間違ったことをしている可能性が非常に高いです....誰かが私を助けることができますか?? どうもありがとう、そして私の英語でごめんなさい！:)

アップデート：

aland のおかげで、構造体 "NLayer" のインスタンスを割り当てる必要があるこの関数を作成するコードを修正しました。

NLayer* setNLayer(int numNeurons,int weightsPerNeuron,int act_fun)
{
    int i;
    NLayer  h_layer;
    NLayer* d_layer;
    float*  d_weights;

    //SET THE LAYER VARIABLE OF THE HOST NLAYER
    h_layer.act_function=act_fun;
    h_layer.n_neurons=numNeurons;
    //ALLOCATING THE DEVICE NLAYER
    if(cudaMalloc((void**)&d_layer,sizeof(NLayer))!=cudaSuccess)
        puts("ERROR: Unable to allocate the Layer");
    //ALLOCATING THE NEURONS ON THE DEVICE
    if(cudaMalloc((void**)&h_layer.neurons,numNeurons*sizeof(Neuron))!=cudaSuccess)
        puts("ERROR: Unable to allocate the Neurons of the Layer");
    //COPING THE HOST NLAYER ON THE DEVICE
    if(cudaMemcpy(d_layer,&h_layer,sizeof(NLayer),cudaMemcpyHostToDevice)!=cudaSuccess)
                puts("ERROR: Unable to copy the data layer onto the device");

    for(i=0;i<numNeurons;i++)
    {
        //ALLOCATING THE WEIGHTS' ARRAY ON THE DEVICE
        cudaMalloc((void**)&d_weights,weightsPerNeuron*sizeof(float));
        //COPING ITS POINTER AS PART OF THE i-TH NEURONS STRUCT
        if(cudaMemcpy(&d_layer->neurons[i].weights,&d_weights,sizeof(float*),cudaMemcpyHostToDevice)!=cudaSuccess)
                puts("Error: unable to copy weights' pointer to the device");
    }


    //RETURN THE DEVICE POINTER
    return d_layer;
}

そして、その関数をそのようにメインから呼び出します（カーネル「テスト」は以前に宣言されています）：

int main()
{
    NLayer* nL;
    int h_tmp1;
    float h_tmp2;

    nL=setNLayer(10,12,13);
    test<<<1,1>>>(nL);
    if(cudaMemcpy(&h_tmp1,&nL->neurons[0].n_weights,sizeof(float),cudaMemcpyDeviceToHost)!=cudaSuccess);
        puts("ERROR!!");
    printf("RESULT:%d",h_tmp1);

}

そのコードをコンパイルすると、コンパイラは警告を表示し、プログラムを実行すると画面に出力されます。

Error: unable to copy weights' pointer to the device
Error: unable to copy weights' pointer to the device
Error: unable to copy weights' pointer to the device
Error: unable to copy weights' pointer to the device
Error: unable to copy weights' pointer to the device
Error: unable to copy weights' pointer to the device
Error: unable to copy weights' pointer to the device
Error: unable to copy weights' pointer to the device
Error: unable to copy weights' pointer to the device
Error: unable to copy weights' pointer to the device
ERROR!!
RESULT:1

カーネル呼び出しをコメントすると、最後のエラーは比較されません。

どこが間違っていますか？やり方がわかりませんよろしくお願いします！

struct - CUDA: 構造体内の構造体の配列の割り当て

2 に答える 2

Related

Reference