Subversion Repositories Kolibri OS

Rev

Go to most recent revision | Blame | Last modification | View Log | RSS feed

  1. /*******************************************************************************
  2.  * Copyright (c) 2008-2010 The Khronos Group Inc.
  3.  *
  4.  * Permission is hereby granted, free of charge, to any person obtaining a
  5.  * copy of this software and/or associated documentation files (the
  6.  * "Materials"), to deal in the Materials without restriction, including
  7.  * without limitation the rights to use, copy, modify, merge, publish,
  8.  * distribute, sublicense, and/or sell copies of the Materials, and to
  9.  * permit persons to whom the Materials are furnished to do so, subject to
  10.  * the following conditions:
  11.  *
  12.  * The above copyright notice and this permission notice shall be included
  13.  * in all copies or substantial portions of the Materials.
  14.  *
  15.  * THE MATERIALS ARE PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND,
  16.  * EXPRESS OR IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF
  17.  * MERCHANTABILITY, FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT.
  18.  * IN NO EVENT SHALL THE AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY
  19.  * CLAIM, DAMAGES OR OTHER LIABILITY, WHETHER IN AN ACTION OF CONTRACT,
  20.  * TORT OR OTHERWISE, ARISING FROM, OUT OF OR IN CONNECTION WITH THE
  21.  * MATERIALS OR THE USE OR OTHER DEALINGS IN THE MATERIALS.
  22.  ******************************************************************************/
  23.  
  24. /* $Revision: 11985 $ on $Date: 2010-07-15 11:16:06 -0700 (Thu, 15 Jul 2010) $ */
  25.  
  26. #ifndef __OPENCL_CL_H
  27. #define __OPENCL_CL_H
  28.  
  29. #ifdef __APPLE__
  30. #include <OpenCL/cl_platform.h>
  31. #else
  32. #include <CL/cl_platform.h>
  33. #endif 
  34.  
  35. #ifdef __cplusplus
  36. extern "C" {
  37. #endif
  38.  
  39. /******************************************************************************/
  40.  
  41. typedef struct _cl_platform_id *    cl_platform_id;
  42. typedef struct _cl_device_id *      cl_device_id;
  43. typedef struct _cl_context *        cl_context;
  44. typedef struct _cl_command_queue *  cl_command_queue;
  45. typedef struct _cl_mem *            cl_mem;
  46. typedef struct _cl_program *        cl_program;
  47. typedef struct _cl_kernel *         cl_kernel;
  48. typedef struct _cl_event *          cl_event;
  49. typedef struct _cl_sampler *        cl_sampler;
  50.  
  51. typedef cl_uint             cl_bool;                     /* WARNING!  Unlike cl_ types in cl_platform.h, cl_bool is not guaranteed to be the same size as the bool in kernels. */
  52. typedef cl_ulong            cl_bitfield;
  53. typedef cl_bitfield         cl_device_type;
  54. typedef cl_uint             cl_platform_info;
  55. typedef cl_uint             cl_device_info;
  56. typedef cl_bitfield         cl_device_fp_config;
  57. typedef cl_uint             cl_device_mem_cache_type;
  58. typedef cl_uint             cl_device_local_mem_type;
  59. typedef cl_bitfield         cl_device_exec_capabilities;
  60. typedef cl_bitfield         cl_command_queue_properties;
  61.  
  62. typedef intptr_t                        cl_context_properties;
  63. typedef cl_uint             cl_context_info;
  64. typedef cl_uint             cl_command_queue_info;
  65. typedef cl_uint             cl_channel_order;
  66. typedef cl_uint             cl_channel_type;
  67. typedef cl_bitfield         cl_mem_flags;
  68. typedef cl_uint             cl_mem_object_type;
  69. typedef cl_uint             cl_mem_info;
  70. typedef cl_uint             cl_image_info;
  71. typedef cl_uint             cl_buffer_create_type;
  72. typedef cl_uint             cl_addressing_mode;
  73. typedef cl_uint             cl_filter_mode;
  74. typedef cl_uint             cl_sampler_info;
  75. typedef cl_bitfield         cl_map_flags;
  76. typedef cl_uint             cl_program_info;
  77. typedef cl_uint             cl_program_build_info;
  78. typedef cl_int              cl_build_status;
  79. typedef cl_uint             cl_kernel_info;
  80. typedef cl_uint             cl_kernel_work_group_info;
  81. typedef cl_uint             cl_event_info;
  82. typedef cl_uint             cl_command_type;
  83. typedef cl_uint             cl_profiling_info;
  84.  
  85. typedef struct _cl_image_format {
  86.     cl_channel_order        image_channel_order;
  87.     cl_channel_type         image_channel_data_type;
  88. } cl_image_format;
  89.  
  90.  
  91. typedef struct _cl_buffer_region {
  92.     size_t                  origin;
  93.     size_t                  size;
  94. } cl_buffer_region;
  95.  
  96. /******************************************************************************/
  97.  
  98. /* Error Codes */
  99. #define CL_SUCCESS                                  0
  100. #define CL_DEVICE_NOT_FOUND                         -1
  101. #define CL_DEVICE_NOT_AVAILABLE                     -2
  102. #define CL_COMPILER_NOT_AVAILABLE                   -3
  103. #define CL_MEM_OBJECT_ALLOCATION_FAILURE            -4
  104. #define CL_OUT_OF_RESOURCES                         -5
  105. #define CL_OUT_OF_HOST_MEMORY                       -6
  106. #define CL_PROFILING_INFO_NOT_AVAILABLE             -7
  107. #define CL_MEM_COPY_OVERLAP                         -8
  108. #define CL_IMAGE_FORMAT_MISMATCH                    -9
  109. #define CL_IMAGE_FORMAT_NOT_SUPPORTED               -10
  110. #define CL_BUILD_PROGRAM_FAILURE                    -11
  111. #define CL_MAP_FAILURE                              -12
  112. #define CL_MISALIGNED_SUB_BUFFER_OFFSET             -13
  113. #define CL_EXEC_STATUS_ERROR_FOR_EVENTS_IN_WAIT_LIST -14
  114.  
  115. #define CL_INVALID_VALUE                            -30
  116. #define CL_INVALID_DEVICE_TYPE                      -31
  117. #define CL_INVALID_PLATFORM                         -32
  118. #define CL_INVALID_DEVICE                           -33
  119. #define CL_INVALID_CONTEXT                          -34
  120. #define CL_INVALID_QUEUE_PROPERTIES                 -35
  121. #define CL_INVALID_COMMAND_QUEUE                    -36
  122. #define CL_INVALID_HOST_PTR                         -37
  123. #define CL_INVALID_MEM_OBJECT                       -38
  124. #define CL_INVALID_IMAGE_FORMAT_DESCRIPTOR          -39
  125. #define CL_INVALID_IMAGE_SIZE                       -40
  126. #define CL_INVALID_SAMPLER                          -41
  127. #define CL_INVALID_BINARY                           -42
  128. #define CL_INVALID_BUILD_OPTIONS                    -43
  129. #define CL_INVALID_PROGRAM                          -44
  130. #define CL_INVALID_PROGRAM_EXECUTABLE               -45
  131. #define CL_INVALID_KERNEL_NAME                      -46
  132. #define CL_INVALID_KERNEL_DEFINITION                -47
  133. #define CL_INVALID_KERNEL                           -48
  134. #define CL_INVALID_ARG_INDEX                        -49
  135. #define CL_INVALID_ARG_VALUE                        -50
  136. #define CL_INVALID_ARG_SIZE                         -51
  137. #define CL_INVALID_KERNEL_ARGS                      -52
  138. #define CL_INVALID_WORK_DIMENSION                   -53
  139. #define CL_INVALID_WORK_GROUP_SIZE                  -54
  140. #define CL_INVALID_WORK_ITEM_SIZE                   -55
  141. #define CL_INVALID_GLOBAL_OFFSET                    -56
  142. #define CL_INVALID_EVENT_WAIT_LIST                  -57
  143. #define CL_INVALID_EVENT                            -58
  144. #define CL_INVALID_OPERATION                        -59
  145. #define CL_INVALID_GL_OBJECT                        -60
  146. #define CL_INVALID_BUFFER_SIZE                      -61
  147. #define CL_INVALID_MIP_LEVEL                        -62
  148. #define CL_INVALID_GLOBAL_WORK_SIZE                 -63
  149. #define CL_INVALID_PROPERTY                         -64
  150.  
  151. /* OpenCL Version */
  152. #define CL_VERSION_1_0                              1
  153. #define CL_VERSION_1_1                              1
  154.  
  155. /* cl_bool */
  156. #define CL_FALSE                                    0
  157. #define CL_TRUE                                     1
  158.  
  159. /* cl_platform_info */
  160. #define CL_PLATFORM_PROFILE                         0x0900
  161. #define CL_PLATFORM_VERSION                         0x0901
  162. #define CL_PLATFORM_NAME                            0x0902
  163. #define CL_PLATFORM_VENDOR                          0x0903
  164. #define CL_PLATFORM_EXTENSIONS                      0x0904
  165.  
  166. /* cl_device_type - bitfield */
  167. #define CL_DEVICE_TYPE_DEFAULT                      (1 << 0)
  168. #define CL_DEVICE_TYPE_CPU                          (1 << 1)
  169. #define CL_DEVICE_TYPE_GPU                          (1 << 2)
  170. #define CL_DEVICE_TYPE_ACCELERATOR                  (1 << 3)
  171. #define CL_DEVICE_TYPE_ALL                          0xFFFFFFFF
  172.  
  173. /* cl_device_info */
  174. #define CL_DEVICE_TYPE                              0x1000
  175. #define CL_DEVICE_VENDOR_ID                         0x1001
  176. #define CL_DEVICE_MAX_COMPUTE_UNITS                 0x1002
  177. #define CL_DEVICE_MAX_WORK_ITEM_DIMENSIONS          0x1003
  178. #define CL_DEVICE_MAX_WORK_GROUP_SIZE               0x1004
  179. #define CL_DEVICE_MAX_WORK_ITEM_SIZES               0x1005
  180. #define CL_DEVICE_PREFERRED_VECTOR_WIDTH_CHAR       0x1006
  181. #define CL_DEVICE_PREFERRED_VECTOR_WIDTH_SHORT      0x1007
  182. #define CL_DEVICE_PREFERRED_VECTOR_WIDTH_INT        0x1008
  183. #define CL_DEVICE_PREFERRED_VECTOR_WIDTH_LONG       0x1009
  184. #define CL_DEVICE_PREFERRED_VECTOR_WIDTH_FLOAT      0x100A
  185. #define CL_DEVICE_PREFERRED_VECTOR_WIDTH_DOUBLE     0x100B
  186. #define CL_DEVICE_MAX_CLOCK_FREQUENCY               0x100C
  187. #define CL_DEVICE_ADDRESS_BITS                      0x100D
  188. #define CL_DEVICE_MAX_READ_IMAGE_ARGS               0x100E
  189. #define CL_DEVICE_MAX_WRITE_IMAGE_ARGS              0x100F
  190. #define CL_DEVICE_MAX_MEM_ALLOC_SIZE                0x1010
  191. #define CL_DEVICE_IMAGE2D_MAX_WIDTH                 0x1011
  192. #define CL_DEVICE_IMAGE2D_MAX_HEIGHT                0x1012
  193. #define CL_DEVICE_IMAGE3D_MAX_WIDTH                 0x1013
  194. #define CL_DEVICE_IMAGE3D_MAX_HEIGHT                0x1014
  195. #define CL_DEVICE_IMAGE3D_MAX_DEPTH                 0x1015
  196. #define CL_DEVICE_IMAGE_SUPPORT                     0x1016
  197. #define CL_DEVICE_MAX_PARAMETER_SIZE                0x1017
  198. #define CL_DEVICE_MAX_SAMPLERS                      0x1018
  199. #define CL_DEVICE_MEM_BASE_ADDR_ALIGN               0x1019
  200. #define CL_DEVICE_MIN_DATA_TYPE_ALIGN_SIZE          0x101A
  201. #define CL_DEVICE_SINGLE_FP_CONFIG                  0x101B
  202. #define CL_DEVICE_GLOBAL_MEM_CACHE_TYPE             0x101C
  203. #define CL_DEVICE_GLOBAL_MEM_CACHELINE_SIZE         0x101D
  204. #define CL_DEVICE_GLOBAL_MEM_CACHE_SIZE             0x101E
  205. #define CL_DEVICE_GLOBAL_MEM_SIZE                   0x101F
  206. #define CL_DEVICE_MAX_CONSTANT_BUFFER_SIZE          0x1020
  207. #define CL_DEVICE_MAX_CONSTANT_ARGS                 0x1021
  208. #define CL_DEVICE_LOCAL_MEM_TYPE                    0x1022
  209. #define CL_DEVICE_LOCAL_MEM_SIZE                    0x1023
  210. #define CL_DEVICE_ERROR_CORRECTION_SUPPORT          0x1024
  211. #define CL_DEVICE_PROFILING_TIMER_RESOLUTION        0x1025
  212. #define CL_DEVICE_ENDIAN_LITTLE                     0x1026
  213. #define CL_DEVICE_AVAILABLE                         0x1027
  214. #define CL_DEVICE_COMPILER_AVAILABLE                0x1028
  215. #define CL_DEVICE_EXECUTION_CAPABILITIES            0x1029
  216. #define CL_DEVICE_QUEUE_PROPERTIES                  0x102A
  217. #define CL_DEVICE_NAME                              0x102B
  218. #define CL_DEVICE_VENDOR                            0x102C
  219. #define CL_DRIVER_VERSION                           0x102D
  220. #define CL_DEVICE_PROFILE                           0x102E
  221. #define CL_DEVICE_VERSION                           0x102F
  222. #define CL_DEVICE_EXTENSIONS                        0x1030
  223. #define CL_DEVICE_PLATFORM                          0x1031
  224. /* 0x1032 reserved for CL_DEVICE_DOUBLE_FP_CONFIG */
  225. /* 0x1033 reserved for CL_DEVICE_HALF_FP_CONFIG */
  226. #define CL_DEVICE_PREFERRED_VECTOR_WIDTH_HALF       0x1034
  227. #define CL_DEVICE_HOST_UNIFIED_MEMORY               0x1035
  228. #define CL_DEVICE_NATIVE_VECTOR_WIDTH_CHAR          0x1036
  229. #define CL_DEVICE_NATIVE_VECTOR_WIDTH_SHORT         0x1037
  230. #define CL_DEVICE_NATIVE_VECTOR_WIDTH_INT           0x1038
  231. #define CL_DEVICE_NATIVE_VECTOR_WIDTH_LONG          0x1039
  232. #define CL_DEVICE_NATIVE_VECTOR_WIDTH_FLOAT         0x103A
  233. #define CL_DEVICE_NATIVE_VECTOR_WIDTH_DOUBLE        0x103B
  234. #define CL_DEVICE_NATIVE_VECTOR_WIDTH_HALF          0x103C
  235. #define CL_DEVICE_OPENCL_C_VERSION                  0x103D
  236.  
  237. /* cl_device_fp_config - bitfield */
  238. #define CL_FP_DENORM                                (1 << 0)
  239. #define CL_FP_INF_NAN                               (1 << 1)
  240. #define CL_FP_ROUND_TO_NEAREST                      (1 << 2)
  241. #define CL_FP_ROUND_TO_ZERO                         (1 << 3)
  242. #define CL_FP_ROUND_TO_INF                          (1 << 4)
  243. #define CL_FP_FMA                                   (1 << 5)
  244. #define CL_FP_SOFT_FLOAT                            (1 << 6)
  245.  
  246. /* cl_device_mem_cache_type */
  247. #define CL_NONE                                     0x0
  248. #define CL_READ_ONLY_CACHE                          0x1
  249. #define CL_READ_WRITE_CACHE                         0x2
  250.  
  251. /* cl_device_local_mem_type */
  252. #define CL_LOCAL                                    0x1
  253. #define CL_GLOBAL                                   0x2
  254.  
  255. /* cl_device_exec_capabilities - bitfield */
  256. #define CL_EXEC_KERNEL                              (1 << 0)
  257. #define CL_EXEC_NATIVE_KERNEL                       (1 << 1)
  258.  
  259. /* cl_command_queue_properties - bitfield */
  260. #define CL_QUEUE_OUT_OF_ORDER_EXEC_MODE_ENABLE      (1 << 0)
  261. #define CL_QUEUE_PROFILING_ENABLE                   (1 << 1)
  262.  
  263. /* cl_context_info  */
  264. #define CL_CONTEXT_REFERENCE_COUNT                  0x1080
  265. #define CL_CONTEXT_DEVICES                          0x1081
  266. #define CL_CONTEXT_PROPERTIES                       0x1082
  267. #define CL_CONTEXT_NUM_DEVICES                      0x1083
  268.  
  269. /* cl_context_info + cl_context_properties */
  270. #define CL_CONTEXT_PLATFORM                         0x1084
  271.  
  272. /* cl_command_queue_info */
  273. #define CL_QUEUE_CONTEXT                            0x1090
  274. #define CL_QUEUE_DEVICE                             0x1091
  275. #define CL_QUEUE_REFERENCE_COUNT                    0x1092
  276. #define CL_QUEUE_PROPERTIES                         0x1093
  277.  
  278. /* cl_mem_flags - bitfield */
  279. #define CL_MEM_READ_WRITE                           (1 << 0)
  280. #define CL_MEM_WRITE_ONLY                           (1 << 1)
  281. #define CL_MEM_READ_ONLY                            (1 << 2)
  282. #define CL_MEM_USE_HOST_PTR                         (1 << 3)
  283. #define CL_MEM_ALLOC_HOST_PTR                       (1 << 4)
  284. #define CL_MEM_COPY_HOST_PTR                        (1 << 5)
  285.  
  286. /* cl_channel_order */
  287. #define CL_R                                        0x10B0
  288. #define CL_A                                        0x10B1
  289. #define CL_RG                                       0x10B2
  290. #define CL_RA                                       0x10B3
  291. #define CL_RGB                                      0x10B4
  292. #define CL_RGBA                                     0x10B5
  293. #define CL_BGRA                                     0x10B6
  294. #define CL_ARGB                                     0x10B7
  295. #define CL_INTENSITY                                0x10B8
  296. #define CL_LUMINANCE                                0x10B9
  297. #define CL_Rx                                       0x10BA
  298. #define CL_RGx                                      0x10BB
  299. #define CL_RGBx                                     0x10BC
  300.  
  301. /* cl_channel_type */
  302. #define CL_SNORM_INT8                               0x10D0
  303. #define CL_SNORM_INT16                              0x10D1
  304. #define CL_UNORM_INT8                               0x10D2
  305. #define CL_UNORM_INT16                              0x10D3
  306. #define CL_UNORM_SHORT_565                          0x10D4
  307. #define CL_UNORM_SHORT_555                          0x10D5
  308. #define CL_UNORM_INT_101010                         0x10D6
  309. #define CL_SIGNED_INT8                              0x10D7
  310. #define CL_SIGNED_INT16                             0x10D8
  311. #define CL_SIGNED_INT32                             0x10D9
  312. #define CL_UNSIGNED_INT8                            0x10DA
  313. #define CL_UNSIGNED_INT16                           0x10DB
  314. #define CL_UNSIGNED_INT32                           0x10DC
  315. #define CL_HALF_FLOAT                               0x10DD
  316. #define CL_FLOAT                                    0x10DE
  317.  
  318. /* cl_mem_object_type */
  319. #define CL_MEM_OBJECT_BUFFER                        0x10F0
  320. #define CL_MEM_OBJECT_IMAGE2D                       0x10F1
  321. #define CL_MEM_OBJECT_IMAGE3D                       0x10F2
  322.  
  323. /* cl_mem_info */
  324. #define CL_MEM_TYPE                                 0x1100
  325. #define CL_MEM_FLAGS                                0x1101
  326. #define CL_MEM_SIZE                                 0x1102
  327. #define CL_MEM_HOST_PTR                             0x1103
  328. #define CL_MEM_MAP_COUNT                            0x1104
  329. #define CL_MEM_REFERENCE_COUNT                      0x1105
  330. #define CL_MEM_CONTEXT                              0x1106
  331. #define CL_MEM_ASSOCIATED_MEMOBJECT                 0x1107
  332. #define CL_MEM_OFFSET                               0x1108
  333.  
  334. /* cl_image_info */
  335. #define CL_IMAGE_FORMAT                             0x1110
  336. #define CL_IMAGE_ELEMENT_SIZE                       0x1111
  337. #define CL_IMAGE_ROW_PITCH                          0x1112
  338. #define CL_IMAGE_SLICE_PITCH                        0x1113
  339. #define CL_IMAGE_WIDTH                              0x1114
  340. #define CL_IMAGE_HEIGHT                             0x1115
  341. #define CL_IMAGE_DEPTH                              0x1116
  342.  
  343. /* cl_addressing_mode */
  344. #define CL_ADDRESS_NONE                             0x1130
  345. #define CL_ADDRESS_CLAMP_TO_EDGE                    0x1131
  346. #define CL_ADDRESS_CLAMP                            0x1132
  347. #define CL_ADDRESS_REPEAT                           0x1133
  348. #define CL_ADDRESS_MIRRORED_REPEAT                  0x1134
  349.  
  350. /* cl_filter_mode */
  351. #define CL_FILTER_NEAREST                           0x1140
  352. #define CL_FILTER_LINEAR                            0x1141
  353.  
  354. /* cl_sampler_info */
  355. #define CL_SAMPLER_REFERENCE_COUNT                  0x1150
  356. #define CL_SAMPLER_CONTEXT                          0x1151
  357. #define CL_SAMPLER_NORMALIZED_COORDS                0x1152
  358. #define CL_SAMPLER_ADDRESSING_MODE                  0x1153
  359. #define CL_SAMPLER_FILTER_MODE                      0x1154
  360.  
  361. /* cl_map_flags - bitfield */
  362. #define CL_MAP_READ                                 (1 << 0)
  363. #define CL_MAP_WRITE                                (1 << 1)
  364.  
  365. /* cl_program_info */
  366. #define CL_PROGRAM_REFERENCE_COUNT                  0x1160
  367. #define CL_PROGRAM_CONTEXT                          0x1161
  368. #define CL_PROGRAM_NUM_DEVICES                      0x1162
  369. #define CL_PROGRAM_DEVICES                          0x1163
  370. #define CL_PROGRAM_SOURCE                           0x1164
  371. #define CL_PROGRAM_BINARY_SIZES                     0x1165
  372. #define CL_PROGRAM_BINARIES                         0x1166
  373.  
  374. /* cl_program_build_info */
  375. #define CL_PROGRAM_BUILD_STATUS                     0x1181
  376. #define CL_PROGRAM_BUILD_OPTIONS                    0x1182
  377. #define CL_PROGRAM_BUILD_LOG                        0x1183
  378.  
  379. /* cl_build_status */
  380. #define CL_BUILD_SUCCESS                            0
  381. #define CL_BUILD_NONE                               -1
  382. #define CL_BUILD_ERROR                              -2
  383. #define CL_BUILD_IN_PROGRESS                        -3
  384.  
  385. /* cl_kernel_info */
  386. #define CL_KERNEL_FUNCTION_NAME                     0x1190
  387. #define CL_KERNEL_NUM_ARGS                          0x1191
  388. #define CL_KERNEL_REFERENCE_COUNT                   0x1192
  389. #define CL_KERNEL_CONTEXT                           0x1193
  390. #define CL_KERNEL_PROGRAM                           0x1194
  391.  
  392. /* cl_kernel_work_group_info */
  393. #define CL_KERNEL_WORK_GROUP_SIZE                   0x11B0
  394. #define CL_KERNEL_COMPILE_WORK_GROUP_SIZE           0x11B1
  395. #define CL_KERNEL_LOCAL_MEM_SIZE                    0x11B2
  396. #define CL_KERNEL_PREFERRED_WORK_GROUP_SIZE_MULTIPLE 0x11B3
  397. #define CL_KERNEL_PRIVATE_MEM_SIZE                  0x11B4
  398.  
  399. /* cl_event_info  */
  400. #define CL_EVENT_COMMAND_QUEUE                      0x11D0
  401. #define CL_EVENT_COMMAND_TYPE                       0x11D1
  402. #define CL_EVENT_REFERENCE_COUNT                    0x11D2
  403. #define CL_EVENT_COMMAND_EXECUTION_STATUS           0x11D3
  404. #define CL_EVENT_CONTEXT                            0x11D4
  405.  
  406. /* cl_command_type */
  407. #define CL_COMMAND_NDRANGE_KERNEL                   0x11F0
  408. #define CL_COMMAND_TASK                             0x11F1
  409. #define CL_COMMAND_NATIVE_KERNEL                    0x11F2
  410. #define CL_COMMAND_READ_BUFFER                      0x11F3
  411. #define CL_COMMAND_WRITE_BUFFER                     0x11F4
  412. #define CL_COMMAND_COPY_BUFFER                      0x11F5
  413. #define CL_COMMAND_READ_IMAGE                       0x11F6
  414. #define CL_COMMAND_WRITE_IMAGE                      0x11F7
  415. #define CL_COMMAND_COPY_IMAGE                       0x11F8
  416. #define CL_COMMAND_COPY_IMAGE_TO_BUFFER             0x11F9
  417. #define CL_COMMAND_COPY_BUFFER_TO_IMAGE             0x11FA
  418. #define CL_COMMAND_MAP_BUFFER                       0x11FB
  419. #define CL_COMMAND_MAP_IMAGE                        0x11FC
  420. #define CL_COMMAND_UNMAP_MEM_OBJECT                 0x11FD
  421. #define CL_COMMAND_MARKER                           0x11FE
  422. #define CL_COMMAND_ACQUIRE_GL_OBJECTS               0x11FF
  423. #define CL_COMMAND_RELEASE_GL_OBJECTS               0x1200
  424. #define CL_COMMAND_READ_BUFFER_RECT                 0x1201
  425. #define CL_COMMAND_WRITE_BUFFER_RECT                0x1202
  426. #define CL_COMMAND_COPY_BUFFER_RECT                 0x1203
  427. #define CL_COMMAND_USER                             0x1204
  428.  
  429. /* command execution status */
  430. #define CL_COMPLETE                                 0x0
  431. #define CL_RUNNING                                  0x1
  432. #define CL_SUBMITTED                                0x2
  433. #define CL_QUEUED                                   0x3
  434.  
  435. /* cl_buffer_create_type  */
  436. #define CL_BUFFER_CREATE_TYPE_REGION                0x1220
  437.  
  438. /* cl_profiling_info  */
  439. #define CL_PROFILING_COMMAND_QUEUED                 0x1280
  440. #define CL_PROFILING_COMMAND_SUBMIT                 0x1281
  441. #define CL_PROFILING_COMMAND_START                  0x1282
  442. #define CL_PROFILING_COMMAND_END                    0x1283
  443.  
  444. /********************************************************************************************************/
  445.  
  446. /* Platform API */
  447. extern CL_API_ENTRY cl_int CL_API_CALL
  448. clGetPlatformIDs(cl_uint          /* num_entries */,
  449.                  cl_platform_id * /* platforms */,
  450.                  cl_uint *        /* num_platforms */) CL_API_SUFFIX__VERSION_1_0;
  451.  
  452. extern CL_API_ENTRY cl_int CL_API_CALL
  453. clGetPlatformInfo(cl_platform_id   /* platform */,
  454.                   cl_platform_info /* param_name */,
  455.                   size_t           /* param_value_size */,
  456.                   void *           /* param_value */,
  457.                   size_t *         /* param_value_size_ret */) CL_API_SUFFIX__VERSION_1_0;
  458.  
  459. /* Device APIs */
  460. extern CL_API_ENTRY cl_int CL_API_CALL
  461. clGetDeviceIDs(cl_platform_id   /* platform */,
  462.                cl_device_type   /* device_type */,
  463.                cl_uint          /* num_entries */,
  464.                cl_device_id *   /* devices */,
  465.                cl_uint *        /* num_devices */) CL_API_SUFFIX__VERSION_1_0;
  466.  
  467. extern CL_API_ENTRY cl_int CL_API_CALL
  468. clGetDeviceInfo(cl_device_id    /* device */,
  469.                 cl_device_info  /* param_name */,
  470.                 size_t          /* param_value_size */,
  471.                 void *          /* param_value */,
  472.                 size_t *        /* param_value_size_ret */) CL_API_SUFFIX__VERSION_1_0;
  473.  
  474. /* Context APIs  */
  475. extern CL_API_ENTRY cl_context CL_API_CALL
  476. clCreateContext(const cl_context_properties * /* properties */,
  477.                 cl_uint                       /* num_devices */,
  478.                 const cl_device_id *          /* devices */,
  479.                 void (CL_CALLBACK * /* pfn_notify */)(const char *, const void *, size_t, void *),
  480.                 void *                        /* user_data */,
  481.                 cl_int *                      /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0;
  482.  
  483. extern CL_API_ENTRY cl_context CL_API_CALL
  484. clCreateContextFromType(const cl_context_properties * /* properties */,
  485.                         cl_device_type                /* device_type */,
  486.                         void (CL_CALLBACK *     /* pfn_notify*/ )(const char *, const void *, size_t, void *),
  487.                         void *                        /* user_data */,
  488.                         cl_int *                      /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0;
  489.  
  490. extern CL_API_ENTRY cl_int CL_API_CALL
  491. clRetainContext(cl_context /* context */) CL_API_SUFFIX__VERSION_1_0;
  492.  
  493. extern CL_API_ENTRY cl_int CL_API_CALL
  494. clReleaseContext(cl_context /* context */) CL_API_SUFFIX__VERSION_1_0;
  495.  
  496. extern CL_API_ENTRY cl_int CL_API_CALL
  497. clGetContextInfo(cl_context         /* context */,
  498.                  cl_context_info    /* param_name */,
  499.                  size_t             /* param_value_size */,
  500.                  void *             /* param_value */,
  501.                  size_t *           /* param_value_size_ret */) CL_API_SUFFIX__VERSION_1_0;
  502.  
  503. /* Command Queue APIs */
  504. extern CL_API_ENTRY cl_command_queue CL_API_CALL
  505. clCreateCommandQueue(cl_context                     /* context */,
  506.                      cl_device_id                   /* device */,
  507.                      cl_command_queue_properties    /* properties */,
  508.                      cl_int *                       /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0;
  509.  
  510. extern CL_API_ENTRY cl_int CL_API_CALL
  511. clRetainCommandQueue(cl_command_queue /* command_queue */) CL_API_SUFFIX__VERSION_1_0;
  512.  
  513. extern CL_API_ENTRY cl_int CL_API_CALL
  514. clReleaseCommandQueue(cl_command_queue /* command_queue */) CL_API_SUFFIX__VERSION_1_0;
  515.  
  516. extern CL_API_ENTRY cl_int CL_API_CALL
  517. clGetCommandQueueInfo(cl_command_queue      /* command_queue */,
  518.                       cl_command_queue_info /* param_name */,
  519.                       size_t                /* param_value_size */,
  520.                       void *                /* param_value */,
  521.                       size_t *              /* param_value_size_ret */) CL_API_SUFFIX__VERSION_1_0;
  522.  
  523. #ifdef CL_USE_DEPRECATED_OPENCL_1_0_APIS
  524. #warning CL_USE_DEPRECATED_OPENCL_1_0_APIS is defined. These APIs are unsupported and untested in OpenCL 1.1!
  525. /*
  526.  *  WARNING:
  527.  *     This API introduces mutable state into the OpenCL implementation. It has been REMOVED
  528.  *  to better facilitate thread safety.  The 1.0 API is not thread safe. It is not tested by the
  529.  *  OpenCL 1.1 conformance test, and consequently may not work or may not work dependably.
  530.  *  It is likely to be non-performant. Use of this API is not advised. Use at your own risk.
  531.  *
  532.  *  Software developers previously relying on this API are instructed to set the command queue
  533.  *  properties when creating the queue, instead.
  534.  */
  535. extern CL_API_ENTRY cl_int CL_API_CALL
  536. clSetCommandQueueProperty(cl_command_queue              /* command_queue */,
  537.                           cl_command_queue_properties   /* properties */,
  538.                           cl_bool                        /* enable */,
  539.                           cl_command_queue_properties * /* old_properties */) CL_EXT_SUFFIX__VERSION_1_0_DEPRECATED;
  540. #endif /* CL_USE_DEPRECATED_OPENCL_1_0_APIS */
  541.  
  542. /* Memory Object APIs */
  543. extern CL_API_ENTRY cl_mem CL_API_CALL
  544. clCreateBuffer(cl_context   /* context */,
  545.                cl_mem_flags /* flags */,
  546.                size_t       /* size */,
  547.                void *       /* host_ptr */,
  548.                cl_int *     /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0;
  549.  
  550. extern CL_API_ENTRY cl_mem CL_API_CALL
  551. clCreateSubBuffer(cl_mem                   /* buffer */,
  552.                   cl_mem_flags             /* flags */,
  553.                   cl_buffer_create_type    /* buffer_create_type */,
  554.                   const void *             /* buffer_create_info */,
  555.                   cl_int *                 /* errcode_ret */) CL_API_SUFFIX__VERSION_1_1;
  556.  
  557. extern CL_API_ENTRY cl_mem CL_API_CALL
  558. clCreateImage2D(cl_context              /* context */,
  559.                 cl_mem_flags            /* flags */,
  560.                 const cl_image_format * /* image_format */,
  561.                 size_t                  /* image_width */,
  562.                 size_t                  /* image_height */,
  563.                 size_t                  /* image_row_pitch */,
  564.                 void *                  /* host_ptr */,
  565.                 cl_int *                /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0;
  566.                        
  567. extern CL_API_ENTRY cl_mem CL_API_CALL
  568. clCreateImage3D(cl_context              /* context */,
  569.                 cl_mem_flags            /* flags */,
  570.                 const cl_image_format * /* image_format */,
  571.                 size_t                  /* image_width */,
  572.                 size_t                  /* image_height */,
  573.                 size_t                  /* image_depth */,
  574.                 size_t                  /* image_row_pitch */,
  575.                 size_t                  /* image_slice_pitch */,
  576.                 void *                  /* host_ptr */,
  577.                 cl_int *                /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0;
  578.                        
  579. extern CL_API_ENTRY cl_int CL_API_CALL
  580. clRetainMemObject(cl_mem /* memobj */) CL_API_SUFFIX__VERSION_1_0;
  581.  
  582. extern CL_API_ENTRY cl_int CL_API_CALL
  583. clReleaseMemObject(cl_mem /* memobj */) CL_API_SUFFIX__VERSION_1_0;
  584.  
  585. extern CL_API_ENTRY cl_int CL_API_CALL
  586. clGetSupportedImageFormats(cl_context           /* context */,
  587.                            cl_mem_flags         /* flags */,
  588.                            cl_mem_object_type   /* image_type */,
  589.                            cl_uint              /* num_entries */,
  590.                            cl_image_format *    /* image_formats */,
  591.                            cl_uint *            /* num_image_formats */) CL_API_SUFFIX__VERSION_1_0;
  592.                                    
  593. extern CL_API_ENTRY cl_int CL_API_CALL
  594. clGetMemObjectInfo(cl_mem           /* memobj */,
  595.                    cl_mem_info      /* param_name */,
  596.                    size_t           /* param_value_size */,
  597.                    void *           /* param_value */,
  598.                    size_t *         /* param_value_size_ret */) CL_API_SUFFIX__VERSION_1_0;
  599.  
  600. extern CL_API_ENTRY cl_int CL_API_CALL
  601. clGetImageInfo(cl_mem           /* image */,
  602.                cl_image_info    /* param_name */,
  603.                size_t           /* param_value_size */,
  604.                void *           /* param_value */,
  605.                size_t *         /* param_value_size_ret */) CL_API_SUFFIX__VERSION_1_0;
  606.  
  607. extern CL_API_ENTRY cl_int CL_API_CALL
  608. clSetMemObjectDestructorCallback(  cl_mem /* memobj */,
  609.                                     void (CL_CALLBACK * /*pfn_notify*/)( cl_mem /* memobj */, void* /*user_data*/),
  610.                                     void * /*user_data */ )             CL_API_SUFFIX__VERSION_1_1;  
  611.  
  612. /* Sampler APIs  */
  613. extern CL_API_ENTRY cl_sampler CL_API_CALL
  614. clCreateSampler(cl_context          /* context */,
  615.                 cl_bool             /* normalized_coords */,
  616.                 cl_addressing_mode  /* addressing_mode */,
  617.                 cl_filter_mode      /* filter_mode */,
  618.                 cl_int *            /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0;
  619.  
  620. extern CL_API_ENTRY cl_int CL_API_CALL
  621. clRetainSampler(cl_sampler /* sampler */) CL_API_SUFFIX__VERSION_1_0;
  622.  
  623. extern CL_API_ENTRY cl_int CL_API_CALL
  624. clReleaseSampler(cl_sampler /* sampler */) CL_API_SUFFIX__VERSION_1_0;
  625.  
  626. extern CL_API_ENTRY cl_int CL_API_CALL
  627. clGetSamplerInfo(cl_sampler         /* sampler */,
  628.                  cl_sampler_info    /* param_name */,
  629.                  size_t             /* param_value_size */,
  630.                  void *             /* param_value */,
  631.                  size_t *           /* param_value_size_ret */) CL_API_SUFFIX__VERSION_1_0;
  632.                            
  633. /* Program Object APIs  */
  634. extern CL_API_ENTRY cl_program CL_API_CALL
  635. clCreateProgramWithSource(cl_context        /* context */,
  636.                           cl_uint           /* count */,
  637.                           const char **     /* strings */,
  638.                           const size_t *    /* lengths */,
  639.                           cl_int *          /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0;
  640.  
  641. extern CL_API_ENTRY cl_program CL_API_CALL
  642. clCreateProgramWithBinary(cl_context                     /* context */,
  643.                           cl_uint                        /* num_devices */,
  644.                           const cl_device_id *           /* device_list */,
  645.                           const size_t *                 /* lengths */,
  646.                           const unsigned char **         /* binaries */,
  647.                           cl_int *                       /* binary_status */,
  648.                           cl_int *                       /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0;
  649.  
  650. extern CL_API_ENTRY cl_int CL_API_CALL
  651. clRetainProgram(cl_program /* program */) CL_API_SUFFIX__VERSION_1_0;
  652.  
  653. extern CL_API_ENTRY cl_int CL_API_CALL
  654. clReleaseProgram(cl_program /* program */) CL_API_SUFFIX__VERSION_1_0;
  655.  
  656. extern CL_API_ENTRY cl_int CL_API_CALL
  657. clBuildProgram(cl_program           /* program */,
  658.                cl_uint              /* num_devices */,
  659.                const cl_device_id * /* device_list */,
  660.                const char *         /* options */,
  661.                void (CL_CALLBACK *  /* pfn_notify */)(cl_program /* program */, void * /* user_data */),
  662.                void *               /* user_data */) CL_API_SUFFIX__VERSION_1_0;
  663.  
  664. extern CL_API_ENTRY cl_int CL_API_CALL
  665. clUnloadCompiler(void) CL_API_SUFFIX__VERSION_1_0;
  666.  
  667. extern CL_API_ENTRY cl_int CL_API_CALL
  668. clGetProgramInfo(cl_program         /* program */,
  669.                  cl_program_info    /* param_name */,
  670.                  size_t             /* param_value_size */,
  671.                  void *             /* param_value */,
  672.                  size_t *           /* param_value_size_ret */) CL_API_SUFFIX__VERSION_1_0;
  673.  
  674. extern CL_API_ENTRY cl_int CL_API_CALL
  675. clGetProgramBuildInfo(cl_program            /* program */,
  676.                       cl_device_id          /* device */,
  677.                       cl_program_build_info /* param_name */,
  678.                       size_t                /* param_value_size */,
  679.                       void *                /* param_value */,
  680.                       size_t *              /* param_value_size_ret */) CL_API_SUFFIX__VERSION_1_0;
  681.                            
  682. /* Kernel Object APIs */
  683. extern CL_API_ENTRY cl_kernel CL_API_CALL
  684. clCreateKernel(cl_program      /* program */,
  685.                const char *    /* kernel_name */,
  686.                cl_int *        /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0;
  687.  
  688. extern CL_API_ENTRY cl_int CL_API_CALL
  689. clCreateKernelsInProgram(cl_program     /* program */,
  690.                          cl_uint        /* num_kernels */,
  691.                          cl_kernel *    /* kernels */,
  692.                          cl_uint *      /* num_kernels_ret */) CL_API_SUFFIX__VERSION_1_0;
  693.  
  694. extern CL_API_ENTRY cl_int CL_API_CALL
  695. clRetainKernel(cl_kernel    /* kernel */) CL_API_SUFFIX__VERSION_1_0;
  696.  
  697. extern CL_API_ENTRY cl_int CL_API_CALL
  698. clReleaseKernel(cl_kernel   /* kernel */) CL_API_SUFFIX__VERSION_1_0;
  699.  
  700. extern CL_API_ENTRY cl_int CL_API_CALL
  701. clSetKernelArg(cl_kernel    /* kernel */,
  702.                cl_uint      /* arg_index */,
  703.                size_t       /* arg_size */,
  704.                const void * /* arg_value */) CL_API_SUFFIX__VERSION_1_0;
  705.  
  706. extern CL_API_ENTRY cl_int CL_API_CALL
  707. clGetKernelInfo(cl_kernel       /* kernel */,
  708.                 cl_kernel_info  /* param_name */,
  709.                 size_t          /* param_value_size */,
  710.                 void *          /* param_value */,
  711.                 size_t *        /* param_value_size_ret */) CL_API_SUFFIX__VERSION_1_0;
  712.  
  713. extern CL_API_ENTRY cl_int CL_API_CALL
  714. clGetKernelWorkGroupInfo(cl_kernel                  /* kernel */,
  715.                          cl_device_id               /* device */,
  716.                          cl_kernel_work_group_info  /* param_name */,
  717.                          size_t                     /* param_value_size */,
  718.                          void *                     /* param_value */,
  719.                          size_t *                   /* param_value_size_ret */) CL_API_SUFFIX__VERSION_1_0;
  720.  
  721. /* Event Object APIs  */
  722. extern CL_API_ENTRY cl_int CL_API_CALL
  723. clWaitForEvents(cl_uint             /* num_events */,
  724.                 const cl_event *    /* event_list */) CL_API_SUFFIX__VERSION_1_0;
  725.  
  726. extern CL_API_ENTRY cl_int CL_API_CALL
  727. clGetEventInfo(cl_event         /* event */,
  728.                cl_event_info    /* param_name */,
  729.                size_t           /* param_value_size */,
  730.                void *           /* param_value */,
  731.                size_t *         /* param_value_size_ret */) CL_API_SUFFIX__VERSION_1_0;
  732.                            
  733. extern CL_API_ENTRY cl_event CL_API_CALL
  734. clCreateUserEvent(cl_context    /* context */,
  735.                   cl_int *      /* errcode_ret */) CL_API_SUFFIX__VERSION_1_1;              
  736.                            
  737. extern CL_API_ENTRY cl_int CL_API_CALL
  738. clRetainEvent(cl_event /* event */) CL_API_SUFFIX__VERSION_1_0;
  739.  
  740. extern CL_API_ENTRY cl_int CL_API_CALL
  741. clReleaseEvent(cl_event /* event */) CL_API_SUFFIX__VERSION_1_0;
  742.  
  743. extern CL_API_ENTRY cl_int CL_API_CALL
  744. clSetUserEventStatus(cl_event   /* event */,
  745.                      cl_int     /* execution_status */) CL_API_SUFFIX__VERSION_1_1;
  746.                      
  747. extern CL_API_ENTRY cl_int CL_API_CALL
  748. clSetEventCallback( cl_event    /* event */,
  749.                     cl_int      /* command_exec_callback_type */,
  750.                     void (CL_CALLBACK * /* pfn_notify */)(cl_event, cl_int, void *),
  751.                     void *      /* user_data */) CL_API_SUFFIX__VERSION_1_1;
  752.  
  753. /* Profiling APIs  */
  754. extern CL_API_ENTRY cl_int CL_API_CALL
  755. clGetEventProfilingInfo(cl_event            /* event */,
  756.                         cl_profiling_info   /* param_name */,
  757.                         size_t              /* param_value_size */,
  758.                         void *              /* param_value */,
  759.                         size_t *            /* param_value_size_ret */) CL_API_SUFFIX__VERSION_1_0;
  760.                                
  761. /* Flush and Finish APIs */
  762. extern CL_API_ENTRY cl_int CL_API_CALL
  763. clFlush(cl_command_queue /* command_queue */) CL_API_SUFFIX__VERSION_1_0;
  764.  
  765. extern CL_API_ENTRY cl_int CL_API_CALL
  766. clFinish(cl_command_queue /* command_queue */) CL_API_SUFFIX__VERSION_1_0;
  767.  
  768. /* Enqueued Commands APIs */
  769. extern CL_API_ENTRY cl_int CL_API_CALL
  770. clEnqueueReadBuffer(cl_command_queue    /* command_queue */,
  771.                     cl_mem              /* buffer */,
  772.                     cl_bool             /* blocking_read */,
  773.                     size_t              /* offset */,
  774.                     size_t              /* cb */,
  775.                     void *              /* ptr */,
  776.                     cl_uint             /* num_events_in_wait_list */,
  777.                     const cl_event *    /* event_wait_list */,
  778.                     cl_event *          /* event */) CL_API_SUFFIX__VERSION_1_0;
  779.                            
  780. extern CL_API_ENTRY cl_int CL_API_CALL
  781. clEnqueueReadBufferRect(cl_command_queue    /* command_queue */,
  782.                         cl_mem              /* buffer */,
  783.                         cl_bool             /* blocking_read */,
  784.                         const size_t *      /* buffer_origin */,
  785.                         const size_t *      /* host_origin */,
  786.                         const size_t *      /* region */,
  787.                         size_t              /* buffer_row_pitch */,
  788.                         size_t              /* buffer_slice_pitch */,
  789.                         size_t              /* host_row_pitch */,
  790.                         size_t              /* host_slice_pitch */,                        
  791.                         void *              /* ptr */,
  792.                         cl_uint             /* num_events_in_wait_list */,
  793.                         const cl_event *    /* event_wait_list */,
  794.                         cl_event *          /* event */) CL_API_SUFFIX__VERSION_1_1;
  795.                            
  796. extern CL_API_ENTRY cl_int CL_API_CALL
  797. clEnqueueWriteBuffer(cl_command_queue   /* command_queue */,
  798.                      cl_mem             /* buffer */,
  799.                      cl_bool            /* blocking_write */,
  800.                      size_t             /* offset */,
  801.                      size_t             /* cb */,
  802.                      const void *       /* ptr */,
  803.                      cl_uint            /* num_events_in_wait_list */,
  804.                      const cl_event *   /* event_wait_list */,
  805.                      cl_event *         /* event */) CL_API_SUFFIX__VERSION_1_0;
  806.                            
  807. extern CL_API_ENTRY cl_int CL_API_CALL
  808. clEnqueueWriteBufferRect(cl_command_queue    /* command_queue */,
  809.                          cl_mem              /* buffer */,
  810.                          cl_bool             /* blocking_write */,
  811.                          const size_t *      /* buffer_origin */,
  812.                          const size_t *      /* host_origin */,
  813.                          const size_t *      /* region */,
  814.                          size_t              /* buffer_row_pitch */,
  815.                          size_t              /* buffer_slice_pitch */,
  816.                          size_t              /* host_row_pitch */,
  817.                          size_t              /* host_slice_pitch */,                        
  818.                          const void *        /* ptr */,
  819.                          cl_uint             /* num_events_in_wait_list */,
  820.                          const cl_event *    /* event_wait_list */,
  821.                          cl_event *          /* event */) CL_API_SUFFIX__VERSION_1_1;
  822.                            
  823. extern CL_API_ENTRY cl_int CL_API_CALL
  824. clEnqueueCopyBuffer(cl_command_queue    /* command_queue */,
  825.                     cl_mem              /* src_buffer */,
  826.                     cl_mem              /* dst_buffer */,
  827.                     size_t              /* src_offset */,
  828.                     size_t              /* dst_offset */,
  829.                     size_t              /* cb */,
  830.                     cl_uint             /* num_events_in_wait_list */,
  831.                     const cl_event *    /* event_wait_list */,
  832.                     cl_event *          /* event */) CL_API_SUFFIX__VERSION_1_0;
  833.                            
  834. extern CL_API_ENTRY cl_int CL_API_CALL
  835. clEnqueueCopyBufferRect(cl_command_queue    /* command_queue */,
  836.                         cl_mem              /* src_buffer */,
  837.                         cl_mem              /* dst_buffer */,
  838.                         const size_t *      /* src_origin */,
  839.                         const size_t *      /* dst_origin */,
  840.                         const size_t *      /* region */,
  841.                         size_t              /* src_row_pitch */,
  842.                         size_t              /* src_slice_pitch */,
  843.                         size_t              /* dst_row_pitch */,
  844.                         size_t              /* dst_slice_pitch */,
  845.                         cl_uint             /* num_events_in_wait_list */,
  846.                         const cl_event *    /* event_wait_list */,
  847.                         cl_event *          /* event */) CL_API_SUFFIX__VERSION_1_1;
  848.                            
  849. extern CL_API_ENTRY cl_int CL_API_CALL
  850. clEnqueueReadImage(cl_command_queue     /* command_queue */,
  851.                    cl_mem               /* image */,
  852.                    cl_bool              /* blocking_read */,
  853.                    const size_t *       /* origin[3] */,
  854.                    const size_t *       /* region[3] */,
  855.                    size_t               /* row_pitch */,
  856.                    size_t               /* slice_pitch */,
  857.                    void *               /* ptr */,
  858.                    cl_uint              /* num_events_in_wait_list */,
  859.                    const cl_event *     /* event_wait_list */,
  860.                    cl_event *           /* event */) CL_API_SUFFIX__VERSION_1_0;
  861.  
  862. extern CL_API_ENTRY cl_int CL_API_CALL
  863. clEnqueueWriteImage(cl_command_queue    /* command_queue */,
  864.                     cl_mem              /* image */,
  865.                     cl_bool             /* blocking_write */,
  866.                     const size_t *      /* origin[3] */,
  867.                     const size_t *      /* region[3] */,
  868.                     size_t              /* input_row_pitch */,
  869.                     size_t              /* input_slice_pitch */,
  870.                     const void *        /* ptr */,
  871.                     cl_uint             /* num_events_in_wait_list */,
  872.                     const cl_event *    /* event_wait_list */,
  873.                     cl_event *          /* event */) CL_API_SUFFIX__VERSION_1_0;
  874.  
  875. extern CL_API_ENTRY cl_int CL_API_CALL
  876. clEnqueueCopyImage(cl_command_queue     /* command_queue */,
  877.                    cl_mem               /* src_image */,
  878.                    cl_mem               /* dst_image */,
  879.                    const size_t *       /* src_origin[3] */,
  880.                    const size_t *       /* dst_origin[3] */,
  881.                    const size_t *       /* region[3] */,
  882.                    cl_uint              /* num_events_in_wait_list */,
  883.                    const cl_event *     /* event_wait_list */,
  884.                    cl_event *           /* event */) CL_API_SUFFIX__VERSION_1_0;
  885.  
  886. extern CL_API_ENTRY cl_int CL_API_CALL
  887. clEnqueueCopyImageToBuffer(cl_command_queue /* command_queue */,
  888.                            cl_mem           /* src_image */,
  889.                            cl_mem           /* dst_buffer */,
  890.                            const size_t *   /* src_origin[3] */,
  891.                            const size_t *   /* region[3] */,
  892.                            size_t           /* dst_offset */,
  893.                            cl_uint          /* num_events_in_wait_list */,
  894.                            const cl_event * /* event_wait_list */,
  895.                            cl_event *       /* event */) CL_API_SUFFIX__VERSION_1_0;
  896.  
  897. extern CL_API_ENTRY cl_int CL_API_CALL
  898. clEnqueueCopyBufferToImage(cl_command_queue /* command_queue */,
  899.                            cl_mem           /* src_buffer */,
  900.                            cl_mem           /* dst_image */,
  901.                            size_t           /* src_offset */,
  902.                            const size_t *   /* dst_origin[3] */,
  903.                            const size_t *   /* region[3] */,
  904.                            cl_uint          /* num_events_in_wait_list */,
  905.                            const cl_event * /* event_wait_list */,
  906.                            cl_event *       /* event */) CL_API_SUFFIX__VERSION_1_0;
  907.  
  908. extern CL_API_ENTRY void * CL_API_CALL
  909. clEnqueueMapBuffer(cl_command_queue /* command_queue */,
  910.                    cl_mem           /* buffer */,
  911.                    cl_bool          /* blocking_map */,
  912.                    cl_map_flags     /* map_flags */,
  913.                    size_t           /* offset */,
  914.                    size_t           /* cb */,
  915.                    cl_uint          /* num_events_in_wait_list */,
  916.                    const cl_event * /* event_wait_list */,
  917.                    cl_event *       /* event */,
  918.                    cl_int *         /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0;
  919.  
  920. extern CL_API_ENTRY void * CL_API_CALL
  921. clEnqueueMapImage(cl_command_queue  /* command_queue */,
  922.                   cl_mem            /* image */,
  923.                   cl_bool           /* blocking_map */,
  924.                   cl_map_flags      /* map_flags */,
  925.                   const size_t *    /* origin[3] */,
  926.                   const size_t *    /* region[3] */,
  927.                   size_t *          /* image_row_pitch */,
  928.                   size_t *          /* image_slice_pitch */,
  929.                   cl_uint           /* num_events_in_wait_list */,
  930.                   const cl_event *  /* event_wait_list */,
  931.                   cl_event *        /* event */,
  932.                   cl_int *          /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0;
  933.  
  934. extern CL_API_ENTRY cl_int CL_API_CALL
  935. clEnqueueUnmapMemObject(cl_command_queue /* command_queue */,
  936.                         cl_mem           /* memobj */,
  937.                         void *           /* mapped_ptr */,
  938.                         cl_uint          /* num_events_in_wait_list */,
  939.                         const cl_event *  /* event_wait_list */,
  940.                         cl_event *        /* event */) CL_API_SUFFIX__VERSION_1_0;
  941.  
  942. extern CL_API_ENTRY cl_int CL_API_CALL
  943. clEnqueueNDRangeKernel(cl_command_queue /* command_queue */,
  944.                        cl_kernel        /* kernel */,
  945.                        cl_uint          /* work_dim */,
  946.                        const size_t *   /* global_work_offset */,
  947.                        const size_t *   /* global_work_size */,
  948.                        const size_t *   /* local_work_size */,
  949.                        cl_uint          /* num_events_in_wait_list */,
  950.                        const cl_event * /* event_wait_list */,
  951.                        cl_event *       /* event */) CL_API_SUFFIX__VERSION_1_0;
  952.  
  953. extern CL_API_ENTRY cl_int CL_API_CALL
  954. clEnqueueTask(cl_command_queue  /* command_queue */,
  955.               cl_kernel         /* kernel */,
  956.               cl_uint           /* num_events_in_wait_list */,
  957.               const cl_event *  /* event_wait_list */,
  958.               cl_event *        /* event */) CL_API_SUFFIX__VERSION_1_0;
  959.  
  960. extern CL_API_ENTRY cl_int CL_API_CALL
  961. clEnqueueNativeKernel(cl_command_queue  /* command_queue */,
  962.                                           void (*user_func)(void *),
  963.                       void *            /* args */,
  964.                       size_t            /* cb_args */,
  965.                       cl_uint           /* num_mem_objects */,
  966.                       const cl_mem *    /* mem_list */,
  967.                       const void **     /* args_mem_loc */,
  968.                       cl_uint           /* num_events_in_wait_list */,
  969.                       const cl_event *  /* event_wait_list */,
  970.                       cl_event *        /* event */) CL_API_SUFFIX__VERSION_1_0;
  971.  
  972. extern CL_API_ENTRY cl_int CL_API_CALL
  973. clEnqueueMarker(cl_command_queue    /* command_queue */,
  974.                 cl_event *          /* event */) CL_API_SUFFIX__VERSION_1_0;
  975.  
  976. extern CL_API_ENTRY cl_int CL_API_CALL
  977. clEnqueueWaitForEvents(cl_command_queue /* command_queue */,
  978.                        cl_uint          /* num_events */,
  979.                        const cl_event * /* event_list */) CL_API_SUFFIX__VERSION_1_0;
  980.  
  981. extern CL_API_ENTRY cl_int CL_API_CALL
  982. clEnqueueBarrier(cl_command_queue /* command_queue */) CL_API_SUFFIX__VERSION_1_0;
  983.  
  984. /* Extension function access
  985.  *
  986.  * Returns the extension function address for the given function name,
  987.  * or NULL if a valid function can not be found.  The client must
  988.  * check to make sure the address is not NULL, before using or
  989.  * calling the returned function address.
  990.  */
  991. extern CL_API_ENTRY void * CL_API_CALL clGetExtensionFunctionAddress(const char * /* func_name */) CL_API_SUFFIX__VERSION_1_0;
  992.  
  993. #ifdef __cplusplus
  994. }
  995. #endif
  996.  
  997. #endif  /* __OPENCL_CL_H */
  998.  
  999.