ocl_icd.h 33 KB

123456789101112131415161718192021222324252627282930313233343536373839404142434445464748495051525354555657585960616263646566676869707172737475767778798081828384858687888990919293949596979899100101102103104105106107108109110111112113114115116117118119120121122123124125126127128129130131132133134135136137138139140141142143144145146147148149150151152153154155156157158159160161162163164165166167168169170171172173174175176177178179180181182183184185186187188189190191192193194195196197198199200201202203204205206207208209210211212213214215216217218219220221222223224225226227228229230231232233234235236237238239240241242243244245246247248249250251252253254255256257258259260261262263264265266267268269270271272273274275276277278279280281282283284285286287288289290291292293294295296297298299300301302303304305306307308309310311312313314315316317318319320321322323324325326327328329330331332333334335336337338339340341342343344345346347348349350351352353354355356357358359360361362363364365366367368369370371372373374375376377378379380381382383384385386387388389390391392393394395396397398399400401402403404405406407408409410411412413414415416417418419420421422423424425426427428429430431432433434435436437438439440441442443444445446447448449450451452453454455456457458459460461462463464465466467468469470471472473474475476477478479480481482483484485486487488489490491492493494495496497498499500501502503504505506507508509510511512513514515516517518519520521522523524525526527528529530531532533534535536537538539540541542543544545546547548549550551552553554555556557558559560561562563564565566567568569570571572573574575576577578579580581582583584585586587588589590591592593594595596597598599600601602603604605606607608609610611612613614615616617618619620621622623624625626627628629630631632633634635636637638639640641642643644645646647648649650651652653654655656657658659660661662663664665666667668669670671672673674675676677678679680681682683684685686687688689690691692693694695696697698699700701702703704705706707708709710711712713714715716717718719720721722723724725726727728729730731732733734735736737738739740741742743744745746747748749750751752753754755756757758759760761762763764765766767768769770771772773774775776777778779780781782783784785786787788789790791792793794795796797798799800801802803804805806807808809810811812813814815816817818819820821822823824825826827828829830831832833834835836837838839840841842843844845846847848849850851852853854855856857858859860861862863864865866867868869870871872873874875876877878879880881882883884885886887888889890891892893894895896897898899900901902903904905906
  1. /**
  2. Copyright (c) 2012, Brice Videau <brice.videau@imag.fr>
  3. Copyright (c) 2012, Vincent Danjean <Vincent.Danjean@ens-lyon.org>
  4. All rights reserved.
  5. Redistribution and use in source and binary forms, with or without
  6. modification, are permitted provided that the following conditions are met:
  7. 1. Redistributions of source code must retain the above copyright notice, this
  8. list of conditions and the following disclaimer.
  9. 2. Redistributions in binary form must reproduce the above copyright notice,
  10. this list of conditions and the following disclaimer in the documentation
  11. and/or other materials provided with the distribution.
  12. THIS SOFTWARE IS PROVIDED BY THE COPYRIGHT HOLDERS AND CONTRIBUTORS "AS IS" AND
  13. ANY EXPRESS OR IMPLIED WARRANTIES, INCLUDING, BUT NOT LIMITED TO, THE IMPLIED
  14. WARRANTIES OF MERCHANTABILITY AND FITNESS FOR A PARTICULAR PURPOSE ARE
  15. DISCLAIMED. IN NO EVENT SHALL THE COPYRIGHT OWNER OR CONTRIBUTORS BE LIABLE FOR
  16. ANY DIRECT, INDIRECT, INCIDENTAL, SPECIAL, EXEMPLARY, OR CONSEQUENTIAL DAMAGES
  17. (INCLUDING, BUT NOT LIMITED TO, PROCUREMENT OF SUBSTITUTE GOODS OR SERVICES;
  18. LOSS OF USE, DATA, OR PROFITS; OR BUSINESS INTERRUPTION) HOWEVER CAUSED AND
  19. ON ANY THEORY OF LIABILITY, WHETHER IN CONTRACT, STRICT LIABILITY, OR TORT
  20. (INCLUDING NEGLIGENCE OR OTHERWISE) ARISING IN ANY WAY OUT OF THE USE OF THIS
  21. SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE.
  22. Do not edit this file. It is automatically generated.
  23. */
  24. #include "CL/cl.h"
  25. #include "CL/cl_gl.h"
  26. #include "CL/cl_ext.h"
  27. #define OCL_ICD_API_VERSION 1
  28. #define OCL_ICD_IDENTIFIED_FUNCTIONS 102
  29. struct _cl_icd_dispatch {
  30. CL_API_ENTRY cl_int (CL_API_CALL*clGetPlatformIDs)(
  31. cl_uint /* num_entries */,
  32. cl_platform_id * /* platforms */,
  33. cl_uint * /* num_platforms */
  34. ) CL_API_SUFFIX__VERSION_1_0;
  35. CL_API_ENTRY cl_int (CL_API_CALL*
  36. clGetPlatformInfo)(
  37. cl_platform_id /* platform */,
  38. cl_platform_info /* param_name */,
  39. size_t /* param_value_size */,
  40. void * /* param_value */,
  41. size_t * /* param_value_size_ret */
  42. ) CL_API_SUFFIX__VERSION_1_0;
  43. CL_API_ENTRY cl_int (CL_API_CALL*clGetDeviceIDs)(
  44. cl_platform_id /* platform */,
  45. cl_device_type /* device_type */,
  46. cl_uint /* num_entries */,
  47. cl_device_id * /* devices */,
  48. cl_uint * /* num_devices */
  49. ) CL_API_SUFFIX__VERSION_1_0;
  50. CL_API_ENTRY cl_int (CL_API_CALL*clGetDeviceInfo)(
  51. cl_device_id /* device */,
  52. cl_device_info /* param_name */,
  53. size_t /* param_value_size */,
  54. void * /* param_value */,
  55. size_t * /* param_value_size_ret */
  56. ) CL_API_SUFFIX__VERSION_1_0;
  57. CL_API_ENTRY cl_context (CL_API_CALL*clCreateContext)(
  58. const cl_context_properties * /* properties */,
  59. cl_uint /* num_devices */,
  60. const cl_device_id * /* devices */,
  61. void (CL_CALLBACK * /* pfn_notify */)(const char *, const void *, size_t, void *),
  62. void * /* user_data */,
  63. cl_int * /* errcode_ret */
  64. ) CL_API_SUFFIX__VERSION_1_0;
  65. CL_API_ENTRY cl_context (CL_API_CALL*clCreateContextFromType)(
  66. const cl_context_properties * /* properties */,
  67. cl_device_type /* device_type */,
  68. void (CL_CALLBACK * /* pfn_notify*/ )(const char *, const void *, size_t, void *),
  69. void * /* user_data */,
  70. cl_int * /* errcode_ret */
  71. ) CL_API_SUFFIX__VERSION_1_0;
  72. CL_API_ENTRY cl_int (CL_API_CALL*clRetainContext)(
  73. cl_context /* context */
  74. ) CL_API_SUFFIX__VERSION_1_0;
  75. CL_API_ENTRY cl_int (CL_API_CALL*clReleaseContext)(
  76. cl_context /* context */
  77. ) CL_API_SUFFIX__VERSION_1_0;
  78. CL_API_ENTRY cl_int (CL_API_CALL*clGetContextInfo)(
  79. cl_context /* context */,
  80. cl_context_info /* param_name */,
  81. size_t /* param_value_size */,
  82. void * /* param_value */,
  83. size_t * /* param_value_size_ret */
  84. ) CL_API_SUFFIX__VERSION_1_0;
  85. CL_API_ENTRY cl_command_queue (CL_API_CALL*clCreateCommandQueue)(
  86. cl_context /* context */,
  87. cl_device_id /* device */,
  88. cl_command_queue_properties /* properties */,
  89. cl_int * /* errcode_ret */
  90. ) CL_API_SUFFIX__VERSION_1_0;
  91. CL_API_ENTRY cl_int (CL_API_CALL*clRetainCommandQueue)(
  92. cl_command_queue /* command_queue */
  93. ) CL_API_SUFFIX__VERSION_1_0;
  94. CL_API_ENTRY cl_int (CL_API_CALL*clReleaseCommandQueue)(
  95. cl_command_queue /* command_queue */
  96. ) CL_API_SUFFIX__VERSION_1_0;
  97. CL_API_ENTRY cl_int (CL_API_CALL*clGetCommandQueueInfo)(
  98. cl_command_queue /* command_queue */,
  99. cl_command_queue_info /* param_name */,
  100. size_t /* param_value_size */,
  101. void * /* param_value */,
  102. size_t * /* param_value_size_ret */
  103. ) CL_API_SUFFIX__VERSION_1_0;
  104. CL_API_ENTRY cl_int (CL_API_CALL*clSetCommandQueueProperty)(
  105. cl_command_queue /* command_queue */,
  106. cl_command_queue_properties /* properties */,
  107. cl_bool /* enable */,
  108. cl_command_queue_properties * /* old_properties */) CL_EXT_SUFFIX__VERSION_1_0_DEPRECATED;
  109. CL_API_ENTRY cl_mem (CL_API_CALL*clCreateBuffer)(
  110. cl_context /* context */,
  111. cl_mem_flags /* flags */,
  112. size_t /* size */,
  113. void * /* host_ptr */,
  114. cl_int * /* errcode_ret */
  115. ) CL_API_SUFFIX__VERSION_1_0;
  116. CL_API_ENTRY cl_mem (CL_API_CALL*clCreateImage2D)(
  117. cl_context /* context */,
  118. cl_mem_flags /* flags */,
  119. const cl_image_format * /* image_format */,
  120. size_t /* image_width */,
  121. size_t /* image_height */,
  122. size_t /* image_row_pitch */,
  123. void * /* host_ptr */,
  124. cl_int * /* errcode_ret */
  125. ) CL_API_SUFFIX__VERSION_1_0;
  126. CL_API_ENTRY cl_mem (CL_API_CALL*clCreateImage3D)(
  127. cl_context /* context */,
  128. cl_mem_flags /* flags */,
  129. const cl_image_format * /* image_format */,
  130. size_t /* image_width */,
  131. size_t /* image_height */,
  132. size_t /* image_depth */,
  133. size_t /* image_row_pitch */,
  134. size_t /* image_slice_pitch */,
  135. void * /* host_ptr */,
  136. cl_int * /* errcode_ret */
  137. ) CL_API_SUFFIX__VERSION_1_0;
  138. CL_API_ENTRY cl_int (CL_API_CALL*clRetainMemObject)(
  139. cl_mem /* memobj */
  140. ) CL_API_SUFFIX__VERSION_1_0;
  141. CL_API_ENTRY cl_int (CL_API_CALL*clReleaseMemObject)(
  142. cl_mem /* memobj */
  143. ) CL_API_SUFFIX__VERSION_1_0;
  144. CL_API_ENTRY cl_int (CL_API_CALL*clGetSupportedImageFormats)(
  145. cl_context /* context */,
  146. cl_mem_flags /* flags */,
  147. cl_mem_object_type /* image_type */,
  148. cl_uint /* num_entries */,
  149. cl_image_format * /* image_formats */,
  150. cl_uint * /* num_image_formats */
  151. ) CL_API_SUFFIX__VERSION_1_0;
  152. CL_API_ENTRY cl_int (CL_API_CALL*clGetMemObjectInfo)(
  153. cl_mem /* memobj */,
  154. cl_mem_info /* param_name */,
  155. size_t /* param_value_size */,
  156. void * /* param_value */,
  157. size_t * /* param_value_size_ret */
  158. ) CL_API_SUFFIX__VERSION_1_0;
  159. CL_API_ENTRY cl_int (CL_API_CALL*clGetImageInfo)(
  160. cl_mem /* image */,
  161. cl_image_info /* param_name */,
  162. size_t /* param_value_size */,
  163. void * /* param_value */,
  164. size_t * /* param_value_size_ret */
  165. ) CL_API_SUFFIX__VERSION_1_0;
  166. CL_API_ENTRY cl_sampler (CL_API_CALL*clCreateSampler)(
  167. cl_context /* context */,
  168. cl_bool /* normalized_coords */,
  169. cl_addressing_mode /* addressing_mode */,
  170. cl_filter_mode /* filter_mode */,
  171. cl_int * /* errcode_ret */
  172. ) CL_API_SUFFIX__VERSION_1_0;
  173. CL_API_ENTRY cl_int (CL_API_CALL*clRetainSampler)(
  174. cl_sampler /* sampler */
  175. ) CL_API_SUFFIX__VERSION_1_0;
  176. CL_API_ENTRY cl_int (CL_API_CALL*clReleaseSampler)(
  177. cl_sampler /* sampler */
  178. ) CL_API_SUFFIX__VERSION_1_0;
  179. CL_API_ENTRY cl_int (CL_API_CALL*clGetSamplerInfo)(
  180. cl_sampler /* sampler */,
  181. cl_sampler_info /* param_name */,
  182. size_t /* param_value_size */,
  183. void * /* param_value */,
  184. size_t * /* param_value_size_ret */
  185. ) CL_API_SUFFIX__VERSION_1_0;
  186. CL_API_ENTRY cl_program (CL_API_CALL*clCreateProgramWithSource)(
  187. cl_context /* context */,
  188. cl_uint /* count */,
  189. const char ** /* strings */,
  190. const size_t * /* lengths */,
  191. cl_int * /* errcode_ret */
  192. ) CL_API_SUFFIX__VERSION_1_0;
  193. CL_API_ENTRY cl_program (CL_API_CALL*clCreateProgramWithBinary)(
  194. cl_context /* context */,
  195. cl_uint /* num_devices */,
  196. const cl_device_id * /* device_list */,
  197. const size_t * /* lengths */,
  198. const unsigned char ** /* binaries */,
  199. cl_int * /* binary_status */,
  200. cl_int * /* errcode_ret */
  201. ) CL_API_SUFFIX__VERSION_1_0;
  202. CL_API_ENTRY cl_int (CL_API_CALL*clRetainProgram)(
  203. cl_program /* program */
  204. ) CL_API_SUFFIX__VERSION_1_0;
  205. CL_API_ENTRY cl_int (CL_API_CALL*clReleaseProgram)(
  206. cl_program /* program */
  207. ) CL_API_SUFFIX__VERSION_1_0;
  208. CL_API_ENTRY cl_int (CL_API_CALL*clBuildProgram)(
  209. cl_program /* program */,
  210. cl_uint /* num_devices */,
  211. const cl_device_id * /* device_list */,
  212. const char * /* options */,
  213. void (CL_CALLBACK * /* pfn_notify */)(cl_program /* program */, void * /* user_data */),
  214. void * /* user_data */
  215. ) CL_API_SUFFIX__VERSION_1_0;
  216. CL_API_ENTRY cl_int (CL_API_CALL*clUnloadCompiler)(
  217. void
  218. ) CL_API_SUFFIX__VERSION_1_0;
  219. CL_API_ENTRY cl_int (CL_API_CALL*clGetProgramInfo)(
  220. cl_program /* program */,
  221. cl_program_info /* param_name */,
  222. size_t /* param_value_size */,
  223. void * /* param_value */,
  224. size_t * /* param_value_size_ret */
  225. ) CL_API_SUFFIX__VERSION_1_0;
  226. CL_API_ENTRY cl_int (CL_API_CALL*clGetProgramBuildInfo)(
  227. cl_program /* program */,
  228. cl_device_id /* device */,
  229. cl_program_build_info /* param_name */,
  230. size_t /* param_value_size */,
  231. void * /* param_value */,
  232. size_t * /* param_value_size_ret */
  233. ) CL_API_SUFFIX__VERSION_1_0;
  234. CL_API_ENTRY cl_kernel (CL_API_CALL*clCreateKernel)(
  235. cl_program /* program */,
  236. const char * /* kernel_name */,
  237. cl_int * /* errcode_ret */
  238. ) CL_API_SUFFIX__VERSION_1_0;
  239. CL_API_ENTRY cl_int (CL_API_CALL*clCreateKernelsInProgram)(
  240. cl_program /* program */,
  241. cl_uint /* num_kernels */,
  242. cl_kernel * /* kernels */,
  243. cl_uint * /* num_kernels_ret */
  244. ) CL_API_SUFFIX__VERSION_1_0;
  245. CL_API_ENTRY cl_int (CL_API_CALL*clRetainKernel)(
  246. cl_kernel /* kernel */
  247. ) CL_API_SUFFIX__VERSION_1_0;
  248. CL_API_ENTRY cl_int (CL_API_CALL*clReleaseKernel)(
  249. cl_kernel /* kernel */
  250. ) CL_API_SUFFIX__VERSION_1_0;
  251. CL_API_ENTRY cl_int (CL_API_CALL*clSetKernelArg)(
  252. cl_kernel /* kernel */,
  253. cl_uint /* arg_index */,
  254. size_t /* arg_size */,
  255. const void * /* arg_value */
  256. ) CL_API_SUFFIX__VERSION_1_0;
  257. CL_API_ENTRY cl_int (CL_API_CALL*clGetKernelInfo)(
  258. cl_kernel /* kernel */,
  259. cl_kernel_info /* param_name */,
  260. size_t /* param_value_size */,
  261. void * /* param_value */,
  262. size_t * /* param_value_size_ret */
  263. ) CL_API_SUFFIX__VERSION_1_0;
  264. CL_API_ENTRY cl_int (CL_API_CALL*clGetKernelWorkGroupInfo)(
  265. cl_kernel /* kernel */,
  266. cl_device_id /* device */,
  267. cl_kernel_work_group_info /* param_name */,
  268. size_t /* param_value_size */,
  269. void * /* param_value */,
  270. size_t * /* param_value_size_ret */
  271. ) CL_API_SUFFIX__VERSION_1_0;
  272. CL_API_ENTRY cl_int (CL_API_CALL*clWaitForEvents)(
  273. cl_uint /* num_events */,
  274. const cl_event * /* event_list */
  275. ) CL_API_SUFFIX__VERSION_1_0;
  276. CL_API_ENTRY cl_int (CL_API_CALL*clGetEventInfo)(
  277. cl_event /* event */,
  278. cl_event_info /* param_name */,
  279. size_t /* param_value_size */,
  280. void * /* param_value */,
  281. size_t * /* param_value_size_ret */
  282. ) CL_API_SUFFIX__VERSION_1_0;
  283. CL_API_ENTRY cl_int (CL_API_CALL*clRetainEvent)(
  284. cl_event /* event */
  285. ) CL_API_SUFFIX__VERSION_1_0;
  286. CL_API_ENTRY cl_int (CL_API_CALL*clReleaseEvent)(
  287. cl_event /* event */
  288. ) CL_API_SUFFIX__VERSION_1_0;
  289. CL_API_ENTRY cl_int (CL_API_CALL*clGetEventProfilingInfo)(
  290. cl_event /* event */,
  291. cl_profiling_info /* param_name */,
  292. size_t /* param_value_size */,
  293. void * /* param_value */,
  294. size_t * /* param_value_size_ret */
  295. ) CL_API_SUFFIX__VERSION_1_0;
  296. CL_API_ENTRY cl_int (CL_API_CALL*clFlush)(
  297. cl_command_queue /* command_queue */
  298. ) CL_API_SUFFIX__VERSION_1_0;
  299. CL_API_ENTRY cl_int (CL_API_CALL*clFinish)(
  300. cl_command_queue /* command_queue */
  301. ) CL_API_SUFFIX__VERSION_1_0;
  302. CL_API_ENTRY cl_int (CL_API_CALL*clEnqueueReadBuffer)(
  303. cl_command_queue /* command_queue */,
  304. cl_mem /* buffer */,
  305. cl_bool /* blocking_read */,
  306. size_t /* offset */,
  307. size_t /* cb */,
  308. void * /* ptr */,
  309. cl_uint /* num_events_in_wait_list */,
  310. const cl_event * /* event_wait_list */,
  311. cl_event * /* event */
  312. ) CL_API_SUFFIX__VERSION_1_0;
  313. CL_API_ENTRY cl_int (CL_API_CALL*clEnqueueWriteBuffer)(
  314. cl_command_queue /* command_queue */,
  315. cl_mem /* buffer */,
  316. cl_bool /* blocking_write */,
  317. size_t /* offset */,
  318. size_t /* cb */,
  319. const void * /* ptr */,
  320. cl_uint /* num_events_in_wait_list */,
  321. const cl_event * /* event_wait_list */,
  322. cl_event * /* event */
  323. ) CL_API_SUFFIX__VERSION_1_0;
  324. CL_API_ENTRY cl_int (CL_API_CALL*clEnqueueCopyBuffer)(
  325. cl_command_queue /* command_queue */,
  326. cl_mem /* src_buffer */,
  327. cl_mem /* dst_buffer */,
  328. size_t /* src_offset */,
  329. size_t /* dst_offset */,
  330. size_t /* cb */,
  331. cl_uint /* num_events_in_wait_list */,
  332. const cl_event * /* event_wait_list */,
  333. cl_event * /* event */
  334. ) CL_API_SUFFIX__VERSION_1_0;
  335. CL_API_ENTRY cl_int (CL_API_CALL*clEnqueueReadImage)(
  336. cl_command_queue /* command_queue */,
  337. cl_mem /* image */,
  338. cl_bool /* blocking_read */,
  339. const size_t * /* origin[3] */,
  340. const size_t * /* region[3] */,
  341. size_t /* row_pitch */,
  342. size_t /* slice_pitch */,
  343. void * /* ptr */,
  344. cl_uint /* num_events_in_wait_list */,
  345. const cl_event * /* event_wait_list */,
  346. cl_event * /* event */
  347. ) CL_API_SUFFIX__VERSION_1_0;
  348. CL_API_ENTRY cl_int (CL_API_CALL*clEnqueueWriteImage)(
  349. cl_command_queue /* command_queue */,
  350. cl_mem /* image */,
  351. cl_bool /* blocking_write */,
  352. const size_t * /* origin[3] */,
  353. const size_t * /* region[3] */,
  354. size_t /* input_row_pitch */,
  355. size_t /* input_slice_pitch */,
  356. const void * /* ptr */,
  357. cl_uint /* num_events_in_wait_list */,
  358. const cl_event * /* event_wait_list */,
  359. cl_event * /* event */
  360. ) CL_API_SUFFIX__VERSION_1_0;
  361. CL_API_ENTRY cl_int (CL_API_CALL*clEnqueueCopyImage)(
  362. cl_command_queue /* command_queue */,
  363. cl_mem /* src_image */,
  364. cl_mem /* dst_image */,
  365. const size_t * /* src_origin[3] */,
  366. const size_t * /* dst_origin[3] */,
  367. const size_t * /* region[3] */,
  368. cl_uint /* num_events_in_wait_list */,
  369. const cl_event * /* event_wait_list */,
  370. cl_event * /* event */
  371. ) CL_API_SUFFIX__VERSION_1_0;
  372. CL_API_ENTRY cl_int (CL_API_CALL*clEnqueueCopyImageToBuffer)(
  373. cl_command_queue /* command_queue */,
  374. cl_mem /* src_image */,
  375. cl_mem /* dst_buffer */,
  376. const size_t * /* src_origin[3] */,
  377. const size_t * /* region[3] */,
  378. size_t /* dst_offset */,
  379. cl_uint /* num_events_in_wait_list */,
  380. const cl_event * /* event_wait_list */,
  381. cl_event * /* event */
  382. ) CL_API_SUFFIX__VERSION_1_0;
  383. CL_API_ENTRY cl_int (CL_API_CALL*clEnqueueCopyBufferToImage)(
  384. cl_command_queue /* command_queue */,
  385. cl_mem /* src_buffer */,
  386. cl_mem /* dst_image */,
  387. size_t /* src_offset */,
  388. const size_t * /* dst_origin[3] */,
  389. const size_t * /* region[3] */,
  390. cl_uint /* num_events_in_wait_list */,
  391. const cl_event * /* event_wait_list */,
  392. cl_event * /* event */
  393. ) CL_API_SUFFIX__VERSION_1_0;
  394. CL_API_ENTRY void * (CL_API_CALL*clEnqueueMapBuffer)(
  395. cl_command_queue /* command_queue */,
  396. cl_mem /* buffer */,
  397. cl_bool /* blocking_map */,
  398. cl_map_flags /* map_flags */,
  399. size_t /* offset */,
  400. size_t /* cb */,
  401. cl_uint /* num_events_in_wait_list */,
  402. const cl_event * /* event_wait_list */,
  403. cl_event * /* event */,
  404. cl_int * /* errcode_ret */
  405. ) CL_API_SUFFIX__VERSION_1_0;
  406. CL_API_ENTRY void * (CL_API_CALL*clEnqueueMapImage)(
  407. cl_command_queue /* command_queue */,
  408. cl_mem /* image */,
  409. cl_bool /* blocking_map */,
  410. cl_map_flags /* map_flags */,
  411. const size_t * /* origin[3] */,
  412. const size_t * /* region[3] */,
  413. size_t * /* image_row_pitch */,
  414. size_t * /* image_slice_pitch */,
  415. cl_uint /* num_events_in_wait_list */,
  416. const cl_event * /* event_wait_list */,
  417. cl_event * /* event */,
  418. cl_int * /* errcode_ret */
  419. ) CL_API_SUFFIX__VERSION_1_0;
  420. CL_API_ENTRY cl_int (CL_API_CALL*clEnqueueUnmapMemObject)(
  421. cl_command_queue /* command_queue */,
  422. cl_mem /* memobj */,
  423. void * /* mapped_ptr */,
  424. cl_uint /* num_events_in_wait_list */,
  425. const cl_event * /* event_wait_list */,
  426. cl_event * /* event */
  427. ) CL_API_SUFFIX__VERSION_1_0;
  428. CL_API_ENTRY cl_int (CL_API_CALL*clEnqueueNDRangeKernel)(
  429. cl_command_queue /* command_queue */,
  430. cl_kernel /* kernel */,
  431. cl_uint /* work_dim */,
  432. const size_t * /* global_work_offset */,
  433. const size_t * /* global_work_size */,
  434. const size_t * /* local_work_size */,
  435. cl_uint /* num_events_in_wait_list */,
  436. const cl_event * /* event_wait_list */,
  437. cl_event * /* event */
  438. ) CL_API_SUFFIX__VERSION_1_0;
  439. CL_API_ENTRY cl_int (CL_API_CALL*clEnqueueTask)(
  440. cl_command_queue /* command_queue */,
  441. cl_kernel /* kernel */,
  442. cl_uint /* num_events_in_wait_list */,
  443. const cl_event * /* event_wait_list */,
  444. cl_event * /* event */
  445. ) CL_API_SUFFIX__VERSION_1_0;
  446. CL_API_ENTRY cl_int (CL_API_CALL*clEnqueueNativeKernel)(
  447. cl_command_queue /* command_queue */,
  448. void (*user_func)(void *),
  449. void * /* args */,
  450. size_t /* cb_args */,
  451. cl_uint /* num_mem_objects */,
  452. const cl_mem * /* mem_list */,
  453. const void ** /* args_mem_loc */,
  454. cl_uint /* num_events_in_wait_list */,
  455. const cl_event * /* event_wait_list */,
  456. cl_event * /* event */
  457. ) CL_API_SUFFIX__VERSION_1_0;
  458. CL_API_ENTRY cl_int (CL_API_CALL*clEnqueueMarker)(
  459. cl_command_queue /* command_queue */,
  460. cl_event * /* event */
  461. ) CL_API_SUFFIX__VERSION_1_0;
  462. CL_API_ENTRY cl_int (CL_API_CALL*clEnqueueWaitForEvents)(
  463. cl_command_queue /* command_queue */,
  464. cl_uint /* num_events */,
  465. const cl_event * /* event_list */
  466. ) CL_API_SUFFIX__VERSION_1_0;
  467. CL_API_ENTRY cl_int (CL_API_CALL*clEnqueueBarrier)(
  468. cl_command_queue /* command_queue */
  469. ) CL_API_SUFFIX__VERSION_1_0;
  470. CL_API_ENTRY void * (CL_API_CALL*clGetExtensionFunctionAddress)(
  471. const char * /* func_name */
  472. ) CL_API_SUFFIX__VERSION_1_0;
  473. CL_API_ENTRY cl_mem (CL_API_CALL*clCreateFromGLBuffer)(
  474. cl_context /* context */,
  475. cl_mem_flags /* flags */,
  476. cl_GLuint /* bufobj */,
  477. int * /* errcode_ret */
  478. ) CL_API_SUFFIX__VERSION_1_0;
  479. CL_API_ENTRY cl_mem (CL_API_CALL*clCreateFromGLTexture2D)(
  480. cl_context /* context */,
  481. cl_mem_flags /* flags */,
  482. cl_GLenum /* target */,
  483. cl_GLint /* miplevel */,
  484. cl_GLuint /* texture */,
  485. cl_int * /* errcode_ret */
  486. ) CL_API_SUFFIX__VERSION_1_0;
  487. CL_API_ENTRY cl_mem (CL_API_CALL*clCreateFromGLTexture3D)(
  488. cl_context /* context */,
  489. cl_mem_flags /* flags */,
  490. cl_GLenum /* target */,
  491. cl_GLint /* miplevel */,
  492. cl_GLuint /* texture */,
  493. cl_int * /* errcode_ret */
  494. ) CL_API_SUFFIX__VERSION_1_0;
  495. CL_API_ENTRY cl_mem (CL_API_CALL*clCreateFromGLRenderbuffer)(
  496. cl_context /* context */,
  497. cl_mem_flags /* flags */,
  498. cl_GLuint /* renderbuffer */,
  499. cl_int * /* errcode_ret */
  500. ) CL_API_SUFFIX__VERSION_1_0;
  501. CL_API_ENTRY cl_int (CL_API_CALL*clGetGLObjectInfo)(
  502. cl_mem /* memobj */,
  503. cl_gl_object_type * /* gl_object_type */,
  504. cl_GLuint * /* gl_object_name */
  505. ) CL_API_SUFFIX__VERSION_1_0;
  506. CL_API_ENTRY cl_int (CL_API_CALL*clGetGLTextureInfo)(
  507. cl_mem /* memobj */,
  508. cl_gl_texture_info /* param_name */,
  509. size_t /* param_value_size */,
  510. void * /* param_value */,
  511. size_t * /* param_value_size_ret */
  512. ) CL_API_SUFFIX__VERSION_1_0;
  513. CL_API_ENTRY cl_int (CL_API_CALL*clEnqueueAcquireGLObjects)(
  514. cl_command_queue /* command_queue */,
  515. cl_uint /* num_objects */,
  516. const cl_mem * /* mem_objects */,
  517. cl_uint /* num_events_in_wait_list */,
  518. const cl_event * /* event_wait_list */,
  519. cl_event * /* event */
  520. ) CL_API_SUFFIX__VERSION_1_0;
  521. CL_API_ENTRY cl_int (CL_API_CALL*clEnqueueReleaseGLObjects)(
  522. cl_command_queue /* command_queue */,
  523. cl_uint /* num_objects */,
  524. const cl_mem * /* mem_objects */,
  525. cl_uint /* num_events_in_wait_list */,
  526. const cl_event * /* event_wait_list */,
  527. cl_event * /* event */
  528. ) CL_API_SUFFIX__VERSION_1_0;
  529. CL_API_ENTRY cl_int (CL_API_CALL*clGetGLContextInfoKHR)(
  530. const cl_context_properties * /* properties */,
  531. cl_gl_context_info /* param_name */,
  532. size_t /* param_value_size */,
  533. void * /* param_value */,
  534. size_t * /* param_value_size_ret */
  535. ) CL_API_SUFFIX__VERSION_1_0;
  536. CL_API_ENTRY cl_int (CL_API_CALL* clUnknown75)(
  537. void);
  538. CL_API_ENTRY cl_int (CL_API_CALL* clUnknown76)(
  539. void);
  540. CL_API_ENTRY cl_int (CL_API_CALL* clUnknown77)(
  541. void);
  542. CL_API_ENTRY cl_int (CL_API_CALL* clUnknown78)(
  543. void);
  544. CL_API_ENTRY cl_int (CL_API_CALL* clUnknown79)(
  545. void);
  546. CL_API_ENTRY cl_int (CL_API_CALL* clUnknown80)(
  547. void);
  548. CL_API_ENTRY cl_int (CL_API_CALL*clSetEventCallback)(
  549. cl_event /* event */,
  550. cl_int /* command_exec_callback_type */,
  551. void (CL_CALLBACK * /* pfn_notify */)(cl_event, cl_int, void *),
  552. void * /* user_data */
  553. ) CL_API_SUFFIX__VERSION_1_1;
  554. CL_API_ENTRY cl_mem (CL_API_CALL*clCreateSubBuffer)(
  555. cl_mem /* buffer */,
  556. cl_mem_flags /* flags */,
  557. cl_buffer_create_type /* buffer_create_type */,
  558. const void * /* buffer_create_info */,
  559. cl_int * /* errcode_ret */
  560. ) CL_API_SUFFIX__VERSION_1_1;
  561. CL_API_ENTRY cl_int (CL_API_CALL*clSetMemObjectDestructorCallback)(
  562. cl_mem /* memobj */,
  563. void (CL_CALLBACK * /*pfn_notify*/)( cl_mem /* memobj */, void* /*user_data*/),
  564. void * /*user_data */ ) CL_API_SUFFIX__VERSION_1_1;
  565. CL_API_ENTRY cl_event (CL_API_CALL*clCreateUserEvent)(
  566. cl_context /* context */,
  567. cl_int * /* errcode_ret */
  568. ) CL_API_SUFFIX__VERSION_1_1;
  569. CL_API_ENTRY cl_int (CL_API_CALL*clSetUserEventStatus)(
  570. cl_event /* event */,
  571. cl_int /* execution_status */
  572. ) CL_API_SUFFIX__VERSION_1_1;
  573. CL_API_ENTRY cl_int (CL_API_CALL*clEnqueueReadBufferRect)(
  574. cl_command_queue /* command_queue */,
  575. cl_mem /* buffer */,
  576. cl_bool /* blocking_read */,
  577. const size_t * /* buffer_origin */,
  578. const size_t * /* host_origin */,
  579. const size_t * /* region */,
  580. size_t /* buffer_row_pitch */,
  581. size_t /* buffer_slice_pitch */,
  582. size_t /* host_row_pitch */,
  583. size_t /* host_slice_pitch */,
  584. void * /* ptr */,
  585. cl_uint /* num_events_in_wait_list */,
  586. const cl_event * /* event_wait_list */,
  587. cl_event * /* event */
  588. ) CL_API_SUFFIX__VERSION_1_1;
  589. CL_API_ENTRY cl_int (CL_API_CALL*clEnqueueWriteBufferRect)(
  590. cl_command_queue /* command_queue */,
  591. cl_mem /* buffer */,
  592. cl_bool /* blocking_write */,
  593. const size_t * /* buffer_origin */,
  594. const size_t * /* host_origin */,
  595. const size_t * /* region */,
  596. size_t /* buffer_row_pitch */,
  597. size_t /* buffer_slice_pitch */,
  598. size_t /* host_row_pitch */,
  599. size_t /* host_slice_pitch */,
  600. const void * /* ptr */,
  601. cl_uint /* num_events_in_wait_list */,
  602. const cl_event * /* event_wait_list */,
  603. cl_event * /* event */
  604. ) CL_API_SUFFIX__VERSION_1_1;
  605. CL_API_ENTRY cl_int (CL_API_CALL*clEnqueueCopyBufferRect)(
  606. cl_command_queue /* command_queue */,
  607. cl_mem /* src_buffer */,
  608. cl_mem /* dst_buffer */,
  609. const size_t * /* src_origin */,
  610. const size_t * /* dst_origin */,
  611. const size_t * /* region */,
  612. size_t /* src_row_pitch */,
  613. size_t /* src_slice_pitch */,
  614. size_t /* dst_row_pitch */,
  615. size_t /* dst_slice_pitch */,
  616. cl_uint /* num_events_in_wait_list */,
  617. const cl_event * /* event_wait_list */,
  618. cl_event * /* event */
  619. ) CL_API_SUFFIX__VERSION_1_1;
  620. CL_API_ENTRY cl_int (CL_API_CALL* clCreateSubDevicesEXT)(
  621. cl_device_id /*in_device*/,
  622. const cl_device_partition_property_ext * /* properties */,
  623. cl_uint /*num_entries*/,
  624. cl_device_id * /*out_devices*/,
  625. cl_uint * /*num_devices*/ ) CL_EXT_SUFFIX__VERSION_1_1;
  626. CL_API_ENTRY cl_int (CL_API_CALL* clRetainDeviceEXT)(
  627. cl_device_id /*device*/ ) CL_EXT_SUFFIX__VERSION_1_1;
  628. CL_API_ENTRY cl_int (CL_API_CALL* clReleaseDeviceEXT)(
  629. cl_device_id /*device*/ ) CL_EXT_SUFFIX__VERSION_1_1;
  630. CL_API_ENTRY cl_int (CL_API_CALL* clUnknown92)(
  631. void);
  632. CL_API_ENTRY cl_int (CL_API_CALL*clCreateSubDevices)(
  633. cl_device_id /* in_device */,
  634. const cl_device_partition_property * /* properties */,
  635. cl_uint /* num_devices */,
  636. cl_device_id * /* out_devices */,
  637. cl_uint * /* num_devices_ret */
  638. ) CL_API_SUFFIX__VERSION_1_2;
  639. CL_API_ENTRY cl_int (CL_API_CALL*clRetainDevice)(
  640. cl_device_id /* device */
  641. ) CL_API_SUFFIX__VERSION_1_2;
  642. CL_API_ENTRY cl_int (CL_API_CALL*clReleaseDevice)(
  643. cl_device_id /* device */
  644. ) CL_API_SUFFIX__VERSION_1_2;
  645. CL_API_ENTRY cl_mem (CL_API_CALL*clCreateImage)(
  646. cl_context /* context */,
  647. cl_mem_flags /* flags */,
  648. const cl_image_format * /* image_format */,
  649. const cl_image_desc * /* image_desc */,
  650. void * /* host_ptr */,
  651. cl_int * /* errcode_ret */
  652. ) CL_API_SUFFIX__VERSION_1_2;
  653. CL_API_ENTRY cl_program (CL_API_CALL*clCreateProgramWithBuiltInKernels)(
  654. cl_context /* context */,
  655. cl_uint /* num_devices */,
  656. const cl_device_id * /* device_list */,
  657. const char * /* kernel_names */,
  658. cl_int * /* errcode_ret */
  659. ) CL_API_SUFFIX__VERSION_1_2;
  660. CL_API_ENTRY cl_int (CL_API_CALL*clCompileProgram)(
  661. cl_program /* program */,
  662. cl_uint /* num_devices */,
  663. const cl_device_id * /* device_list */,
  664. const char * /* options */,
  665. cl_uint /* num_input_headers */,
  666. const cl_program * /* input_headers */,
  667. const char ** /* header_include_names */,
  668. void (CL_CALLBACK * /* pfn_notify */)(cl_program /* program */, void * /* user_data */),
  669. void * /* user_data */
  670. ) CL_API_SUFFIX__VERSION_1_2;
  671. CL_API_ENTRY cl_program (CL_API_CALL*clLinkProgram)(
  672. cl_context /* context */,
  673. cl_uint /* num_devices */,
  674. const cl_device_id * /* device_list */,
  675. const char * /* options */,
  676. cl_uint /* num_input_programs */,
  677. const cl_program * /* input_programs */,
  678. void (CL_CALLBACK * /* pfn_notify */)(cl_program /* program */, void * /* user_data */),
  679. void * /* user_data */,
  680. cl_int * /* errcode_ret */
  681. ) CL_API_SUFFIX__VERSION_1_2;
  682. CL_API_ENTRY cl_int (CL_API_CALL*clUnloadPlatformCompiler)(
  683. cl_platform_id /* platform */
  684. ) CL_API_SUFFIX__VERSION_1_2;
  685. CL_API_ENTRY cl_int (CL_API_CALL*clGetKernelArgInfo)(
  686. cl_kernel /* kernel */,
  687. cl_uint /* arg_indx */,
  688. cl_kernel_arg_info /* param_name */,
  689. size_t /* param_value_size */,
  690. void * /* param_value */,
  691. size_t * /* param_value_size_ret */
  692. ) CL_API_SUFFIX__VERSION_1_2;
  693. CL_API_ENTRY cl_int (CL_API_CALL*clEnqueueFillBuffer)(
  694. cl_command_queue /* command_queue */,
  695. cl_mem /* buffer */,
  696. const void * /* pattern */,
  697. size_t /* pattern_size */,
  698. size_t /* offset */,
  699. size_t /* size */,
  700. cl_uint /* num_events_in_wait_list */,
  701. const cl_event * /* event_wait_list */,
  702. cl_event * /* event */
  703. ) CL_API_SUFFIX__VERSION_1_2;
  704. CL_API_ENTRY cl_int (CL_API_CALL*clEnqueueFillImage)(
  705. cl_command_queue /* command_queue */,
  706. cl_mem /* image */,
  707. const void * /* fill_color */,
  708. const size_t * /* origin[3] */,
  709. const size_t * /* region[3] */,
  710. cl_uint /* num_events_in_wait_list */,
  711. const cl_event * /* event_wait_list */,
  712. cl_event * /* event */
  713. ) CL_API_SUFFIX__VERSION_1_2;
  714. CL_API_ENTRY cl_int (CL_API_CALL*clEnqueueMigrateMemObjects)(
  715. cl_command_queue /* command_queue */,
  716. cl_uint /* num_mem_objects */,
  717. const cl_mem * /* mem_objects */,
  718. cl_mem_migration_flags /* flags */,
  719. cl_uint /* num_events_in_wait_list */,
  720. const cl_event * /* event_wait_list */,
  721. cl_event * /* event */
  722. ) CL_API_SUFFIX__VERSION_1_2;
  723. CL_API_ENTRY cl_int (CL_API_CALL*clEnqueueMarkerWithWaitList)(
  724. cl_command_queue /* command_queue */,
  725. cl_uint /* num_events_in_wait_list */,
  726. const cl_event * /* event_wait_list */,
  727. cl_event * /* event */
  728. ) CL_API_SUFFIX__VERSION_1_2;
  729. CL_API_ENTRY cl_int (CL_API_CALL*clEnqueueBarrierWithWaitList)(
  730. cl_command_queue /* command_queue */,
  731. cl_uint /* num_events_in_wait_list */,
  732. const cl_event * /* event_wait_list */,
  733. cl_event * /* event */
  734. ) CL_API_SUFFIX__VERSION_1_2;
  735. CL_API_ENTRY void * (CL_API_CALL*
  736. clGetExtensionFunctionAddressForPlatform)(
  737. cl_platform_id /* platform */,
  738. const char * /* func_name */
  739. ) CL_API_SUFFIX__VERSION_1_2;
  740. CL_API_ENTRY cl_mem (CL_API_CALL*clCreateFromGLTexture)(
  741. cl_context /* context */,
  742. cl_mem_flags /* flags */,
  743. cl_GLenum /* target */,
  744. cl_GLint /* miplevel */,
  745. cl_GLuint /* texture */,
  746. cl_int * /* errcode_ret */
  747. ) CL_API_SUFFIX__VERSION_1_2;
  748. CL_API_ENTRY cl_int (CL_API_CALL* clUnknown109)(
  749. void);
  750. CL_API_ENTRY cl_int (CL_API_CALL* clUnknown110)(
  751. void);
  752. CL_API_ENTRY cl_int (CL_API_CALL* clUnknown111)(
  753. void);
  754. CL_API_ENTRY cl_int (CL_API_CALL* clUnknown112)(
  755. void);
  756. CL_API_ENTRY cl_int (CL_API_CALL* clUnknown113)(
  757. void);
  758. CL_API_ENTRY cl_int (CL_API_CALL* clUnknown114)(
  759. void);
  760. CL_API_ENTRY cl_int (CL_API_CALL* clUnknown115)(
  761. void);
  762. CL_API_ENTRY cl_int (CL_API_CALL* clUnknown116)(
  763. void);
  764. CL_API_ENTRY cl_int (CL_API_CALL* clUnknown117)(
  765. void);
  766. CL_API_ENTRY cl_int (CL_API_CALL* clUnknown118)(
  767. void);
  768. CL_API_ENTRY cl_int (CL_API_CALL* clUnknown119)(
  769. void);
  770. CL_API_ENTRY cl_int (CL_API_CALL* clUnknown120)(
  771. void);
  772. CL_API_ENTRY cl_int (CL_API_CALL* clUnknown121)(
  773. void);
  774. };