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 C Programming Guideの付録DのCUDA __device__の関数でC++のサポートについて読むことができます。