如何将单个主机变量值正确复制到CUDA设备变量？遇未初始化问题

我来帮你梳理一下代码里的核心问题——你混淆了主机指针和设备指针的用法，导致数据根本没正确拷贝到设备端，自然会读到垃圾值。咱们一步步拆解错误并修正：

你的代码里的关键错误 #

• cudaMalloc使用错误：
  你写的cudaMalloc((void**) size, sizeof(size_t));完全不符合规范。cudaMalloc需要接收一个主机端指针变量的地址，用来存储分配好的设备内存地址。你直接传主机变量size的数值，相当于让cudaMalloc往一个非法地址写数据，这会导致内存分配失败或者崩溃。

• 内存拷贝/清零的目标地址错误：
  cudaMemset(&size, 0, sizeof(size_t));是给主机的size变量清零，和设备端内存毫无关系；后续的cudaMemcpy(&size, &global_size, sizeof(size_t), HostToDevice);也是把数据拷贝到主机变量的内存里，根本没传到设备上。设备端的变量必须用设备指针来指向，你现在完全没正确分配设备端的size内存。

• 核函数传参错误：
  设备核函数无法直接访问主机内存，你传给Show_Device_Variables的&size是主机变量的地址，核函数里读到的必然是垃圾值。必须传设备指针才能让核函数访问设备端的数据。

• 内存释放错误：
  cudaFree只能释放用cudaMalloc分配的设备内存地址，你写的cudaFree(&size);是释放主机变量的地址，属于非法操作，会导致内存错误。

修正后的完整代码示例 #

// 假设Host_Array已经在主机端正确分配并初始化
Pixel_GPU* Host_Array = ...;
size_t global_size = 1000000;

// 定义设备指针：主机端的变量，用来存储设备内存的地址
Pixel_GPU* Device_Array{}; 
size_t* d_size{}; // 这个指针将指向设备端的size内存

// 1. 正确分配设备内存
cudaError_t err;
err = cudaMalloc((void**)&Device_Array, global_size * sizeof(Pixel_GPU));
if (err != cudaSuccess) {
    std::cout << "cudaMalloc Device_Array failed: " << cudaGetErrorString(err) << std::endl;
    return -1;
}

err = cudaMalloc((void**)&d_size, sizeof(size_t));
if (err != cudaSuccess) {
    std::cout << "cudaMalloc d_size failed: " << cudaGetErrorString(err) << std::endl;
    return -1;
}

// 2. 正确拷贝数据到设备端
err = cudaMemcpy(Device_Array, Host_Array, global_size * sizeof(Pixel_GPU), cudaMemcpyHostToDevice);
if (err != cudaSuccess) {
    std::cout << "cudaMemcpy HostToDevice Device_Array failed: " << cudaGetErrorString(err) << std::endl;
    return -1;
}

err = cudaMemcpy(d_size, &global_size, sizeof(size_t), cudaMemcpyHostToDevice);
if (err != cudaSuccess) {
    std::cout << "cudaMemcpy HostToDevice d_size failed: " << cudaGetErrorString(err) << std::endl;
    return -1;
}

// 3. 调用核函数，传入设备指针d_size
Show_Device_Variables <<<2, 1>>>(d_size);

// 4. 同步设备并检查核函数错误（非常重要，调试必备）
err = cudaDeviceSynchronize();
if (err != cudaSuccess) {
    std::cout << "cudaDeviceSynchronize failed: " << cudaGetErrorString(err) << std::endl;
    return -1;
}

err = cudaGetLastError();
if (err != cudaSuccess) {
    std::cout << "Kernel execution error: " << cudaGetErrorString(err) << std::endl;
    return -1;
}

// 5. 正确释放内存
cudaFree(d_size);
cudaFree(Device_Array);
free(Host_Array);

额外调试建议 #

• 给你的核函数定义加上正确的参数类型：

  __global__ void Show_Device_Variables(size_t* size) {
      // 访问设备端的size值：*size
      printf("Device size: %zu\n", *size);
  }
  

• 养成每次调用CUDA API后检查错误的习惯，这样能快速定位问题，而不是到最后才发现读到垃圾值。

内容的提问来源于stack exchange，提问作者Damian Andrysiak