cudamemcpy - cudamalloc example

Error desconocido de Cuda(ErrNo: 30) en cudaMalloc()

Question

He buscado el motivo pero no tuve suerte. No funciona en un programa tan simple:

#include <iostream>
using namespace std;
int main() {
int* n;
cout << cudaMallocManaged(&n, 4 * sizeof(int)) << endl;
return 0;
}

El código de retorno es 30, error desconocido. cudaMalloc también falla con el mismo código.

Este es mi hardware:

$ lspci | grep NV
01:00.0 3D controller: NVIDIA Corporation GF117M [GeForce 610M/710M/820M / GT 620M/625M/630M/720M] (rev a1)
$ nvidia-smi
Sat Mar 7 14:02:04 2015
+------------------------------------------------------+
| NVIDIA-SMI 331.113 Driver Version: 331.113 |
|-------------------------------+----------------------+----------------------+
| GPU Name Persistence-M| Bus-Id Disp.A | Volatile Uncorr. ECC |
| Fan Temp Perf Pwr:Usage/Cap| Memory-Usage | GPU-Util Compute M. |
|===============================+======================+======================|
| 0 NVS 5200M Off | 0000:01:00.0 N/A | N/A |
| N/A 53C N/A N/A / N/A | 279MiB / 1023MiB | N/A Default |
+-------------------------------+----------------------+----------------------+
+-----------------------------------------------------------------------------+
| Compute processes: GPU Memory |
| GPU PID Process name Usage |
|=============================================================================|
| 0 Not Supported |
+-----------------------------------------------------------------------------+

Estoy usando Ubuntu 14.10, con CUDA 6.0 del repositorio oficial (con suerte, si Ubuntu no lo estropea).

Es un labtop Lenovo T430s, la tarjeta está en Optimus por lo que podría causar algún problema. He probado en otra máquina y funciona el mismo código.

Actualización 1

OK, nvidia_uvm no está cargado ...

$ lsmod |grep nv
nvidia 10744914 65
nvram 14362 1 thinkpad_acpi
drm 310919 6 i915,drm_kms_helper,nvidia
$ sudo modprobe nvidia_uvm
modprobe: ERROR: ../libkmod/libkmod-module.c:816 kmod_module_insert_module() could not find module by name=''nvidia_331_updates_uvm''
modprobe: ERROR: could not insert ''nvidia_331_updates_uvm'': Function not implemented

Actualización 2

OK, reinstalé nvidia-331-updates-uvm y el módulo se cargó.

$ lsmod | grep nv
nvidia_uvm 34855 0
nvidia 10744914 66 nvidia_uvm
nvram 14362 1 thinkpad_acpi
drm 310919 6 i915,drm_kms_helper,nvidia

Sin embargo, el código aún devuelve el error 30.

Actualización 3

Después de algunas pruebas más (principalmente intenté ejecutar como root), ahora recibo el error 71: operación no admitida. Sin embargo, si solo estoy usando cudaMalloc , tuvo éxito. También verificaré si mi dispositivo es compatible con el direccionamiento de memoria unificada.

Actualización 4

De acuerdo, mi tarjeta solo es compatible con SM 2.1, por lo que no es compatible con la memoria unificada.

Answer 1

Se requiere el módulo de núcleo de nvidia_uvm AFAIK para que funcione CUDA.

Necesitará instalar el paquete con ese módulo kernel, por ejemplo, nvidia-331-uvm y habilitar su carga automática instalando el paquete nvidia-modprobe :

sudo apt-get install nvidia-modprobe nvidia-331-uvm

Si no desea reiniciar después de instalar nvidia-modprobe , puede intentar ejecutar su programa como root (por ejemplo, sudo ./a.out ) - el módulo debe cargarse durante la ejecución como root.