Cómo copiar la memoria asignada en la función del dispositivo a la memoria principal
Tengo un programa CUDA que contiene una función de host y una función de dispositivoEjecutar(). En la función de host, asigno una memoria globalsalida que luego pasará a la función del dispositivo y se usará para almacenar la dirección de la memoria global asignada dentro de la función del dispositivo. Quiero acceder a la memoria asignada en el kernel en la función de host. El siguiente es el código:
#include <stdio.h>
typedef struct
{
int * p;
int num;
} Structure_A;
__global__ void Execute(Structure_A *output);
int main(){
Structure_A *output;
cudaMalloc((void***)&output,sizeof(Structure_A)*1);
dim3 dimBlockExecute(1,1);
dim3 dimGridExecute(1,1);
Execute<<<dimGridExecute,dimBlockExecute>>>(output);
Structure_A * output_cpu;
int * p_cpu;
cudaError_t err;
output_cpu= (Structure_A*)malloc(sizeof(Structure_A));
err=cudaMemcpy(output_cpu,output,sizeof(Structure_A),cudaMemcpyDeviceToHost);
if( err != cudaSuccess)
{
printf("CUDA error a: %s\n", cudaGetErrorString(err));
exit(-1);
}
p_cpu=(int *)malloc(sizeof(int));
err=cudaMemcpy(p_cpu,output_cpu[0].p,sizeof(int),cudaMemcpyDeviceToHost);
if( err != cudaSuccess)
{
printf("CUDA error b: %s\n", cudaGetErrorString(err));
exit(-1);
}
printf("output=(%d,%d)\n",output_cpu[0].num,p_cpu[0]);
return 0;
}
__global__ void Execute(Structure_A *output){
int thid=threadIdx.x;
output[thid].p= (int*)malloc(thid+1);
output[thid].num=(thid+1);
output[thid].p[0]=5;
}
Puedo compilar el programa. Pero cuando lo ejecuto, recibí un error que muestra que hay un argumento no válido en la siguiente función de copia de memoria:
err=cudaMemcpy(p_cpu,output_cpu[0].p,sizeof(int),cudaMemcpyDeviceToHost);
La versión de CUDA es 4.2. Tarjeta CUDA: Tesla C2075 OS: x86_64 GNU / Linux
Editar: modificó el código y asignó el tamaño adecuado de memoria para output_cpu y p_cpu.