源代码应使用 nvcc 和 the -G option 进行编译，以便提供带有调试符号和行号表的非优化代码。也可以使用 -linetable 进行编译，以便使用符号进行调试；但是，这将优化 SASS，并导致不稳定的源步进和源断点行为。

步进时，除调试器焦点 Warp 外，所有 Warp 均被冻结。但是，当单步跳过 __syncthreads() 时，当前代码块中的所有 Warp 均可取得进展。这允许焦点 Warp 越过 __syncthreads() 函数。

步出全局函数将恢复应用程序（与按 F5 或选择菜单命令“调试”>“继续”的结果相同）。

单步跳过内核函数的最后一行也将恢复应用程序执行。

单步跳过内联函数的最后一行与步出内联函数的结果相同。

为了在调试时获得最佳步进行为，我们建议在您的代码中尽可能使用花括号。将花括号放在其自身的源代码行上。例如，由于编译器生成作用域信息的方式，以下编码风格会导致不同的步进行为。

以下代码片段导致低于最佳水平的步进行为

for () statement; 
for ()        statement; 
for () {        statement;
} 

以下代码片段导致最佳步进行为

for ()     
{
     statement;     
} 

通常，通过声明临时变量来分解计算会使代码更易于调试。变量在特定行集中“存活”的可能性增加。这意味着，当您单步执行代码时，变量的值将更容易识别。

1. 启动调试会话。

2. 使用 Nsight CUDA 调试位置工具栏选择要单步调试的线程。

   有关更多信息，请参阅指定调试器上下文。

3. 从“调试”菜单中，选择“步入”。

   或者，按键盘上的 F11 键。

4. 当前线程的程序计数器将前进一个源代码行。

要将目标应用程序运行到光标位置

1. 在包含源代码的“文档”窗口中，右键单击所需的源代码行。

2. 从上下文菜单中，选择运行到光标...

3. 程序计数器将前进到指定的源代码行。

从“调试”菜单中，选择停止调试。

或者，您也可以按调试器工具栏上的停止图标，或键入SHIFT+F5。

目标应用程序现在将停止。

源代码应使用 nvcc 和 the -G option 进行编译，以便提供带有调试符号和行号表的非优化代码。也可以使用 -linetable 进行编译，以便使用符号进行调试；但是，这将优化 SASS，并导致不稳定的源步进和源断点行为。

您可以使用 NVIDIA Nsight™ VSCE 在 CUDA 代码中设置源断点。源断点允许您在指定的 CUDA 源代码行处暂停应用程序。您还可以约束断点，使其仅在特定块和线程正在执行时中断。将断点约束到特定块和线程是在大规模并行环境中至关重要的能力，在这样的环境中，您可能同时运行数百或数千个线程。

您可以使用与其他 Visual Studio Code 支持的语言相同的熟悉对话框、键盘快捷键和工具窗口来设置和配置 CUDA 断点。

在具有数百或数千个线程的大规模并行环境中，能够将断点缩小到仅感兴趣的区域至关重要。CUDA 调试器支持为具有任意表达式的 GPU 线程设置条件断点。表达式可以使用程序变量、内部函数 blockIdx 和 threadIdx，以及一些简写宏，以便更轻松地基于 blockIdx 和 threadIdx 设置条件。

要在 CUDA C 断点上设置块或线程条件

1. 在源代码行上设置断点。

2. 右键单击断点。

3. 从下拉菜单中，选择 编辑条件...

4. 键入您希望调试器在此断点处评估的表达式。

NVIDIA Nsight™ VSCE 支持函数断点。要设置函数断点，请使用以下方法之一

• 从 运行和调试 选项卡的 断点 部分，选择 添加函数断点。

• 从 运行 菜单中，选择 新建断点 > 函数断点...

用户可以输入 CUDA 内核的函数。

CUDA 调试器具有在发生某些运行时活动时（例如内核启动或发生 API 错误时）暂停执行的选项。

CUDA 调试器可以在启动函数时自动插入内部断点。通过在启动配置中将 breakOnLaunch 属性设置为 true 来启用 启动时中断 功能。有关启动配置的更多信息，请参阅创建启动配置。

启用后，当任何 __global__ 内核启动时，执行将暂停。当设置函数断点很繁琐时，这很有用。如下所示，没有显示用户断点，但执行在内核入口点处暂停。

用于控制 CUDA API 错误发生时行为的设置通过启动配置中的 onAPIError 属性进行配置。有效值为

• hide 将不会报告任何类型的错误。

• ignore 将发出警告，但继续应用程序的执行。

• stop 将发出错误并停止应用程序。