Copiar uma estrutura contendo ponteiros para o dispositivo CUDA
Estou trabalhando em um projeto em que preciso do meu dispositivo CUDA para fazer cálculos em uma estrutura contendo ponteiro
typedef struct StructA {
int* arr;
} StructA;
Quando eu alocar memória para a estrutura e depois copiá-la para o dispositivo, ela copiará apenas a estrutura e não o conteúdo do ponteiro. No momento, estou resolvendo isso alocando o ponteiro primeiro e, em seguida, defina a estrutura do host para usar esse novo ponteiro (que reside na GPU). O exemplo de código a seguir descreve essa abordagem usando a estrutura acima:
#define N 10
int main() {
int h_arr[N] = {1,2,3,4,5,6,7,8,9,10};
StructA *h_a = (StructA*)malloc(sizeof(StructA));
StructA *d_a;
int *d_arr;
// 1. Allocate device struct.
cudaMalloc((void**) &d_a, sizeof(StructA));
// 2. Allocate device pointer.
cudaMalloc((void**) &(d_arr), sizeof(int)*N);
// 3. Copy pointer content from host to device.
cudaMemcpy(d_arr, h_arr, sizeof(int)*N, cudaMemcpyHostToDevice);
// 4. Point to device pointer in host struct.
h_a->arr = d_arr;
// 5. Copy struct from host to device.
cudaMemcpy(d_a, h_a, sizeof(StructA), cudaMemcpyHostToDevice);
// 6. Call kernel.
kernel<<<N,1>>>(d_a);
// 7. Copy struct from device to host.
cudaMemcpy(h_a, d_a, sizeof(StructA), cudaMemcpyDeviceToHost);
// 8. Copy pointer from device to host.
cudaMemcpy(h_arr, d_arr, sizeof(int)*N, cudaMemcpyDeviceToHost);
// 9. Point to host pointer in host struct.
h_a->arr = h_arr;
}
Minha pergunta é: É assim que se faz?
Parece muito trabalho e lembro que essa é uma estrutura muito simples. Se minha estrutura contiver muitos ponteiros ou estruturas com ponteiros, o código para alocação e cópia será bastante extenso e confus