cudaFreeHost cura quale dispositivo è attivo quando cudaMallocHost viene utilizzato per allocare memoria?

Question

Sto usando Cuda SDK 4.0 e sto riscontrando un problema che mi ha richiesto 2 giorni per crearmi nel seguente codice.

#include <cuda.h> 
#include <cuda_runtime.h> 
void main (int argc, char ** argv) { 

    int* test; 
    cudaError_t err; 

    err = cudaSetDevice( 1 ); err = cudaMallocHost(&test, 1024*sizeof(int));  
    err = cudaSetDevice( 0 ); err = cudaFreeHost(test);  
} 

Questo genera il seguente errore nel richiamo cudaFreeHost:

First-chance exception at 0x000007fefd96aa7d in Test.exe: Microsoft C++ exception: cudaError_enum at memory location 0x0022f958.. 

Il valore ERR è cudaErrorInvalidValue

Lo stesso errore si verifica tale variazione:

err = cudaSetDevice( 0 ); err = cudaMallocHost(&test, 1024*sizeof(int));  
err = cudaSetDevice( 1 ); err = cudaFreeHost(test); 

Le seguenti variazioni non lanciare l'errore:

err = cudaSetDevice( 0 ); err = cudaMallocHost(&test, 1024*sizeof(int));  
err = cudaSetDevice( 0 ); err = cudaFreeHost(test); 

e

err = cudaSetDevice( 1 ); err = cudaMallocHost(&test, 1024*sizeof(int));  
err = cudaSetDevice( 1 ); err = cudaFreeHost(test); 

Ho avuto l'impressione che solo bisogno di chiamare cudaSetDevice se si vuole allocare memoria su una GPU specifica. Nell'esempio sopra, sto solo assegnando la memoria bloccata alla CPU.

Si tratta di un errore o ho perso qualcosa nel manuale?

Answer 1

Ho trovato il problema. cudaHostAlloc e cudaMallocHost NON SONO GLI STESSI.

Per tutti coloro che incontra questo problema la soluzione è quella di utilizzare

cudaHostAlloc(&test, 1024*sizeof(int),cudaHostAllocPortable); 

invece di

cudaMallocHost(&test, 1024*sizeof(int));