Giới hạn (amp) có hạn chế hơn mã hạt nhân CUDA không?

Question

Trong C++ AMP, các hàm hạt nhân hoặc lambdas được đánh dấu bằng giới hạn (amp), áp đặt các hạn chế nghiêm trọng đối với tập hợp con được phép của C++ (listed here). CUDA có cho phép tự do hơn trên tập hợp con của C hoặc C++ trong các hàm hạt nhân không?

Answer 1

Do các chức năng Visual Studio 11 và CUDA 4.1, restrict(amp) có nhiều hạn chế hơn các hàm tương tự của CUDA __device__. Đáng chú ý nhất, AMP là hạn chế hơn về cách con trỏ có thể được sử dụng. Đây là hậu quả tự nhiên của chất nền tính toán DirectX11 của AMP, không cho phép con trỏ trong mã số HLSL (trình đổ bóng đồ họa). Theo constrast, IR mức thấp của CUDA là PTX, mục đích chung hơn HLSL.

Dưới đây là một dòng bằng cách so sánh dòng:

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

Bạn có thể đọc thêm về giới hạn restrict(amp) 's here. Bạn có thể đọc về hỗ trợ C++ trong các hàm CUDA __device__ trong Phụ lục D của CUDA C Programming Guide.