[解決済み] OSXでNVIDIA Cudaエラー「すべてのCUDA対応デバイスはビジー状態か使用不可」発生

質問

cudaMallocのような単純な呼び出しでも、CUDAライブラリが完全に失敗してエラー46（"すべてのCUDA対応デバイスはビジーまたは使用できません"）で返されることがよくあります。コンピュータを再起動するとコードは正常に実行されますが、これは理想的な状態とは程遠いものです。この問題はどうやら なかなか 共通 .

私の設定は以下の通りです。

• OSX 10.6.8
• NVIDIA CUDA ドライバー : CUDA ドライバーバージョン。4.0.31 (最新)
• GPUドライババージョン：1.6.36.10 (256.00.35f11)

Nvidiaのフォーラムにある解決策をいろいろ試しましたが、うまくいきませんでした。起こるたびに再起動するのは嫌です。正しいと思われる手順でドライバのアンロードとリロードも試しました（違うかもしれません）。

kextunload -b com.nvidia.CUDA
kextload -b com.nvidia.CUDA

しかし、それでもうまくいきません。どうすればGPU（またはCUDA）を正気に戻せますか？

これはデバイスのクエリ結果です

 CUDA Device Query (Runtime API) version (CUDART static linking)

Found 1 CUDA Capable device(s)

Device 0: "GeForce 9400M"
  CUDA Driver Version / Runtime Version          4.0 / 4.0
  CUDA Capability Major/Minor version number:    1.1
  Total amount of global memory:                 254 MBytes (265945088 bytes)
  ( 2) Multiprocessors x ( 8) CUDA Cores/MP:     16 CUDA Cores
  GPU Clock Speed:                               1.10 GHz
  Memory Clock rate:                             1075.00 Mhz
  Memory Bus Width:                              128-bit
  Max Texture Dimension Size (x,y,z)             1D=(8192), 2D=(65536,32768), 3D=(2048,2048,2048)
  Max Layered Texture Size (dim) x layers        1D=(8192) x 512, 2D=(8192,8192) x 512
  Total amount of constant memory:               65536 bytes
  Total amount of shared memory per block:       16384 bytes
  Total number of registers available per block: 8192
  Warp size:                                     32
  Maximum number of threads per block:           512
  Maximum sizes of each dimension of a block:    512 x 512 x 64
  Maximum sizes of each dimension of a grid:     65535 x 65535 x 1
  Maximum memory pitch:                          2147483647 bytes
  Texture alignment:                             256 bytes
  Concurrent copy and execution:                 No with 0 copy engine(s)
  Run time limit on kernels:                     Yes
  Integrated GPU sharing Host Memory:            Yes
  Support host page-locked memory mapping:       Yes
  Concurrent kernel execution:                   No
  Alignment requirement for Surfaces:            Yes
  Device has ECC support enabled:                No
  Device is using TCC driver mode:               No
  Device supports Unified Addressing (UVA):      No
  Device PCI Bus ID / PCI location ID:           2 / 0
  Compute Mode:
     < Default (multiple host threads can use ::cudaSetDevice() with device simultaneously) >

deviceQuery, CUDA Driver = CUDART, CUDA Driver Version = 4.0, CUDA Runtime Version = 4.0, NumDevs = 1, Device = GeForce 9400M
[deviceQuery] test results...
PASSED

これは、失敗する可能性のあるコードの例です（ただし、通常の状態では失敗しません）。

#include <stdio.h>

__global__ void add(int a, int b, int *c) {
    *c = a + b;
}

int main(void) {
    int c;
    int *dev_c;

    cudaMalloc( (void **) &dev_c, sizeof(int)); // fails here, returning 46

    add<<<1,1>>>(2,7,dev_c);
    cudaMemcpy(&c, dev_c, sizeof(int), cudaMemcpyDeviceToHost);
    printf("hello world, %d\n",c);
    cudaFree( dev_c);
    return 0;
}

あと、たまに再起動しなくてもまともな動作に戻ることがあることがわかった。何が引き金になるのかはまだ分かりませんが。

解決方法は？

私の投稿にコメントされた方々の発言を確認します。他のアプリケーションがGPUを制御している場合、GPUが動作しないことがあります。私の場合、firefoxのフラッシュプレーヤーがカードの利用可能なリソースをすべて占有していたようです。私はフラッシュ用のfirefoxプラグインを停止させ、カードはすぐに再び動作し始めました。