CUDA 커널 코드보다 restrict (amp)가 더 제한적입니까?

Question

C++ AMP에서 커널 함수 또는 람다는 restrict (amp)로 표시되며 C++의 허용 된 하위 집합 (listed here)에 심각한 제한을 적용합니다. CUDA는 커널 기능에서 C 또는 C++의 하위 집합에 대해 더 많은 자유를 허용합니까?

Answer 1

Visual Studio 11 및 CUDA 4.1에서 restrict(amp) 기능은 CUDA의 유사 __device__ 기능보다 더 제한적입니다. 가장 두드러지게 AMP는 포인터를 사용하는 방법에 대해 더 제한적입니다. 이는 HLSL (그래픽 쉐이더) 코드의 포인터를 허용하지 않는 AMP의 DirectX11 계산 기판의 당연한 결과입니다. 대조적으로, CUDA의 하위 레벨 IR은 PTX이며 HLSL보다 일반적인 목적입니다.

이

| 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       | 

당신은 restrict(amp)의 제한 here에 대한 자세한 내용을보실 수 있습니다 :

여기에 라인 비교하여 라인입니다. CUDA __device__ 함수의 C++ 지원은 부록 D의 CUDA C Programming Guide에서 읽을 수 있습니다.