WSL2中无法获取CUDA核函数printf输出的求助

在WSL2的Ubuntu 20.04环境中，编写了CUDA代码与CMake配置，编译运行后核函数内的printf输出未显示，已调用cudaDeviceSynchronize()但问题仍存在。以下是详细的代码、配置、运行结果及环境信息：

问题代码与配置 #

CUDA代码（main.cu） #

#include <cstdio>
#include <cuda_runtime.h>

__global__ void kernel() {
    printf("Hello, world!\n");
}

int main() {
    kernel<<<1, 1>>>();
    
    {
    cudaError_t cudaerr = cudaDeviceSynchronize();
    if (cudaerr != cudaSuccess)
        printf("kernel launch failed with error \"%s\".\n",
               cudaGetErrorString(cudaerr));
    else
        printf("cudaerr == cudaSuccess\n");
    }

    return 0;
}

CMakeLists.txt #

cmake_minimum_required(VERSION 3.10)

set(CMAKE_CXX_STANDARD 17)
set(CMAKE_BUILD_TYPE Release)

project(hellocuda LANGUAGES CXX CUDA)

add_executable(main main.cu)

编译运行结果 #

-- Generating done (0.0s)
-- Build files have been written to: /home/me/project/cuda_hello/build
[ 50%] Building CUDA object CMakeFiles/main.dir/main.cu.o
[100%] Linking CUDA executable main
[100%] Built target main
cudaerr == cudaSuccess

环境版本信息 #

• nvcc版本：

nvcc: NVIDIA (R) Cuda compiler driver
Copyright (c) 2005-2023 NVIDIA Corporation
Built on Tue_Aug_15_22:02:13_PDT_2023
Cuda compilation tools, release 12.2, V12.2.140
Build cuda_12.2.r12.2/compiler.33191640_0

• nvcc路径：/usr/local/cuda/bin/nvcc
• WSL版本：

NAME      STATE           VERSION
* ubuntu    Running         2

解决方法 #

• 验证WSL2 GPU直通功能：运行nvidia-smi确认WSL2能识别GPU设备。如果命令无输出或报错，需检查Windows主机的NVIDIA驱动是否安装正确，确保WSL2的GPU直通已启用（需Windows 10 2004及以上版本，且驱动支持WSL2 CUDA）。
• 调整编译模式或选项：
  • 将CMAKE_BUILD_TYPE从Release改为Debug，Debug模式默认保留核函数的printf输出，避免优化导致输出被丢弃；
  • 若需保留Release模式，在CMakeLists.txt中添加CUDA编译选项禁用相关优化：

    target_compile_options(main PRIVATE $<$<COMPILE_LANGUAGE:CUDA>:-G>)
    

• 添加核函数启动错误检查：在核函数启动后立即检查启动错误，避免同步时无法捕获的启动问题：

  int main() {
      kernel<<<1, 1>>>();
      // 检查核函数启动错误
      cudaError_t launch_err = cudaGetLastError();
      if (launch_err != cudaSuccess) {
          printf("Kernel launch error: %s\n", cudaGetErrorString(launch_err));
          return 1;
      }
      
      cudaError_t cudaerr = cudaDeviceSynchronize();
      if (cudaerr != cudaSuccess)
          printf("kernel launch failed with error \"%s\".\n",
                 cudaGetErrorString(cudaerr));
      else
          printf("cudaerr == cudaSuccess\n");
      
      // 强制刷新输出缓冲区
      fflush(stdout);
      return 0;
  }
  

• 指定CUDA架构版本：在CMakeLists.txt中添加目标GPU的compute capability，确保编译生成兼容的代码：

  set_target_properties(main PROPERTIES CUDA_ARCHITECTURES "75;80;86")
  

  （需根据你的GPU型号调整，如RTX 20系为75，RTX 30/40系为86，NVIDIA A100为80）
• 刷新主机端输出缓冲区：在cudaDeviceSynchronize()后调用fflush(stdout);，确保核函数的输出被立即打印到终端。

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