La restrizione (amp) è più restrittiva del codice del kernel CUDA?

Question

In C++ AMP, le funzioni del kernel o lambdas sono contrassegnate con restrizioni (amp), che impone severe restrizioni sul sottoinsieme consentito di C++ (listed here). CUDA consente più libertà sul sottoinsieme di C o C++ nelle funzioni del kernel?

Answer 1

A partire da Visual Studio 11 e CUDA 4.1, le funzioni restrict(amp) sono più restrittive delle analoghe funzioni di CUDA. Il più notevolmente, AMP è più restrittivo su come i puntatori possono essere usati. Questa è una conseguenza naturale del substrato computazionale DirectX11 di AMP, che non consente l'uso di puntatori nel codice HLSL (shader grafico). Per contrasto, l'IR di livello inferiore di CUDA è PTX, che è più generico di HLSL.

Ecco una linea di confronto riga:

| VS 11 AMP restrict(amp) functions  | CUDA 4.1 sm_2x __device__ functions | 
|------------------------------------------------------------------------------| 
|* can only call functions that have |* can only call functions that have | 
| the restrict(amp) clause    | the __device__ decoration   | 
|* The function must be inlinable  |* need not be inlined     | 
|* The function can declare only  |* Class types are allowed    | 
| POD variables      |          | 
|* Lambda functions cannot    |* Lambdas are not supported, but  | 
| capture by reference and    | user functors can hold pointers  | 
| cannot capture pointers    |          | 
|* References and single-indirection |* References and multiple-indirection | 
| pointers are supported only as  | pointers are supported    | 
| local variables and function   |          | 
|* No recursion       |* Recursion OK      | 
|* No volatile variables    |* Volatile variables OK    | 
|* No virtual functions     |* Virtual functions OK    | 
|* No pointers to functions    |* Pointers to functions OK   | 
|* No pointers to member functions  |* Pointers to member functions OK  | 
|* No pointers in structures   |* Pointers in structures OK   | 
|* No pointers to pointers    |* Pointers to pointers OK    | 
|* No goto statements     |* goto statements OK     | 
|* No labeled statements    |* Labeled statements OK    | 
|* No try, catch, or throw statements |* No try, catch, or throw statements | 
|* No global variables     |* Global __device__ variables OK  | 
|* Static variables through tile_static |* Static variables through __shared__ | 
|* No dynamic_cast      |* No dynamic_cast      | 
|* No typeid operator     |* No typeid operator     | 
|* No asm declarations     |* asm declarations (inline PTX) OK | 
|* No varargs       |* No varargs       | 

Si può leggere di più su restrizioni l' restrict(amp)here. È possibile leggere il supporto C++ nelle funzioni CUDA __device__ nell'appendice D dello CUDA C Programming Guide.