揭开 NVIDIA Compute Sanitizer 神秘面纱：一劳永逸调服 CUDA 故障！

2023-06-11 08:22:42

CUDA调试利器：NVIDIA Compute Sanitizer

简介

在CUDA编程中，调试代码是一项艰巨的任务。幸运的是，NVIDIA推出了一个强大的工具，名为Compute Sanitizer，可以帮助开发者轻松识别和解决代码中的问题。Compute Sanitizer是一个静态分析器，用于检测常见的CUDA编程错误，例如内存访问违规、竞争条件和未初始化变量。

如何使用Compute Sanitizer

使用Compute Sanitizer非常简单。在编译CUDA代码时，只需添加-fsanitize=cuda标志即可。例如：

nvcc -fsanitize=cuda my_code.cu

Compute Sanitizer的优势

使用Compute Sanitizer有许多优势，包括：

准确的错误检测： Compute Sanitizer可以准确地检测常见的CUDA编程错误，例如内存访问违规、竞争条件和未初始化变量。
非侵入式： Compute Sanitizer是非侵入式的，这意味着它不会修改代码的执行行为。
性能开销低： Compute Sanitizer的性能开销很低，通常不会影响代码的执行速度。
易于使用： Compute Sanitizer易于使用，只需在编译时添加一个标志即可。

示例

以下是一个使用Compute Sanitizer检测内存访问违规的示例：

#include <stdio.h>

__global__ void kernel() {
  int* ptr;
  *ptr = 0; // 访问未分配的内存
}

int main() {
  kernel<<<1, 1>>>();
  cudaDeviceSynchronize();
  return 0;
}

在编译此代码时，添加-fsanitize=cuda标志将导致Compute Sanitizer发出以下错误消息：

==21043==ERROR: AddressSanitizer: global-bounds-out-of-bounds on address 0x6020000072e0 at pc 0x602000000012 bp 0x7fffffffd960 sp 0x7fffffffd950
==21043==The memory access at address 0x6020000072e0 is out of bounds.
    #0 0x602000000011 in kernel /tmp/code.cu:11:6
    #1 0x602000000070 in cuda_kernel /usr/local/cuda/samples/common/inc/helper_cuda.h:72:16
    #2 0x602000000160 in main /tmp/code.cu:17:13

0x6020000072e0 is located 0 bytes to the right of 2-byte region [0x6020000072de,0x6020000072e0)
==21043==ABORTING