显示驱动停止响应并恢复

CUDA C 程序运行的时候， by default, 由于Windows 系统假设我们的显卡（GPU） 的用途是用于图形处理的（graphics processing）。 在图形处理这种applications 中， GPU的计算的速度是十分快的。  从CPU请求GPU处理 到GPU处理完成并返回结果可能只是需要花费几个nano seconds 即可。   所以这种情况下面， 我们并需要修改注册表（registry）。 但是gpu 的driver 每2秒（默认时间）在检测到我们的GPU是hanging的时候， 驱动程序会进行复位（reset）。 也就是说， 如果我们的GPU在执行某个任务花费超过了2s， 就会出现问题。  2秒对于处理graphics 是很好的。 但是当我们使用CUDA进行一般的computation 的时候， 却很容易超过2秒。 所以我们就需要修改注册表（regestry）。

         (1)什么是注册表

即把所有的计算机硬件、软件信息集中在一个称为“注册表”数据文件中，通过它来对计算机的硬软件系统进行有效的管理。打开它的方法：可以在“运行”中通过命令来打开它。命令为：regedit

     （2）在修改注册表之前最好进行备份(back up)， 以免在出现错误的时候，便于 restore（直接双击导入的文件就可导入到注册表）。 须知， registry is a dangerous place,  轻易不要改动。 改动的时候， 为了保险， 一定要备份。 下面我们将注册表备份到桌面上。

2.1 开始-----》 运行 ----》 regedit 打开注册表编辑器

2,2  文件 ----》 导出 ------》 桌面（这里我们保存到桌面） ----》 命名： myReg -----> 保存

（3）修改显卡驱动注册子项值

目录： HKEY_LOCAL_MACHINE\SYSTEM\ControlSet002\Control\GraphicsDrivers

在这里我们将添加两个Dword 的 value 到这个subkey。

注意：

3,1 TdrLevel: timeout detection and recovery level.

      0: off， donnot detect timeout

     3: timed, this is default,  it will use the value of TdrDelay(默认值为2秒)

 
在编辑菜单上单击新建TdrLevel, TdrDalay：设定值如下

TdrLevel: 0

TdrDelay: 20（表明设定默认值为20秒）

关闭即可保存。 接下来， 我们就可以使用GPU处理超过2秒才能完成的任务而不会出现显示驱动停止响应并恢复等错误了。

例如， 下面的程序就可以运行（时间会超过两秒了）了。

#include <iostream>#include <cuda.h>using namespace std;__global__ void AddInts(int* a, int* b) {// this could be any operation that takes more than 2 seconds// Here I've rather pointlessly asked a single cuda thread to add b to a 10, 000, 005 timesfor (int i = 0; i < 10000005; i++) {a[0] += b[0];}}int main() {int h_a = 0; h_b = 1; // two integer variablesint* d_a;int* d_b;// allocate space for copies of the integers on the GPUif(cudaMalloc((void**)&d_a, sizeof(int)) != cudaSuccess) {    cout << "Error allocating memory" << endl;return 0;}if(cudaMalloc((void**)&h_b, sizeof(int)) != cudaSuccess) {    cout << "Error allocating memory" << endl;cudaFree(d_a);return 0;}// copy the integer's values from the CPU to GPUif(codaMemcpy(d_a, &h_a, sizeof(int), cudaMemcpyHostToDevice) != cudaSuccess) {cout << "Error copying memory" << endl;cudaFree(d_a);cudaFree(d_b);return 0;}if(codaMemcpy(d_b, &h_b, sizeof(int), cudaMemcpyHostToDevice) != cudaSuccess) {cout << "Error copying memory" << endl;cudaFree(d_a);cudaFree(d_b);return 0;}AddInts<<<1, 1>>>(d_a, d_bh);if(codaMemcpy(&h_a, d_b, sizeof(int), cudaMemcpyDeviceToHost) != cudaSuccess) {cout << "Error copying memory" << endl;cudaFree(d_a);cudaFree(d_b);return 0;}cout << "Adding 1 to 10, 000, 005 times is " << h_a << endl;cudaFree(d_a);cudaFree(d_b);cudaDeviceReset();return 0;}