title: Dynamic Parallelism on GTX 980 ti: Unknown Error
body: <p>I am attempting dynamic parallelism on a GTX 980 ti card.
  All attempts at running code return "unknown error".
  Simple code is shown below with compilation options.</p>
  
  <p>I can execute kernels at <code>depth=0</code> with no issues.
  The first time a child is called, the error is given.
  The <code>cudaDeviceSynchronize()</code> were included after looking at other questions here, but didn't solve problem.</p>
  
  <p>Any ideas? Could this be a drivers issue?</p>
  
  <p>Edit 1:</p>
  
  <p>OS: Linux-x86_64</p>
  
  <p>Nvidia driver version: 384.59</p>
  
  <p>nvcc version 7.5.17</p>
  
  <p>There are two 980 ti's connected with PCIe x16 Gen3. The system also has windows installed on another RAID configured SSD.</p>
  
  <pre><code>#include &lt;cuda.h&gt;
  #include &lt;fstream&gt;
  #include &lt;stdio.h&gt;
  #include &lt;stdlib.h&gt;
  
  __global__ void ker_two(){
  int two=0;
  two++;
  }
  
  __global__ void ker_one(){
  int one=0;
  one++;
  ker_two&lt;&lt;&lt;1,1&gt;&gt;&gt;();
  cudaDeviceSynchronize();
  };
  
  int main( ){
  
  ker_one&lt;&lt;&lt;1,1&gt;&gt;&gt;();
  cudaDeviceSynchronize();
  
  cudaError_t err = cudaGetLastError();
  if (err != cudaSuccess) 
      printf("Cuda Error: %s\n", cudaGetErrorString(err));//*/
  
  return 0;
  }
  </code></pre>
  
  <p>compiled with </p>
  
  <pre><code>nvcc -arch=compute_52 -rdc=true -lcudadevrt test.cu
  </code></pre>