cl.h@ 105856

最後變更在這個檔案從105856是 103996,由 vboxsync 提交於 11 月前
Additions/3D/mesa: export mesa-24.0.2 to OSE. bugref:10606
屬性 svn:eol-style 設為 `native`
檔案大小: 79.7 KB

行
1	/*******************************************************************************
2	* Copyright (c) 2008-2020 The Khronos Group Inc.
3	*
4	* Licensed under the Apache License, Version 2.0 (the "License");
5	* you may not use this file except in compliance with the License.
6	* You may obtain a copy of the License at
7	*
8	* http://www.apache.org/licenses/LICENSE-2.0
9	*
10	* Unless required by applicable law or agreed to in writing, software
11	* distributed under the License is distributed on an "AS IS" BASIS,
12	* WITHOUT WARRANTIES OR CONDITIONS OF ANY KIND, either express or implied.
13	* See the License for the specific language governing permissions and
14	* limitations under the License.
15	******************************************************************************/
16
17	#ifndef __OPENCL_CL_H
18	#define __OPENCL_CL_H
19
20	#include <CL/cl_version.h>
21	#include <CL/cl_platform.h>
22
23	#ifdef __cplusplus
24	extern "C" {
25	#endif
26
27	/******************************************************************************/
28
29	typedef struct _cl_platform_id * cl_platform_id;
30	typedef struct _cl_device_id * cl_device_id;
31	typedef struct _cl_context * cl_context;
32	typedef struct _cl_command_queue * cl_command_queue;
33	typedef struct _cl_mem * cl_mem;
34	typedef struct _cl_program * cl_program;
35	typedef struct _cl_kernel * cl_kernel;
36	typedef struct _cl_event * cl_event;
37	typedef struct _cl_sampler * cl_sampler;
38
39	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. */
40	typedef cl_ulong cl_bitfield;
41	typedef cl_ulong cl_properties;
42	typedef cl_bitfield cl_device_type;
43	typedef cl_uint cl_platform_info;
44	typedef cl_uint cl_device_info;
45	typedef cl_bitfield cl_device_fp_config;
46	typedef cl_uint cl_device_mem_cache_type;
47	typedef cl_uint cl_device_local_mem_type;
48	typedef cl_bitfield cl_device_exec_capabilities;
49	#ifdef CL_VERSION_2_0
50	typedef cl_bitfield cl_device_svm_capabilities;
51	#endif
52	typedef cl_bitfield cl_command_queue_properties;
53	#ifdef CL_VERSION_1_2
54	typedef intptr_t cl_device_partition_property;
55	typedef cl_bitfield cl_device_affinity_domain;
56	#endif
57
58	typedef intptr_t cl_context_properties;
59	typedef cl_uint cl_context_info;
60	#ifdef CL_VERSION_2_0
61	typedef cl_properties cl_queue_properties;
62	#endif
63	typedef cl_uint cl_command_queue_info;
64	typedef cl_uint cl_channel_order;
65	typedef cl_uint cl_channel_type;
66	typedef cl_bitfield cl_mem_flags;
67	#ifdef CL_VERSION_2_0
68	typedef cl_bitfield cl_svm_mem_flags;
69	#endif
70	typedef cl_uint cl_mem_object_type;
71	typedef cl_uint cl_mem_info;
72	#ifdef CL_VERSION_1_2
73	typedef cl_bitfield cl_mem_migration_flags;
74	#endif
75	typedef cl_uint cl_image_info;
76	#ifdef CL_VERSION_1_1
77	typedef cl_uint cl_buffer_create_type;
78	#endif
79	typedef cl_uint cl_addressing_mode;
80	typedef cl_uint cl_filter_mode;
81	typedef cl_uint cl_sampler_info;
82	typedef cl_bitfield cl_map_flags;
83	#ifdef CL_VERSION_2_0
84	typedef intptr_t cl_pipe_properties;
85	typedef cl_uint cl_pipe_info;
86	#endif
87	typedef cl_uint cl_program_info;
88	typedef cl_uint cl_program_build_info;
89	#ifdef CL_VERSION_1_2
90	typedef cl_uint cl_program_binary_type;
91	#endif
92	typedef cl_int cl_build_status;
93	typedef cl_uint cl_kernel_info;
94	#ifdef CL_VERSION_1_2
95	typedef cl_uint cl_kernel_arg_info;
96	typedef cl_uint cl_kernel_arg_address_qualifier;
97	typedef cl_uint cl_kernel_arg_access_qualifier;
98	typedef cl_bitfield cl_kernel_arg_type_qualifier;
99	#endif
100	typedef cl_uint cl_kernel_work_group_info;
101	#ifdef CL_VERSION_2_1
102	typedef cl_uint cl_kernel_sub_group_info;
103	#endif
104	typedef cl_uint cl_event_info;
105	typedef cl_uint cl_command_type;
106	typedef cl_uint cl_profiling_info;
107	#ifdef CL_VERSION_2_0
108	typedef cl_properties cl_sampler_properties;
109	typedef cl_uint cl_kernel_exec_info;
110	#endif
111	#ifdef CL_VERSION_3_0
112	typedef cl_bitfield cl_device_atomic_capabilities;
113	typedef cl_bitfield cl_device_device_enqueue_capabilities;
114	typedef cl_uint cl_khronos_vendor_id;
115	typedef cl_properties cl_mem_properties;
116	typedef cl_uint cl_version;
117	#endif
118
119	typedef struct _cl_image_format {
120	cl_channel_order image_channel_order;
121	cl_channel_type image_channel_data_type;
122	} cl_image_format;
123
124	#ifdef CL_VERSION_1_2
125
126	typedef struct _cl_image_desc {
127	cl_mem_object_type image_type;
128	size_t image_width;
129	size_t image_height;
130	size_t image_depth;
131	size_t image_array_size;
132	size_t image_row_pitch;
133	size_t image_slice_pitch;
134	cl_uint num_mip_levels;
135	cl_uint num_samples;
136	#ifdef CL_VERSION_2_0
137	#if defined(__GNUC__)
138	__extension__ /* Prevents warnings about anonymous union in -pedantic builds */
139	#endif
140	#if defined(_MSC_VER) && !defined(__STDC__)
141	#pragma warning( push )
142	#pragma warning( disable : 4201 ) /* Prevents warning about nameless struct/union in /W4 builds */
143	#endif
144	#ifdef __clang__
145	#pragma clang diagnostic push
146	#pragma clang diagnostic ignored "-Wc11-extensions" /* Prevents warning about nameless union being C11 extension*/
147	#endif
148	#if defined(_MSC_VER) && defined(__STDC__)
149	/* Anonymous unions are not supported in /Za builds */
150	#else
151	union {
152	#endif
153	#endif
154	cl_mem buffer;
155	#ifdef CL_VERSION_2_0
156	#if defined(_MSC_VER) && defined(__STDC__)
157	/* Anonymous unions are not supported in /Za builds */
158	#else
159	cl_mem mem_object;
160	};
161	#endif
162	#if defined(_MSC_VER) && !defined(__STDC__)
163	#pragma warning( pop )
164	#endif
165	#ifdef __clang__
166	#pragma clang diagnostic pop
167	#endif
168	#endif
169	} cl_image_desc;
170
171	#endif
172
173	#ifdef CL_VERSION_1_1
174
175	typedef struct _cl_buffer_region {
176	size_t origin;
177	size_t size;
178	} cl_buffer_region;
179
180	#endif
181
182	#ifdef CL_VERSION_3_0
183
184	#define CL_NAME_VERSION_MAX_NAME_SIZE 64
185
186	typedef struct _cl_name_version {
187	cl_version version;
188	char name[CL_NAME_VERSION_MAX_NAME_SIZE];
189	} cl_name_version;
190
191	#endif
192
193	/******************************************************************************/
194
195	/* Error Codes */
196	#define CL_SUCCESS 0
197	#define CL_DEVICE_NOT_FOUND -1
198	#define CL_DEVICE_NOT_AVAILABLE -2
199	#define CL_COMPILER_NOT_AVAILABLE -3
200	#define CL_MEM_OBJECT_ALLOCATION_FAILURE -4
201	#define CL_OUT_OF_RESOURCES -5
202	#define CL_OUT_OF_HOST_MEMORY -6
203	#define CL_PROFILING_INFO_NOT_AVAILABLE -7
204	#define CL_MEM_COPY_OVERLAP -8
205	#define CL_IMAGE_FORMAT_MISMATCH -9
206	#define CL_IMAGE_FORMAT_NOT_SUPPORTED -10
207	#define CL_BUILD_PROGRAM_FAILURE -11
208	#define CL_MAP_FAILURE -12
209	#ifdef CL_VERSION_1_1
210	#define CL_MISALIGNED_SUB_BUFFER_OFFSET -13
211	#define CL_EXEC_STATUS_ERROR_FOR_EVENTS_IN_WAIT_LIST -14
212	#endif
213	#ifdef CL_VERSION_1_2
214	#define CL_COMPILE_PROGRAM_FAILURE -15
215	#define CL_LINKER_NOT_AVAILABLE -16
216	#define CL_LINK_PROGRAM_FAILURE -17
217	#define CL_DEVICE_PARTITION_FAILED -18
218	#define CL_KERNEL_ARG_INFO_NOT_AVAILABLE -19
219	#endif
220
221	#define CL_INVALID_VALUE -30
222	#define CL_INVALID_DEVICE_TYPE -31
223	#define CL_INVALID_PLATFORM -32
224	#define CL_INVALID_DEVICE -33
225	#define CL_INVALID_CONTEXT -34
226	#define CL_INVALID_QUEUE_PROPERTIES -35
227	#define CL_INVALID_COMMAND_QUEUE -36
228	#define CL_INVALID_HOST_PTR -37
229	#define CL_INVALID_MEM_OBJECT -38
230	#define CL_INVALID_IMAGE_FORMAT_DESCRIPTOR -39
231	#define CL_INVALID_IMAGE_SIZE -40
232	#define CL_INVALID_SAMPLER -41
233	#define CL_INVALID_BINARY -42
234	#define CL_INVALID_BUILD_OPTIONS -43
235	#define CL_INVALID_PROGRAM -44
236	#define CL_INVALID_PROGRAM_EXECUTABLE -45
237	#define CL_INVALID_KERNEL_NAME -46
238	#define CL_INVALID_KERNEL_DEFINITION -47
239	#define CL_INVALID_KERNEL -48
240	#define CL_INVALID_ARG_INDEX -49
241	#define CL_INVALID_ARG_VALUE -50
242	#define CL_INVALID_ARG_SIZE -51
243	#define CL_INVALID_KERNEL_ARGS -52
244	#define CL_INVALID_WORK_DIMENSION -53
245	#define CL_INVALID_WORK_GROUP_SIZE -54
246	#define CL_INVALID_WORK_ITEM_SIZE -55
247	#define CL_INVALID_GLOBAL_OFFSET -56
248	#define CL_INVALID_EVENT_WAIT_LIST -57
249	#define CL_INVALID_EVENT -58
250	#define CL_INVALID_OPERATION -59
251	#define CL_INVALID_GL_OBJECT -60
252	#define CL_INVALID_BUFFER_SIZE -61
253	#define CL_INVALID_MIP_LEVEL -62
254	#define CL_INVALID_GLOBAL_WORK_SIZE -63
255	#ifdef CL_VERSION_1_1
256	#define CL_INVALID_PROPERTY -64
257	#endif
258	#ifdef CL_VERSION_1_2
259	#define CL_INVALID_IMAGE_DESCRIPTOR -65
260	#define CL_INVALID_COMPILER_OPTIONS -66
261	#define CL_INVALID_LINKER_OPTIONS -67
262	#define CL_INVALID_DEVICE_PARTITION_COUNT -68
263	#endif
264	#ifdef CL_VERSION_2_0
265	#define CL_INVALID_PIPE_SIZE -69
266	#define CL_INVALID_DEVICE_QUEUE -70
267	#endif
268	#ifdef CL_VERSION_2_2
269	#define CL_INVALID_SPEC_ID -71
270	#define CL_MAX_SIZE_RESTRICTION_EXCEEDED -72
271	#endif
272
273
274	/* cl_bool */
275	#define CL_FALSE 0
276	#define CL_TRUE 1
277	#ifdef CL_VERSION_1_2
278	#define CL_BLOCKING CL_TRUE
279	#define CL_NON_BLOCKING CL_FALSE
280	#endif
281
282	/* cl_platform_info */
283	#define CL_PLATFORM_PROFILE 0x0900
284	#define CL_PLATFORM_VERSION 0x0901
285	#define CL_PLATFORM_NAME 0x0902
286	#define CL_PLATFORM_VENDOR 0x0903
287	#define CL_PLATFORM_EXTENSIONS 0x0904
288	#ifdef CL_VERSION_2_1
289	#define CL_PLATFORM_HOST_TIMER_RESOLUTION 0x0905
290	#endif
291	#ifdef CL_VERSION_3_0
292	#define CL_PLATFORM_NUMERIC_VERSION 0x0906
293	#define CL_PLATFORM_EXTENSIONS_WITH_VERSION 0x0907
294	#endif
295
296	/* cl_device_type - bitfield */
297	#define CL_DEVICE_TYPE_DEFAULT (1 << 0)
298	#define CL_DEVICE_TYPE_CPU (1 << 1)
299	#define CL_DEVICE_TYPE_GPU (1 << 2)
300	#define CL_DEVICE_TYPE_ACCELERATOR (1 << 3)
301	#ifdef CL_VERSION_1_2
302	#define CL_DEVICE_TYPE_CUSTOM (1 << 4)
303	#endif
304	#define CL_DEVICE_TYPE_ALL 0xFFFFFFFF
305
306	/* cl_device_info */
307	#define CL_DEVICE_TYPE 0x1000
308	#define CL_DEVICE_VENDOR_ID 0x1001
309	#define CL_DEVICE_MAX_COMPUTE_UNITS 0x1002
310	#define CL_DEVICE_MAX_WORK_ITEM_DIMENSIONS 0x1003
311	#define CL_DEVICE_MAX_WORK_GROUP_SIZE 0x1004
312	#define CL_DEVICE_MAX_WORK_ITEM_SIZES 0x1005
313	#define CL_DEVICE_PREFERRED_VECTOR_WIDTH_CHAR 0x1006
314	#define CL_DEVICE_PREFERRED_VECTOR_WIDTH_SHORT 0x1007
315	#define CL_DEVICE_PREFERRED_VECTOR_WIDTH_INT 0x1008
316	#define CL_DEVICE_PREFERRED_VECTOR_WIDTH_LONG 0x1009
317	#define CL_DEVICE_PREFERRED_VECTOR_WIDTH_FLOAT 0x100A
318	#define CL_DEVICE_PREFERRED_VECTOR_WIDTH_DOUBLE 0x100B
319	#define CL_DEVICE_MAX_CLOCK_FREQUENCY 0x100C
320	#define CL_DEVICE_ADDRESS_BITS 0x100D
321	#define CL_DEVICE_MAX_READ_IMAGE_ARGS 0x100E
322	#define CL_DEVICE_MAX_WRITE_IMAGE_ARGS 0x100F
323	#define CL_DEVICE_MAX_MEM_ALLOC_SIZE 0x1010
324	#define CL_DEVICE_IMAGE2D_MAX_WIDTH 0x1011
325	#define CL_DEVICE_IMAGE2D_MAX_HEIGHT 0x1012
326	#define CL_DEVICE_IMAGE3D_MAX_WIDTH 0x1013
327	#define CL_DEVICE_IMAGE3D_MAX_HEIGHT 0x1014
328	#define CL_DEVICE_IMAGE3D_MAX_DEPTH 0x1015
329	#define CL_DEVICE_IMAGE_SUPPORT 0x1016
330	#define CL_DEVICE_MAX_PARAMETER_SIZE 0x1017
331	#define CL_DEVICE_MAX_SAMPLERS 0x1018
332	#define CL_DEVICE_MEM_BASE_ADDR_ALIGN 0x1019
333	#define CL_DEVICE_MIN_DATA_TYPE_ALIGN_SIZE 0x101A
334	#define CL_DEVICE_SINGLE_FP_CONFIG 0x101B
335	#define CL_DEVICE_GLOBAL_MEM_CACHE_TYPE 0x101C
336	#define CL_DEVICE_GLOBAL_MEM_CACHELINE_SIZE 0x101D
337	#define CL_DEVICE_GLOBAL_MEM_CACHE_SIZE 0x101E
338	#define CL_DEVICE_GLOBAL_MEM_SIZE 0x101F
339	#define CL_DEVICE_MAX_CONSTANT_BUFFER_SIZE 0x1020
340	#define CL_DEVICE_MAX_CONSTANT_ARGS 0x1021
341	#define CL_DEVICE_LOCAL_MEM_TYPE 0x1022
342	#define CL_DEVICE_LOCAL_MEM_SIZE 0x1023
343	#define CL_DEVICE_ERROR_CORRECTION_SUPPORT 0x1024
344	#define CL_DEVICE_PROFILING_TIMER_RESOLUTION 0x1025
345	#define CL_DEVICE_ENDIAN_LITTLE 0x1026
346	#define CL_DEVICE_AVAILABLE 0x1027
347	#define CL_DEVICE_COMPILER_AVAILABLE 0x1028
348	#define CL_DEVICE_EXECUTION_CAPABILITIES 0x1029
349	#define CL_DEVICE_QUEUE_PROPERTIES 0x102A /* deprecated */
350	#ifdef CL_VERSION_2_0
351	#define CL_DEVICE_QUEUE_ON_HOST_PROPERTIES 0x102A
352	#endif
353	#define CL_DEVICE_NAME 0x102B
354	#define CL_DEVICE_VENDOR 0x102C
355	#define CL_DRIVER_VERSION 0x102D
356	#define CL_DEVICE_PROFILE 0x102E
357	#define CL_DEVICE_VERSION 0x102F
358	#define CL_DEVICE_EXTENSIONS 0x1030
359	#define CL_DEVICE_PLATFORM 0x1031
360	#ifdef CL_VERSION_1_2
361	#define CL_DEVICE_DOUBLE_FP_CONFIG 0x1032
362	#endif
363	/* 0x1033 reserved for CL_DEVICE_HALF_FP_CONFIG which is already defined in "cl_ext.h" */
364	#ifdef CL_VERSION_1_1
365	#define CL_DEVICE_PREFERRED_VECTOR_WIDTH_HALF 0x1034
366	#define CL_DEVICE_HOST_UNIFIED_MEMORY 0x1035 /* deprecated */
367	#define CL_DEVICE_NATIVE_VECTOR_WIDTH_CHAR 0x1036
368	#define CL_DEVICE_NATIVE_VECTOR_WIDTH_SHORT 0x1037
369	#define CL_DEVICE_NATIVE_VECTOR_WIDTH_INT 0x1038
370	#define CL_DEVICE_NATIVE_VECTOR_WIDTH_LONG 0x1039
371	#define CL_DEVICE_NATIVE_VECTOR_WIDTH_FLOAT 0x103A
372	#define CL_DEVICE_NATIVE_VECTOR_WIDTH_DOUBLE 0x103B
373	#define CL_DEVICE_NATIVE_VECTOR_WIDTH_HALF 0x103C
374	#define CL_DEVICE_OPENCL_C_VERSION 0x103D
375	#endif
376	#ifdef CL_VERSION_1_2
377	#define CL_DEVICE_LINKER_AVAILABLE 0x103E
378	#define CL_DEVICE_BUILT_IN_KERNELS 0x103F
379	#define CL_DEVICE_IMAGE_MAX_BUFFER_SIZE 0x1040
380	#define CL_DEVICE_IMAGE_MAX_ARRAY_SIZE 0x1041
381	#define CL_DEVICE_PARENT_DEVICE 0x1042
382	#define CL_DEVICE_PARTITION_MAX_SUB_DEVICES 0x1043
383	#define CL_DEVICE_PARTITION_PROPERTIES 0x1044
384	#define CL_DEVICE_PARTITION_AFFINITY_DOMAIN 0x1045
385	#define CL_DEVICE_PARTITION_TYPE 0x1046
386	#define CL_DEVICE_REFERENCE_COUNT 0x1047
387	#define CL_DEVICE_PREFERRED_INTEROP_USER_SYNC 0x1048
388	#define CL_DEVICE_PRINTF_BUFFER_SIZE 0x1049
389	#endif
390	#ifdef CL_VERSION_2_0
391	#define CL_DEVICE_IMAGE_PITCH_ALIGNMENT 0x104A
392	#define CL_DEVICE_IMAGE_BASE_ADDRESS_ALIGNMENT 0x104B
393	#define CL_DEVICE_MAX_READ_WRITE_IMAGE_ARGS 0x104C
394	#define CL_DEVICE_MAX_GLOBAL_VARIABLE_SIZE 0x104D
395	#define CL_DEVICE_QUEUE_ON_DEVICE_PROPERTIES 0x104E
396	#define CL_DEVICE_QUEUE_ON_DEVICE_PREFERRED_SIZE 0x104F
397	#define CL_DEVICE_QUEUE_ON_DEVICE_MAX_SIZE 0x1050
398	#define CL_DEVICE_MAX_ON_DEVICE_QUEUES 0x1051
399	#define CL_DEVICE_MAX_ON_DEVICE_EVENTS 0x1052
400	#define CL_DEVICE_SVM_CAPABILITIES 0x1053
401	#define CL_DEVICE_GLOBAL_VARIABLE_PREFERRED_TOTAL_SIZE 0x1054
402	#define CL_DEVICE_MAX_PIPE_ARGS 0x1055
403	#define CL_DEVICE_PIPE_MAX_ACTIVE_RESERVATIONS 0x1056
404	#define CL_DEVICE_PIPE_MAX_PACKET_SIZE 0x1057
405	#define CL_DEVICE_PREFERRED_PLATFORM_ATOMIC_ALIGNMENT 0x1058
406	#define CL_DEVICE_PREFERRED_GLOBAL_ATOMIC_ALIGNMENT 0x1059
407	#define CL_DEVICE_PREFERRED_LOCAL_ATOMIC_ALIGNMENT 0x105A
408	#endif
409	#ifdef CL_VERSION_2_1
410	#define CL_DEVICE_IL_VERSION 0x105B
411	#define CL_DEVICE_MAX_NUM_SUB_GROUPS 0x105C
412	#define CL_DEVICE_SUB_GROUP_INDEPENDENT_FORWARD_PROGRESS 0x105D
413	#endif
414	#ifdef CL_VERSION_3_0
415	#define CL_DEVICE_NUMERIC_VERSION 0x105E
416	#define CL_DEVICE_EXTENSIONS_WITH_VERSION 0x1060
417	#define CL_DEVICE_ILS_WITH_VERSION 0x1061
418	#define CL_DEVICE_BUILT_IN_KERNELS_WITH_VERSION 0x1062
419	#define CL_DEVICE_ATOMIC_MEMORY_CAPABILITIES 0x1063
420	#define CL_DEVICE_ATOMIC_FENCE_CAPABILITIES 0x1064
421	#define CL_DEVICE_NON_UNIFORM_WORK_GROUP_SUPPORT 0x1065
422	#define CL_DEVICE_OPENCL_C_ALL_VERSIONS 0x1066
423	#define CL_DEVICE_PREFERRED_WORK_GROUP_SIZE_MULTIPLE 0x1067
424	#define CL_DEVICE_WORK_GROUP_COLLECTIVE_FUNCTIONS_SUPPORT 0x1068
425	#define CL_DEVICE_GENERIC_ADDRESS_SPACE_SUPPORT 0x1069
426	/* 0x106A to 0x106E - Reserved for upcoming KHR extension */
427	#define CL_DEVICE_OPENCL_C_FEATURES 0x106F
428	#define CL_DEVICE_DEVICE_ENQUEUE_CAPABILITIES 0x1070
429	#define CL_DEVICE_PIPE_SUPPORT 0x1071
430	#define CL_DEVICE_LATEST_CONFORMANCE_VERSION_PASSED 0x1072
431	#endif
432
433	/* cl_device_fp_config - bitfield */
434	#define CL_FP_DENORM (1 << 0)
435	#define CL_FP_INF_NAN (1 << 1)
436	#define CL_FP_ROUND_TO_NEAREST (1 << 2)
437	#define CL_FP_ROUND_TO_ZERO (1 << 3)
438	#define CL_FP_ROUND_TO_INF (1 << 4)
439	#define CL_FP_FMA (1 << 5)
440	#ifdef CL_VERSION_1_1
441	#define CL_FP_SOFT_FLOAT (1 << 6)
442	#endif
443	#ifdef CL_VERSION_1_2
444	#define CL_FP_CORRECTLY_ROUNDED_DIVIDE_SQRT (1 << 7)
445	#endif
446
447	/* cl_device_mem_cache_type */
448	#define CL_NONE 0x0
449	#define CL_READ_ONLY_CACHE 0x1
450	#define CL_READ_WRITE_CACHE 0x2
451
452	/* cl_device_local_mem_type */
453	#define CL_LOCAL 0x1
454	#define CL_GLOBAL 0x2
455
456	/* cl_device_exec_capabilities - bitfield */
457	#define CL_EXEC_KERNEL (1 << 0)
458	#define CL_EXEC_NATIVE_KERNEL (1 << 1)
459
460	/* cl_command_queue_properties - bitfield */
461	#define CL_QUEUE_OUT_OF_ORDER_EXEC_MODE_ENABLE (1 << 0)
462	#define CL_QUEUE_PROFILING_ENABLE (1 << 1)
463	#ifdef CL_VERSION_2_0
464	#define CL_QUEUE_ON_DEVICE (1 << 2)
465	#define CL_QUEUE_ON_DEVICE_DEFAULT (1 << 3)
466	#endif
467
468	/* cl_context_info */
469	#define CL_CONTEXT_REFERENCE_COUNT 0x1080
470	#define CL_CONTEXT_DEVICES 0x1081
471	#define CL_CONTEXT_PROPERTIES 0x1082
472	#ifdef CL_VERSION_1_1
473	#define CL_CONTEXT_NUM_DEVICES 0x1083
474	#endif
475
476	/* cl_context_properties */
477	#define CL_CONTEXT_PLATFORM 0x1084
478	#ifdef CL_VERSION_1_2
479	#define CL_CONTEXT_INTEROP_USER_SYNC 0x1085
480	#endif
481
482	#ifdef CL_VERSION_1_2
483
484	/* cl_device_partition_property */
485	#define CL_DEVICE_PARTITION_EQUALLY 0x1086
486	#define CL_DEVICE_PARTITION_BY_COUNTS 0x1087
487	#define CL_DEVICE_PARTITION_BY_COUNTS_LIST_END 0x0
488	#define CL_DEVICE_PARTITION_BY_AFFINITY_DOMAIN 0x1088
489
490	#endif
491
492	#ifdef CL_VERSION_1_2
493
494	/* cl_device_affinity_domain */
495	#define CL_DEVICE_AFFINITY_DOMAIN_NUMA (1 << 0)
496	#define CL_DEVICE_AFFINITY_DOMAIN_L4_CACHE (1 << 1)
497	#define CL_DEVICE_AFFINITY_DOMAIN_L3_CACHE (1 << 2)
498	#define CL_DEVICE_AFFINITY_DOMAIN_L2_CACHE (1 << 3)
499	#define CL_DEVICE_AFFINITY_DOMAIN_L1_CACHE (1 << 4)
500	#define CL_DEVICE_AFFINITY_DOMAIN_NEXT_PARTITIONABLE (1 << 5)
501
502	#endif
503
504	#ifdef CL_VERSION_2_0
505
506	/* cl_device_svm_capabilities */
507	#define CL_DEVICE_SVM_COARSE_GRAIN_BUFFER (1 << 0)
508	#define CL_DEVICE_SVM_FINE_GRAIN_BUFFER (1 << 1)
509	#define CL_DEVICE_SVM_FINE_GRAIN_SYSTEM (1 << 2)
510	#define CL_DEVICE_SVM_ATOMICS (1 << 3)
511
512	#endif
513
514	/* cl_command_queue_info */
515	#define CL_QUEUE_CONTEXT 0x1090
516	#define CL_QUEUE_DEVICE 0x1091
517	#define CL_QUEUE_REFERENCE_COUNT 0x1092
518	#define CL_QUEUE_PROPERTIES 0x1093
519	#ifdef CL_VERSION_2_0
520	#define CL_QUEUE_SIZE 0x1094
521	#endif
522	#ifdef CL_VERSION_2_1
523	#define CL_QUEUE_DEVICE_DEFAULT 0x1095
524	#endif
525	#ifdef CL_VERSION_3_0
526	#define CL_QUEUE_PROPERTIES_ARRAY 0x1098
527	#endif
528
529	/* cl_mem_flags and cl_svm_mem_flags - bitfield */
530	#define CL_MEM_READ_WRITE (1 << 0)
531	#define CL_MEM_WRITE_ONLY (1 << 1)
532	#define CL_MEM_READ_ONLY (1 << 2)
533	#define CL_MEM_USE_HOST_PTR (1 << 3)
534	#define CL_MEM_ALLOC_HOST_PTR (1 << 4)
535	#define CL_MEM_COPY_HOST_PTR (1 << 5)
536	/* reserved (1 << 6) */
537	#ifdef CL_VERSION_1_2
538	#define CL_MEM_HOST_WRITE_ONLY (1 << 7)
539	#define CL_MEM_HOST_READ_ONLY (1 << 8)
540	#define CL_MEM_HOST_NO_ACCESS (1 << 9)
541	#endif
542	#ifdef CL_VERSION_2_0
543	#define CL_MEM_SVM_FINE_GRAIN_BUFFER (1 << 10) /* used by cl_svm_mem_flags only */
544	#define CL_MEM_SVM_ATOMICS (1 << 11) /* used by cl_svm_mem_flags only */
545	#define CL_MEM_KERNEL_READ_AND_WRITE (1 << 12)
546	#endif
547
548	#ifdef CL_VERSION_1_2
549
550	/* cl_mem_migration_flags - bitfield */
551	#define CL_MIGRATE_MEM_OBJECT_HOST (1 << 0)
552	#define CL_MIGRATE_MEM_OBJECT_CONTENT_UNDEFINED (1 << 1)
553
554	#endif
555
556	/* cl_channel_order */
557	#define CL_R 0x10B0
558	#define CL_A 0x10B1
559	#define CL_RG 0x10B2
560	#define CL_RA 0x10B3
561	#define CL_RGB 0x10B4
562	#define CL_RGBA 0x10B5
563	#define CL_BGRA 0x10B6
564	#define CL_ARGB 0x10B7
565	#define CL_INTENSITY 0x10B8
566	#define CL_LUMINANCE 0x10B9
567	#ifdef CL_VERSION_1_1
568	#define CL_Rx 0x10BA
569	#define CL_RGx 0x10BB
570	#define CL_RGBx 0x10BC
571	#endif
572	#ifdef CL_VERSION_1_2
573	#define CL_DEPTH 0x10BD
574	#define CL_DEPTH_STENCIL 0x10BE
575	#endif
576	#ifdef CL_VERSION_2_0
577	#define CL_sRGB 0x10BF
578	#define CL_sRGBx 0x10C0
579	#define CL_sRGBA 0x10C1
580	#define CL_sBGRA 0x10C2
581	#define CL_ABGR 0x10C3
582	#endif
583
584	/* cl_channel_type */
585	#define CL_SNORM_INT8 0x10D0
586	#define CL_SNORM_INT16 0x10D1
587	#define CL_UNORM_INT8 0x10D2
588	#define CL_UNORM_INT16 0x10D3
589	#define CL_UNORM_SHORT_565 0x10D4
590	#define CL_UNORM_SHORT_555 0x10D5
591	#define CL_UNORM_INT_101010 0x10D6
592	#define CL_SIGNED_INT8 0x10D7
593	#define CL_SIGNED_INT16 0x10D8
594	#define CL_SIGNED_INT32 0x10D9
595	#define CL_UNSIGNED_INT8 0x10DA
596	#define CL_UNSIGNED_INT16 0x10DB
597	#define CL_UNSIGNED_INT32 0x10DC
598	#define CL_HALF_FLOAT 0x10DD
599	#define CL_FLOAT 0x10DE
600	#ifdef CL_VERSION_1_2
601	#define CL_UNORM_INT24 0x10DF
602	#endif
603	#ifdef CL_VERSION_2_1
604	#define CL_UNORM_INT_101010_2 0x10E0
605	#endif
606
607	/* cl_mem_object_type */
608	#define CL_MEM_OBJECT_BUFFER 0x10F0
609	#define CL_MEM_OBJECT_IMAGE2D 0x10F1
610	#define CL_MEM_OBJECT_IMAGE3D 0x10F2
611	#ifdef CL_VERSION_1_2
612	#define CL_MEM_OBJECT_IMAGE2D_ARRAY 0x10F3
613	#define CL_MEM_OBJECT_IMAGE1D 0x10F4
614	#define CL_MEM_OBJECT_IMAGE1D_ARRAY 0x10F5
615	#define CL_MEM_OBJECT_IMAGE1D_BUFFER 0x10F6
616	#endif
617	#ifdef CL_VERSION_2_0
618	#define CL_MEM_OBJECT_PIPE 0x10F7
619	#endif
620
621	/* cl_mem_info */
622	#define CL_MEM_TYPE 0x1100
623	#define CL_MEM_FLAGS 0x1101
624	#define CL_MEM_SIZE 0x1102
625	#define CL_MEM_HOST_PTR 0x1103
626	#define CL_MEM_MAP_COUNT 0x1104
627	#define CL_MEM_REFERENCE_COUNT 0x1105
628	#define CL_MEM_CONTEXT 0x1106
629	#ifdef CL_VERSION_1_1
630	#define CL_MEM_ASSOCIATED_MEMOBJECT 0x1107
631	#define CL_MEM_OFFSET 0x1108
632	#endif
633	#ifdef CL_VERSION_2_0
634	#define CL_MEM_USES_SVM_POINTER 0x1109
635	#endif
636	#ifdef CL_VERSION_3_0
637	#define CL_MEM_PROPERTIES 0x110A
638	#endif
639
640	/* cl_image_info */
641	#define CL_IMAGE_FORMAT 0x1110
642	#define CL_IMAGE_ELEMENT_SIZE 0x1111
643	#define CL_IMAGE_ROW_PITCH 0x1112
644	#define CL_IMAGE_SLICE_PITCH 0x1113
645	#define CL_IMAGE_WIDTH 0x1114
646	#define CL_IMAGE_HEIGHT 0x1115
647	#define CL_IMAGE_DEPTH 0x1116
648	#ifdef CL_VERSION_1_2
649	#define CL_IMAGE_ARRAY_SIZE 0x1117
650	#define CL_IMAGE_BUFFER 0x1118
651	#define CL_IMAGE_NUM_MIP_LEVELS 0x1119
652	#define CL_IMAGE_NUM_SAMPLES 0x111A
653	#endif
654
655
656	/* cl_pipe_info */
657	#ifdef CL_VERSION_2_0
658	#define CL_PIPE_PACKET_SIZE 0x1120
659	#define CL_PIPE_MAX_PACKETS 0x1121
660	#endif
661	#ifdef CL_VERSION_3_0
662	#define CL_PIPE_PROPERTIES 0x1122
663	#endif
664
665	/* cl_addressing_mode */
666	#define CL_ADDRESS_NONE 0x1130
667	#define CL_ADDRESS_CLAMP_TO_EDGE 0x1131
668	#define CL_ADDRESS_CLAMP 0x1132
669	#define CL_ADDRESS_REPEAT 0x1133
670	#ifdef CL_VERSION_1_1
671	#define CL_ADDRESS_MIRRORED_REPEAT 0x1134
672	#endif
673
674	/* cl_filter_mode */
675	#define CL_FILTER_NEAREST 0x1140
676	#define CL_FILTER_LINEAR 0x1141
677
678	/* cl_sampler_info */
679	#define CL_SAMPLER_REFERENCE_COUNT 0x1150
680	#define CL_SAMPLER_CONTEXT 0x1151
681	#define CL_SAMPLER_NORMALIZED_COORDS 0x1152
682	#define CL_SAMPLER_ADDRESSING_MODE 0x1153
683	#define CL_SAMPLER_FILTER_MODE 0x1154
684	#ifdef CL_VERSION_2_0
685	/* These enumerants are for the cl_khr_mipmap_image extension.
686	They have since been added to cl_ext.h with an appropriate
687	KHR suffix, but are left here for backwards compatibility. */
688	#define CL_SAMPLER_MIP_FILTER_MODE 0x1155
689	#define CL_SAMPLER_LOD_MIN 0x1156
690	#define CL_SAMPLER_LOD_MAX 0x1157
691	#endif
692	#ifdef CL_VERSION_3_0
693	#define CL_SAMPLER_PROPERTIES 0x1158
694	#endif
695
696	/* cl_map_flags - bitfield */
697	#define CL_MAP_READ (1 << 0)
698	#define CL_MAP_WRITE (1 << 1)
699	#ifdef CL_VERSION_1_2
700	#define CL_MAP_WRITE_INVALIDATE_REGION (1 << 2)
701	#endif
702
703	/* cl_program_info */
704	#define CL_PROGRAM_REFERENCE_COUNT 0x1160
705	#define CL_PROGRAM_CONTEXT 0x1161
706	#define CL_PROGRAM_NUM_DEVICES 0x1162
707	#define CL_PROGRAM_DEVICES 0x1163
708	#define CL_PROGRAM_SOURCE 0x1164
709	#define CL_PROGRAM_BINARY_SIZES 0x1165
710	#define CL_PROGRAM_BINARIES 0x1166
711	#ifdef CL_VERSION_1_2
712	#define CL_PROGRAM_NUM_KERNELS 0x1167
713	#define CL_PROGRAM_KERNEL_NAMES 0x1168
714	#endif
715	#ifdef CL_VERSION_2_1
716	#define CL_PROGRAM_IL 0x1169
717	#endif
718	#ifdef CL_VERSION_2_2
719	#define CL_PROGRAM_SCOPE_GLOBAL_CTORS_PRESENT 0x116A
720	#define CL_PROGRAM_SCOPE_GLOBAL_DTORS_PRESENT 0x116B
721	#endif
722
723	/* cl_program_build_info */
724	#define CL_PROGRAM_BUILD_STATUS 0x1181
725	#define CL_PROGRAM_BUILD_OPTIONS 0x1182
726	#define CL_PROGRAM_BUILD_LOG 0x1183
727	#ifdef CL_VERSION_1_2
728	#define CL_PROGRAM_BINARY_TYPE 0x1184
729	#endif
730	#ifdef CL_VERSION_2_0
731	#define CL_PROGRAM_BUILD_GLOBAL_VARIABLE_TOTAL_SIZE 0x1185
732	#endif
733
734	#ifdef CL_VERSION_1_2
735
736	/* cl_program_binary_type */
737	#define CL_PROGRAM_BINARY_TYPE_NONE 0x0
738	#define CL_PROGRAM_BINARY_TYPE_COMPILED_OBJECT 0x1
739	#define CL_PROGRAM_BINARY_TYPE_LIBRARY 0x2
740	#define CL_PROGRAM_BINARY_TYPE_EXECUTABLE 0x4
741
742	#endif
743
744	/* cl_build_status */
745	#define CL_BUILD_SUCCESS 0
746	#define CL_BUILD_NONE -1
747	#define CL_BUILD_ERROR -2
748	#define CL_BUILD_IN_PROGRESS -3
749
750	/* cl_kernel_info */
751	#define CL_KERNEL_FUNCTION_NAME 0x1190
752	#define CL_KERNEL_NUM_ARGS 0x1191
753	#define CL_KERNEL_REFERENCE_COUNT 0x1192
754	#define CL_KERNEL_CONTEXT 0x1193
755	#define CL_KERNEL_PROGRAM 0x1194
756	#ifdef CL_VERSION_1_2
757	#define CL_KERNEL_ATTRIBUTES 0x1195
758	#endif
759
760	#ifdef CL_VERSION_1_2
761
762	/* cl_kernel_arg_info */
763	#define CL_KERNEL_ARG_ADDRESS_QUALIFIER 0x1196
764	#define CL_KERNEL_ARG_ACCESS_QUALIFIER 0x1197
765	#define CL_KERNEL_ARG_TYPE_NAME 0x1198
766	#define CL_KERNEL_ARG_TYPE_QUALIFIER 0x1199
767	#define CL_KERNEL_ARG_NAME 0x119A
768
769	#endif
770
771	#ifdef CL_VERSION_1_2
772
773	/* cl_kernel_arg_address_qualifier */
774	#define CL_KERNEL_ARG_ADDRESS_GLOBAL 0x119B
775	#define CL_KERNEL_ARG_ADDRESS_LOCAL 0x119C
776	#define CL_KERNEL_ARG_ADDRESS_CONSTANT 0x119D
777	#define CL_KERNEL_ARG_ADDRESS_PRIVATE 0x119E
778
779	#endif
780
781	#ifdef CL_VERSION_1_2
782
783	/* cl_kernel_arg_access_qualifier */
784	#define CL_KERNEL_ARG_ACCESS_READ_ONLY 0x11A0
785	#define CL_KERNEL_ARG_ACCESS_WRITE_ONLY 0x11A1
786	#define CL_KERNEL_ARG_ACCESS_READ_WRITE 0x11A2
787	#define CL_KERNEL_ARG_ACCESS_NONE 0x11A3
788
789	#endif
790
791	#ifdef CL_VERSION_1_2
792
793	/* cl_kernel_arg_type_qualifier */
794	#define CL_KERNEL_ARG_TYPE_NONE 0
795	#define CL_KERNEL_ARG_TYPE_CONST (1 << 0)
796	#define CL_KERNEL_ARG_TYPE_RESTRICT (1 << 1)
797	#define CL_KERNEL_ARG_TYPE_VOLATILE (1 << 2)
798	#ifdef CL_VERSION_2_0
799	#define CL_KERNEL_ARG_TYPE_PIPE (1 << 3)
800	#endif
801
802	#endif
803
804	/* cl_kernel_work_group_info */
805	#define CL_KERNEL_WORK_GROUP_SIZE 0x11B0
806	#define CL_KERNEL_COMPILE_WORK_GROUP_SIZE 0x11B1
807	#define CL_KERNEL_LOCAL_MEM_SIZE 0x11B2
808	#define CL_KERNEL_PREFERRED_WORK_GROUP_SIZE_MULTIPLE 0x11B3
809	#define CL_KERNEL_PRIVATE_MEM_SIZE 0x11B4
810	#ifdef CL_VERSION_1_2
811	#define CL_KERNEL_GLOBAL_WORK_SIZE 0x11B5
812	#endif
813
814	#ifdef CL_VERSION_2_1
815
816	/* cl_kernel_sub_group_info */
817	#define CL_KERNEL_MAX_SUB_GROUP_SIZE_FOR_NDRANGE 0x2033
818	#define CL_KERNEL_SUB_GROUP_COUNT_FOR_NDRANGE 0x2034
819	#define CL_KERNEL_LOCAL_SIZE_FOR_SUB_GROUP_COUNT 0x11B8
820	#define CL_KERNEL_MAX_NUM_SUB_GROUPS 0x11B9
821	#define CL_KERNEL_COMPILE_NUM_SUB_GROUPS 0x11BA
822
823	#endif
824
825	#ifdef CL_VERSION_2_0
826
827	/* cl_kernel_exec_info */
828	#define CL_KERNEL_EXEC_INFO_SVM_PTRS 0x11B6
829	#define CL_KERNEL_EXEC_INFO_SVM_FINE_GRAIN_SYSTEM 0x11B7
830
831	#endif
832
833	/* cl_event_info */
834	#define CL_EVENT_COMMAND_QUEUE 0x11D0
835	#define CL_EVENT_COMMAND_TYPE 0x11D1
836	#define CL_EVENT_REFERENCE_COUNT 0x11D2
837	#define CL_EVENT_COMMAND_EXECUTION_STATUS 0x11D3
838	#ifdef CL_VERSION_1_1
839	#define CL_EVENT_CONTEXT 0x11D4
840	#endif
841
842	/* cl_command_type */
843	#define CL_COMMAND_NDRANGE_KERNEL 0x11F0
844	#define CL_COMMAND_TASK 0x11F1
845	#define CL_COMMAND_NATIVE_KERNEL 0x11F2
846	#define CL_COMMAND_READ_BUFFER 0x11F3
847	#define CL_COMMAND_WRITE_BUFFER 0x11F4
848	#define CL_COMMAND_COPY_BUFFER 0x11F5
849	#define CL_COMMAND_READ_IMAGE 0x11F6
850	#define CL_COMMAND_WRITE_IMAGE 0x11F7
851	#define CL_COMMAND_COPY_IMAGE 0x11F8
852	#define CL_COMMAND_COPY_IMAGE_TO_BUFFER 0x11F9
853	#define CL_COMMAND_COPY_BUFFER_TO_IMAGE 0x11FA
854	#define CL_COMMAND_MAP_BUFFER 0x11FB
855	#define CL_COMMAND_MAP_IMAGE 0x11FC
856	#define CL_COMMAND_UNMAP_MEM_OBJECT 0x11FD
857	#define CL_COMMAND_MARKER 0x11FE
858	#define CL_COMMAND_ACQUIRE_GL_OBJECTS 0x11FF
859	#define CL_COMMAND_RELEASE_GL_OBJECTS 0x1200
860	#ifdef CL_VERSION_1_1
861	#define CL_COMMAND_READ_BUFFER_RECT 0x1201
862	#define CL_COMMAND_WRITE_BUFFER_RECT 0x1202
863	#define CL_COMMAND_COPY_BUFFER_RECT 0x1203
864	#define CL_COMMAND_USER 0x1204
865	#endif
866	#ifdef CL_VERSION_1_2
867	#define CL_COMMAND_BARRIER 0x1205
868	#define CL_COMMAND_MIGRATE_MEM_OBJECTS 0x1206
869	#define CL_COMMAND_FILL_BUFFER 0x1207
870	#define CL_COMMAND_FILL_IMAGE 0x1208
871	#endif
872	#ifdef CL_VERSION_2_0
873	#define CL_COMMAND_SVM_FREE 0x1209
874	#define CL_COMMAND_SVM_MEMCPY 0x120A
875	#define CL_COMMAND_SVM_MEMFILL 0x120B
876	#define CL_COMMAND_SVM_MAP 0x120C
877	#define CL_COMMAND_SVM_UNMAP 0x120D
878	#endif
879	#ifdef CL_VERSION_3_0
880	#define CL_COMMAND_SVM_MIGRATE_MEM 0x120E
881	#endif
882
883	/* command execution status */
884	#define CL_COMPLETE 0x0
885	#define CL_RUNNING 0x1
886	#define CL_SUBMITTED 0x2
887	#define CL_QUEUED 0x3
888
889	/* cl_buffer_create_type */
890	#ifdef CL_VERSION_1_1
891	#define CL_BUFFER_CREATE_TYPE_REGION 0x1220
892	#endif
893
894	/* cl_profiling_info */
895	#define CL_PROFILING_COMMAND_QUEUED 0x1280
896	#define CL_PROFILING_COMMAND_SUBMIT 0x1281
897	#define CL_PROFILING_COMMAND_START 0x1282
898	#define CL_PROFILING_COMMAND_END 0x1283
899	#ifdef CL_VERSION_2_0
900	#define CL_PROFILING_COMMAND_COMPLETE 0x1284
901	#endif
902
903	/* cl_device_atomic_capabilities - bitfield */
904	#ifdef CL_VERSION_3_0
905	#define CL_DEVICE_ATOMIC_ORDER_RELAXED (1 << 0)
906	#define CL_DEVICE_ATOMIC_ORDER_ACQ_REL (1 << 1)
907	#define CL_DEVICE_ATOMIC_ORDER_SEQ_CST (1 << 2)
908	#define CL_DEVICE_ATOMIC_SCOPE_WORK_ITEM (1 << 3)
909	#define CL_DEVICE_ATOMIC_SCOPE_WORK_GROUP (1 << 4)
910	#define CL_DEVICE_ATOMIC_SCOPE_DEVICE (1 << 5)
911	#define CL_DEVICE_ATOMIC_SCOPE_ALL_DEVICES (1 << 6)
912	#endif
913
914	/* cl_device_device_enqueue_capabilities - bitfield */
915	#ifdef CL_VERSION_3_0
916	#define CL_DEVICE_QUEUE_SUPPORTED (1 << 0)
917	#define CL_DEVICE_QUEUE_REPLACEABLE_DEFAULT (1 << 1)
918	#endif
919
920	/* cl_khronos_vendor_id */
921	#define CL_KHRONOS_VENDOR_ID_CODEPLAY 0x10004
922
923	#ifdef CL_VERSION_3_0
924
925	/* cl_version */
926	#define CL_VERSION_MAJOR_BITS (10)
927	#define CL_VERSION_MINOR_BITS (10)
928	#define CL_VERSION_PATCH_BITS (12)
929
930	#define CL_VERSION_MAJOR_MASK ((1 << CL_VERSION_MAJOR_BITS) - 1)
931	#define CL_VERSION_MINOR_MASK ((1 << CL_VERSION_MINOR_BITS) - 1)
932	#define CL_VERSION_PATCH_MASK ((1 << CL_VERSION_PATCH_BITS) - 1)
933
934	#define CL_VERSION_MAJOR(version) \
935	((version) >> (CL_VERSION_MINOR_BITS + CL_VERSION_PATCH_BITS))
936
937	#define CL_VERSION_MINOR(version) \
938	(((version) >> CL_VERSION_PATCH_BITS) & CL_VERSION_MINOR_MASK)
939
940	#define CL_VERSION_PATCH(version) ((version) & CL_VERSION_PATCH_MASK)
941
942	#define CL_MAKE_VERSION(major, minor, patch) \
943	((((major) & CL_VERSION_MAJOR_MASK) \
944	<< (CL_VERSION_MINOR_BITS + CL_VERSION_PATCH_BITS)) \| \
945	(((minor) & CL_VERSION_MINOR_MASK) << CL_VERSION_PATCH_BITS) \| \
946	((patch) & CL_VERSION_PATCH_MASK))
947
948	#endif
949
950	/********************************************************************************************************/
951
952	/* Platform API */
953	extern CL_API_ENTRY cl_int CL_API_CALL
954	clGetPlatformIDs(cl_uint num_entries,
955	cl_platform_id * platforms,
956	cl_uint * num_platforms) CL_API_SUFFIX__VERSION_1_0;
957
958	extern CL_API_ENTRY cl_int CL_API_CALL
959	clGetPlatformInfo(cl_platform_id platform,
960	cl_platform_info param_name,
961	size_t param_value_size,
962	void * param_value,
963	size_t * param_value_size_ret) CL_API_SUFFIX__VERSION_1_0;
964
965	/* Device APIs */
966	extern CL_API_ENTRY cl_int CL_API_CALL
967	clGetDeviceIDs(cl_platform_id platform,
968	cl_device_type device_type,
969	cl_uint num_entries,
970	cl_device_id * devices,
971	cl_uint * num_devices) CL_API_SUFFIX__VERSION_1_0;
972
973	extern CL_API_ENTRY cl_int CL_API_CALL
974	clGetDeviceInfo(cl_device_id device,
975	cl_device_info param_name,
976	size_t param_value_size,
977	void * param_value,
978	size_t * param_value_size_ret) CL_API_SUFFIX__VERSION_1_0;
979
980	#ifdef CL_VERSION_1_2
981
982	extern CL_API_ENTRY cl_int CL_API_CALL
983	clCreateSubDevices(cl_device_id in_device,
984	const cl_device_partition_property * properties,
985	cl_uint num_devices,
986	cl_device_id * out_devices,
987	cl_uint * num_devices_ret) CL_API_SUFFIX__VERSION_1_2;
988
989	extern CL_API_ENTRY cl_int CL_API_CALL
990	clRetainDevice(cl_device_id device) CL_API_SUFFIX__VERSION_1_2;
991
992	extern CL_API_ENTRY cl_int CL_API_CALL
993	clReleaseDevice(cl_device_id device) CL_API_SUFFIX__VERSION_1_2;
994
995	#endif
996
997	#ifdef CL_VERSION_2_1
998
999	extern CL_API_ENTRY cl_int CL_API_CALL
1000	clSetDefaultDeviceCommandQueue(cl_context context,
1001	cl_device_id device,
1002	cl_command_queue command_queue) CL_API_SUFFIX__VERSION_2_1;
1003
1004	extern CL_API_ENTRY cl_int CL_API_CALL
1005	clGetDeviceAndHostTimer(cl_device_id device,
1006	cl_ulong* device_timestamp,
1007	cl_ulong* host_timestamp) CL_API_SUFFIX__VERSION_2_1;
1008
1009	extern CL_API_ENTRY cl_int CL_API_CALL
1010	clGetHostTimer(cl_device_id device,
1011	cl_ulong * host_timestamp) CL_API_SUFFIX__VERSION_2_1;
1012
1013	#endif
1014
1015	/* Context APIs */
1016	extern CL_API_ENTRY cl_context CL_API_CALL
1017	clCreateContext(const cl_context_properties * properties,
1018	cl_uint num_devices,
1019	const cl_device_id * devices,
1020	void (CL_CALLBACK * pfn_notify)(const char * errinfo,
1021	const void * private_info,
1022	size_t cb,
1023	void * user_data),
1024	void * user_data,
1025	cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_0;
1026
1027	extern CL_API_ENTRY cl_context CL_API_CALL
1028	clCreateContextFromType(const cl_context_properties * properties,
1029	cl_device_type device_type,
1030	void (CL_CALLBACK * pfn_notify)(const char * errinfo,
1031	const void * private_info,
1032	size_t cb,
1033	void * user_data),
1034	void * user_data,
1035	cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_0;
1036
1037	extern CL_API_ENTRY cl_int CL_API_CALL
1038	clRetainContext(cl_context context) CL_API_SUFFIX__VERSION_1_0;
1039
1040	extern CL_API_ENTRY cl_int CL_API_CALL
1041	clReleaseContext(cl_context context) CL_API_SUFFIX__VERSION_1_0;
1042
1043	extern CL_API_ENTRY cl_int CL_API_CALL
1044	clGetContextInfo(cl_context context,
1045	cl_context_info param_name,
1046	size_t param_value_size,
1047	void * param_value,
1048	size_t * param_value_size_ret) CL_API_SUFFIX__VERSION_1_0;
1049
1050	#ifdef CL_VERSION_3_0
1051
1052	extern CL_API_ENTRY cl_int CL_API_CALL
1053	clSetContextDestructorCallback(cl_context context,
1054	void (CL_CALLBACK* pfn_notify)(cl_context context,
1055	void* user_data),
1056	void* user_data) CL_API_SUFFIX__VERSION_3_0;
1057
1058	#endif
1059
1060	/* Command Queue APIs */
1061
1062	#ifdef CL_VERSION_2_0
1063
1064	extern CL_API_ENTRY cl_command_queue CL_API_CALL
1065	clCreateCommandQueueWithProperties(cl_context context,
1066	cl_device_id device,
1067	const cl_queue_properties * properties,
1068	cl_int * errcode_ret) CL_API_SUFFIX__VERSION_2_0;
1069
1070	#endif
1071
1072	extern CL_API_ENTRY cl_int CL_API_CALL
1073	clRetainCommandQueue(cl_command_queue command_queue) CL_API_SUFFIX__VERSION_1_0;
1074
1075	extern CL_API_ENTRY cl_int CL_API_CALL
1076	clReleaseCommandQueue(cl_command_queue command_queue) CL_API_SUFFIX__VERSION_1_0;
1077
1078	extern CL_API_ENTRY cl_int CL_API_CALL
1079	clGetCommandQueueInfo(cl_command_queue command_queue,
1080	cl_command_queue_info param_name,
1081	size_t param_value_size,
1082	void * param_value,
1083	size_t * param_value_size_ret) CL_API_SUFFIX__VERSION_1_0;
1084
1085	/* Memory Object APIs */
1086	extern CL_API_ENTRY cl_mem CL_API_CALL
1087	clCreateBuffer(cl_context context,
1088	cl_mem_flags flags,
1089	size_t size,
1090	void * host_ptr,
1091	cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_0;
1092
1093	#ifdef CL_VERSION_1_1
1094
1095	extern CL_API_ENTRY cl_mem CL_API_CALL
1096	clCreateSubBuffer(cl_mem buffer,
1097	cl_mem_flags flags,
1098	cl_buffer_create_type buffer_create_type,
1099	const void * buffer_create_info,
1100	cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_1;
1101
1102	#endif
1103
1104	#ifdef CL_VERSION_1_2
1105
1106	extern CL_API_ENTRY cl_mem CL_API_CALL
1107	clCreateImage(cl_context context,
1108	cl_mem_flags flags,
1109	const cl_image_format * image_format,
1110	const cl_image_desc * image_desc,
1111	void * host_ptr,
1112	cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_2;
1113
1114	#endif
1115
1116	#ifdef CL_VERSION_2_0
1117
1118	extern CL_API_ENTRY cl_mem CL_API_CALL
1119	clCreatePipe(cl_context context,
1120	cl_mem_flags flags,
1121	cl_uint pipe_packet_size,
1122	cl_uint pipe_max_packets,
1123	const cl_pipe_properties * properties,
1124	cl_int * errcode_ret) CL_API_SUFFIX__VERSION_2_0;
1125
1126	#endif
1127
1128	#ifdef CL_VERSION_3_0
1129
1130	extern CL_API_ENTRY cl_mem CL_API_CALL
1131	clCreateBufferWithProperties(cl_context context,
1132	const cl_mem_properties * properties,
1133	cl_mem_flags flags,
1134	size_t size,
1135	void * host_ptr,
1136	cl_int * errcode_ret) CL_API_SUFFIX__VERSION_3_0;
1137
1138	extern CL_API_ENTRY cl_mem CL_API_CALL
1139	clCreateImageWithProperties(cl_context context,
1140	const cl_mem_properties * properties,
1141	cl_mem_flags flags,
1142	const cl_image_format * image_format,
1143	const cl_image_desc * image_desc,
1144	void * host_ptr,
1145	cl_int * errcode_ret) CL_API_SUFFIX__VERSION_3_0;
1146
1147	#endif
1148
1149	extern CL_API_ENTRY cl_int CL_API_CALL
1150	clRetainMemObject(cl_mem memobj) CL_API_SUFFIX__VERSION_1_0;
1151
1152	extern CL_API_ENTRY cl_int CL_API_CALL
1153	clReleaseMemObject(cl_mem memobj) CL_API_SUFFIX__VERSION_1_0;
1154
1155	extern CL_API_ENTRY cl_int CL_API_CALL
1156	clGetSupportedImageFormats(cl_context context,
1157	cl_mem_flags flags,
1158	cl_mem_object_type image_type,
1159	cl_uint num_entries,
1160	cl_image_format * image_formats,
1161	cl_uint * num_image_formats) CL_API_SUFFIX__VERSION_1_0;
1162
1163	extern CL_API_ENTRY cl_int CL_API_CALL
1164	clGetMemObjectInfo(cl_mem memobj,
1165	cl_mem_info param_name,
1166	size_t param_value_size,
1167	void * param_value,
1168	size_t * param_value_size_ret) CL_API_SUFFIX__VERSION_1_0;
1169
1170	extern CL_API_ENTRY cl_int CL_API_CALL
1171	clGetImageInfo(cl_mem image,
1172	cl_image_info param_name,
1173	size_t param_value_size,
1174	void * param_value,
1175	size_t * param_value_size_ret) CL_API_SUFFIX__VERSION_1_0;
1176
1177	#ifdef CL_VERSION_2_0
1178
1179	extern CL_API_ENTRY cl_int CL_API_CALL
1180	clGetPipeInfo(cl_mem pipe,
1181	cl_pipe_info param_name,
1182	size_t param_value_size,
1183	void * param_value,
1184	size_t * param_value_size_ret) CL_API_SUFFIX__VERSION_2_0;
1185
1186	#endif
1187
1188	#ifdef CL_VERSION_1_1
1189
1190	extern CL_API_ENTRY cl_int CL_API_CALL
1191	clSetMemObjectDestructorCallback(cl_mem memobj,
1192	void (CL_CALLBACK * pfn_notify)(cl_mem memobj,
1193	void * user_data),
1194	void * user_data) CL_API_SUFFIX__VERSION_1_1;
1195
1196	#endif
1197
1198	/* SVM Allocation APIs */
1199
1200	#ifdef CL_VERSION_2_0
1201
1202	extern CL_API_ENTRY void * CL_API_CALL
1203	clSVMAlloc(cl_context context,
1204	cl_svm_mem_flags flags,
1205	size_t size,
1206	cl_uint alignment) CL_API_SUFFIX__VERSION_2_0;
1207
1208	extern CL_API_ENTRY void CL_API_CALL
1209	clSVMFree(cl_context context,
1210	void * svm_pointer) CL_API_SUFFIX__VERSION_2_0;
1211
1212	#endif
1213
1214	/* Sampler APIs */
1215
1216	#ifdef CL_VERSION_2_0
1217
1218	extern CL_API_ENTRY cl_sampler CL_API_CALL
1219	clCreateSamplerWithProperties(cl_context context,
1220	const cl_sampler_properties * sampler_properties,
1221	cl_int * errcode_ret) CL_API_SUFFIX__VERSION_2_0;
1222
1223	#endif
1224
1225	extern CL_API_ENTRY cl_int CL_API_CALL
1226	clRetainSampler(cl_sampler sampler) CL_API_SUFFIX__VERSION_1_0;
1227
1228	extern CL_API_ENTRY cl_int CL_API_CALL
1229	clReleaseSampler(cl_sampler sampler) CL_API_SUFFIX__VERSION_1_0;
1230
1231	extern CL_API_ENTRY cl_int CL_API_CALL
1232	clGetSamplerInfo(cl_sampler sampler,
1233	cl_sampler_info param_name,
1234	size_t param_value_size,
1235	void * param_value,
1236	size_t * param_value_size_ret) CL_API_SUFFIX__VERSION_1_0;
1237
1238	/* Program Object APIs */
1239	extern CL_API_ENTRY cl_program CL_API_CALL
1240	clCreateProgramWithSource(cl_context context,
1241	cl_uint count,
1242	const char ** strings,
1243	const size_t * lengths,
1244	cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_0;
1245
1246	extern CL_API_ENTRY cl_program CL_API_CALL
1247	clCreateProgramWithBinary(cl_context context,
1248	cl_uint num_devices,
1249	const cl_device_id * device_list,
1250	const size_t * lengths,
1251	const unsigned char ** binaries,
1252	cl_int * binary_status,
1253	cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_0;
1254
1255	#ifdef CL_VERSION_1_2
1256
1257	extern CL_API_ENTRY cl_program CL_API_CALL
1258	clCreateProgramWithBuiltInKernels(cl_context context,
1259	cl_uint num_devices,
1260	const cl_device_id * device_list,
1261	const char * kernel_names,
1262	cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_2;
1263
1264	#endif
1265
1266	#ifdef CL_VERSION_2_1
1267
1268	extern CL_API_ENTRY cl_program CL_API_CALL
1269	clCreateProgramWithIL(cl_context context,
1270	const void* il,
1271	size_t length,
1272	cl_int* errcode_ret) CL_API_SUFFIX__VERSION_2_1;
1273
1274	#endif
1275
1276	extern CL_API_ENTRY cl_int CL_API_CALL
1277	clRetainProgram(cl_program program) CL_API_SUFFIX__VERSION_1_0;
1278
1279	extern CL_API_ENTRY cl_int CL_API_CALL
1280	clReleaseProgram(cl_program program) CL_API_SUFFIX__VERSION_1_0;
1281
1282	extern CL_API_ENTRY cl_int CL_API_CALL
1283	clBuildProgram(cl_program program,
1284	cl_uint num_devices,
1285	const cl_device_id * device_list,
1286	const char * options,
1287	void (CL_CALLBACK * pfn_notify)(cl_program program,
1288	void * user_data),
1289	void * user_data) CL_API_SUFFIX__VERSION_1_0;
1290
1291	#ifdef CL_VERSION_1_2
1292
1293	extern CL_API_ENTRY cl_int CL_API_CALL
1294	clCompileProgram(cl_program program,
1295	cl_uint num_devices,
1296	const cl_device_id * device_list,
1297	const char * options,
1298	cl_uint num_input_headers,
1299	const cl_program * input_headers,
1300	const char ** header_include_names,
1301	void (CL_CALLBACK * pfn_notify)(cl_program program,
1302	void * user_data),
1303	void * user_data) CL_API_SUFFIX__VERSION_1_2;
1304
1305	extern CL_API_ENTRY cl_program CL_API_CALL
1306	clLinkProgram(cl_context context,
1307	cl_uint num_devices,
1308	const cl_device_id * device_list,
1309	const char * options,
1310	cl_uint num_input_programs,
1311	const cl_program * input_programs,
1312	void (CL_CALLBACK * pfn_notify)(cl_program program,
1313	void * user_data),
1314	void * user_data,
1315	cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_2;
1316
1317	#endif
1318
1319	#ifdef CL_VERSION_2_2
1320
1321	extern CL_API_ENTRY CL_API_PREFIX__VERSION_2_2_DEPRECATED cl_int CL_API_CALL
1322	clSetProgramReleaseCallback(cl_program program,
1323	void (CL_CALLBACK * pfn_notify)(cl_program program,
1324	void * user_data),
1325	void * user_data) CL_API_SUFFIX__VERSION_2_2_DEPRECATED;
1326
1327	extern CL_API_ENTRY cl_int CL_API_CALL
1328	clSetProgramSpecializationConstant(cl_program program,
1329	cl_uint spec_id,
1330	size_t spec_size,
1331	const void* spec_value) CL_API_SUFFIX__VERSION_2_2;
1332
1333	#endif
1334
1335	#ifdef CL_VERSION_1_2
1336
1337	extern CL_API_ENTRY cl_int CL_API_CALL
1338	clUnloadPlatformCompiler(cl_platform_id platform) CL_API_SUFFIX__VERSION_1_2;
1339
1340	#endif
1341
1342	extern CL_API_ENTRY cl_int CL_API_CALL
1343	clGetProgramInfo(cl_program program,
1344	cl_program_info param_name,
1345	size_t param_value_size,
1346	void * param_value,
1347	size_t * param_value_size_ret) CL_API_SUFFIX__VERSION_1_0;
1348
1349	extern CL_API_ENTRY cl_int CL_API_CALL
1350	clGetProgramBuildInfo(cl_program program,
1351	cl_device_id device,
1352	cl_program_build_info param_name,
1353	size_t param_value_size,
1354	void * param_value,
1355	size_t * param_value_size_ret) CL_API_SUFFIX__VERSION_1_0;
1356
1357	/* Kernel Object APIs */
1358	extern CL_API_ENTRY cl_kernel CL_API_CALL
1359	clCreateKernel(cl_program program,
1360	const char * kernel_name,
1361	cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_0;
1362
1363	extern CL_API_ENTRY cl_int CL_API_CALL
1364	clCreateKernelsInProgram(cl_program program,
1365	cl_uint num_kernels,
1366	cl_kernel * kernels,
1367	cl_uint * num_kernels_ret) CL_API_SUFFIX__VERSION_1_0;
1368
1369	#ifdef CL_VERSION_2_1
1370
1371	extern CL_API_ENTRY cl_kernel CL_API_CALL
1372	clCloneKernel(cl_kernel source_kernel,
1373	cl_int* errcode_ret) CL_API_SUFFIX__VERSION_2_1;
1374
1375	#endif
1376
1377	extern CL_API_ENTRY cl_int CL_API_CALL
1378	clRetainKernel(cl_kernel kernel) CL_API_SUFFIX__VERSION_1_0;
1379
1380	extern CL_API_ENTRY cl_int CL_API_CALL
1381	clReleaseKernel(cl_kernel kernel) CL_API_SUFFIX__VERSION_1_0;
1382
1383	extern CL_API_ENTRY cl_int CL_API_CALL
1384	clSetKernelArg(cl_kernel kernel,
1385	cl_uint arg_index,
1386	size_t arg_size,
1387	const void * arg_value) CL_API_SUFFIX__VERSION_1_0;
1388
1389	#ifdef CL_VERSION_2_0
1390
1391	extern CL_API_ENTRY cl_int CL_API_CALL
1392	clSetKernelArgSVMPointer(cl_kernel kernel,
1393	cl_uint arg_index,
1394	const void * arg_value) CL_API_SUFFIX__VERSION_2_0;
1395
1396	extern CL_API_ENTRY cl_int CL_API_CALL
1397	clSetKernelExecInfo(cl_kernel kernel,
1398	cl_kernel_exec_info param_name,
1399	size_t param_value_size,
1400	const void * param_value) CL_API_SUFFIX__VERSION_2_0;
1401
1402	#endif
1403
1404	extern CL_API_ENTRY cl_int CL_API_CALL
1405	clGetKernelInfo(cl_kernel kernel,
1406	cl_kernel_info param_name,
1407	size_t param_value_size,
1408	void * param_value,
1409	size_t * param_value_size_ret) CL_API_SUFFIX__VERSION_1_0;
1410
1411	#ifdef CL_VERSION_1_2
1412
1413	extern CL_API_ENTRY cl_int CL_API_CALL
1414	clGetKernelArgInfo(cl_kernel kernel,
1415	cl_uint arg_indx,
1416	cl_kernel_arg_info param_name,
1417	size_t param_value_size,
1418	void * param_value,
1419	size_t * param_value_size_ret) CL_API_SUFFIX__VERSION_1_2;
1420
1421	#endif
1422
1423	extern CL_API_ENTRY cl_int CL_API_CALL
1424	clGetKernelWorkGroupInfo(cl_kernel kernel,
1425	cl_device_id device,
1426	cl_kernel_work_group_info param_name,
1427	size_t param_value_size,
1428	void * param_value,
1429	size_t * param_value_size_ret) CL_API_SUFFIX__VERSION_1_0;
1430
1431	#ifdef CL_VERSION_2_1
1432
1433	extern CL_API_ENTRY cl_int CL_API_CALL
1434	clGetKernelSubGroupInfo(cl_kernel kernel,
1435	cl_device_id device,
1436	cl_kernel_sub_group_info param_name,
1437	size_t input_value_size,
1438	const void* input_value,
1439	size_t param_value_size,
1440	void* param_value,
1441	size_t* param_value_size_ret) CL_API_SUFFIX__VERSION_2_1;
1442
1443	#endif
1444
1445	/* Event Object APIs */
1446	extern CL_API_ENTRY cl_int CL_API_CALL
1447	clWaitForEvents(cl_uint num_events,
1448	const cl_event * event_list) CL_API_SUFFIX__VERSION_1_0;
1449
1450	extern CL_API_ENTRY cl_int CL_API_CALL
1451	clGetEventInfo(cl_event event,
1452	cl_event_info param_name,
1453	size_t param_value_size,
1454	void * param_value,
1455	size_t * param_value_size_ret) CL_API_SUFFIX__VERSION_1_0;
1456
1457	#ifdef CL_VERSION_1_1
1458
1459	extern CL_API_ENTRY cl_event CL_API_CALL
1460	clCreateUserEvent(cl_context context,
1461	cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_1;
1462
1463	#endif
1464
1465	extern CL_API_ENTRY cl_int CL_API_CALL
1466	clRetainEvent(cl_event event) CL_API_SUFFIX__VERSION_1_0;
1467
1468	extern CL_API_ENTRY cl_int CL_API_CALL
1469	clReleaseEvent(cl_event event) CL_API_SUFFIX__VERSION_1_0;
1470
1471	#ifdef CL_VERSION_1_1
1472
1473	extern CL_API_ENTRY cl_int CL_API_CALL
1474	clSetUserEventStatus(cl_event event,
1475	cl_int execution_status) CL_API_SUFFIX__VERSION_1_1;
1476
1477	extern CL_API_ENTRY cl_int CL_API_CALL
1478	clSetEventCallback(cl_event event,
1479	cl_int command_exec_callback_type,
1480	void (CL_CALLBACK * pfn_notify)(cl_event event,
1481	cl_int event_command_status,
1482	void * user_data),
1483	void * user_data) CL_API_SUFFIX__VERSION_1_1;
1484
1485	#endif
1486
1487	/* Profiling APIs */
1488	extern CL_API_ENTRY cl_int CL_API_CALL
1489	clGetEventProfilingInfo(cl_event event,
1490	cl_profiling_info param_name,
1491	size_t param_value_size,
1492	void * param_value,
1493	size_t * param_value_size_ret) CL_API_SUFFIX__VERSION_1_0;
1494
1495	/* Flush and Finish APIs */
1496	extern CL_API_ENTRY cl_int CL_API_CALL
1497	clFlush(cl_command_queue command_queue) CL_API_SUFFIX__VERSION_1_0;
1498
1499	extern CL_API_ENTRY cl_int CL_API_CALL
1500	clFinish(cl_command_queue command_queue) CL_API_SUFFIX__VERSION_1_0;
1501
1502	/* Enqueued Commands APIs */
1503	extern CL_API_ENTRY cl_int CL_API_CALL
1504	clEnqueueReadBuffer(cl_command_queue command_queue,
1505	cl_mem buffer,
1506	cl_bool blocking_read,
1507	size_t offset,
1508	size_t size,
1509	void * ptr,
1510	cl_uint num_events_in_wait_list,
1511	const cl_event * event_wait_list,
1512	cl_event * event) CL_API_SUFFIX__VERSION_1_0;
1513
1514	#ifdef CL_VERSION_1_1
1515
1516	extern CL_API_ENTRY cl_int CL_API_CALL
1517	clEnqueueReadBufferRect(cl_command_queue command_queue,
1518	cl_mem buffer,
1519	cl_bool blocking_read,
1520	const size_t * buffer_origin,
1521	const size_t * host_origin,
1522	const size_t * region,
1523	size_t buffer_row_pitch,
1524	size_t buffer_slice_pitch,
1525	size_t host_row_pitch,
1526	size_t host_slice_pitch,
1527	void * ptr,
1528	cl_uint num_events_in_wait_list,
1529	const cl_event * event_wait_list,
1530	cl_event * event) CL_API_SUFFIX__VERSION_1_1;
1531
1532	#endif
1533
1534	extern CL_API_ENTRY cl_int CL_API_CALL
1535	clEnqueueWriteBuffer(cl_command_queue command_queue,
1536	cl_mem buffer,
1537	cl_bool blocking_write,
1538	size_t offset,
1539	size_t size,
1540	const void * ptr,
1541	cl_uint num_events_in_wait_list,
1542	const cl_event * event_wait_list,
1543	cl_event * event) CL_API_SUFFIX__VERSION_1_0;
1544
1545	#ifdef CL_VERSION_1_1
1546
1547	extern CL_API_ENTRY cl_int CL_API_CALL
1548	clEnqueueWriteBufferRect(cl_command_queue command_queue,
1549	cl_mem buffer,
1550	cl_bool blocking_write,
1551	const size_t * buffer_origin,
1552	const size_t * host_origin,
1553	const size_t * region,
1554	size_t buffer_row_pitch,
1555	size_t buffer_slice_pitch,
1556	size_t host_row_pitch,
1557	size_t host_slice_pitch,
1558	const void * ptr,
1559	cl_uint num_events_in_wait_list,
1560	const cl_event * event_wait_list,
1561	cl_event * event) CL_API_SUFFIX__VERSION_1_1;
1562
1563	#endif
1564
1565	#ifdef CL_VERSION_1_2
1566
1567	extern CL_API_ENTRY cl_int CL_API_CALL
1568	clEnqueueFillBuffer(cl_command_queue command_queue,
1569	cl_mem buffer,
1570	const void * pattern,
1571	size_t pattern_size,
1572	size_t offset,
1573	size_t size,
1574	cl_uint num_events_in_wait_list,
1575	const cl_event * event_wait_list,
1576	cl_event * event) CL_API_SUFFIX__VERSION_1_2;
1577
1578	#endif
1579
1580	extern CL_API_ENTRY cl_int CL_API_CALL
1581	clEnqueueCopyBuffer(cl_command_queue command_queue,
1582	cl_mem src_buffer,
1583	cl_mem dst_buffer,
1584	size_t src_offset,
1585	size_t dst_offset,
1586	size_t size,
1587	cl_uint num_events_in_wait_list,
1588	const cl_event * event_wait_list,
1589	cl_event * event) CL_API_SUFFIX__VERSION_1_0;
1590
1591	#ifdef CL_VERSION_1_1
1592
1593	extern CL_API_ENTRY cl_int CL_API_CALL
1594	clEnqueueCopyBufferRect(cl_command_queue command_queue,
1595	cl_mem src_buffer,
1596	cl_mem dst_buffer,
1597	const size_t * src_origin,
1598	const size_t * dst_origin,
1599	const size_t * region,
1600	size_t src_row_pitch,
1601	size_t src_slice_pitch,
1602	size_t dst_row_pitch,
1603	size_t dst_slice_pitch,
1604	cl_uint num_events_in_wait_list,
1605	const cl_event * event_wait_list,
1606	cl_event * event) CL_API_SUFFIX__VERSION_1_1;
1607
1608	#endif
1609
1610	extern CL_API_ENTRY cl_int CL_API_CALL
1611	clEnqueueReadImage(cl_command_queue command_queue,
1612	cl_mem image,
1613	cl_bool blocking_read,
1614	const size_t * origin,
1615	const size_t * region,
1616	size_t row_pitch,
1617	size_t slice_pitch,
1618	void * ptr,
1619	cl_uint num_events_in_wait_list,
1620	const cl_event * event_wait_list,
1621	cl_event * event) CL_API_SUFFIX__VERSION_1_0;
1622
1623	extern CL_API_ENTRY cl_int CL_API_CALL
1624	clEnqueueWriteImage(cl_command_queue command_queue,
1625	cl_mem image,
1626	cl_bool blocking_write,
1627	const size_t * origin,
1628	const size_t * region,
1629	size_t input_row_pitch,
1630	size_t input_slice_pitch,
1631	const void * ptr,
1632	cl_uint num_events_in_wait_list,
1633	const cl_event * event_wait_list,
1634	cl_event * event) CL_API_SUFFIX__VERSION_1_0;
1635
1636	#ifdef CL_VERSION_1_2
1637
1638	extern CL_API_ENTRY cl_int CL_API_CALL
1639	clEnqueueFillImage(cl_command_queue command_queue,
1640	cl_mem image,
1641	const void * fill_color,
1642	const size_t * origin,
1643	const size_t * region,
1644	cl_uint num_events_in_wait_list,
1645	const cl_event * event_wait_list,
1646	cl_event * event) CL_API_SUFFIX__VERSION_1_2;
1647
1648	#endif
1649
1650	extern CL_API_ENTRY cl_int CL_API_CALL
1651	clEnqueueCopyImage(cl_command_queue command_queue,
1652	cl_mem src_image,
1653	cl_mem dst_image,
1654	const size_t * src_origin,
1655	const size_t * dst_origin,
1656	const size_t * region,
1657	cl_uint num_events_in_wait_list,
1658	const cl_event * event_wait_list,
1659	cl_event * event) CL_API_SUFFIX__VERSION_1_0;
1660
1661	extern CL_API_ENTRY cl_int CL_API_CALL
1662	clEnqueueCopyImageToBuffer(cl_command_queue command_queue,
1663	cl_mem src_image,
1664	cl_mem dst_buffer,
1665	const size_t * src_origin,
1666	const size_t * region,
1667	size_t dst_offset,
1668	cl_uint num_events_in_wait_list,
1669	const cl_event * event_wait_list,
1670	cl_event * event) CL_API_SUFFIX__VERSION_1_0;
1671
1672	extern CL_API_ENTRY cl_int CL_API_CALL
1673	clEnqueueCopyBufferToImage(cl_command_queue command_queue,
1674	cl_mem src_buffer,
1675	cl_mem dst_image,
1676	size_t src_offset,
1677	const size_t * dst_origin,
1678	const size_t * region,
1679	cl_uint num_events_in_wait_list,
1680	const cl_event * event_wait_list,
1681	cl_event * event) CL_API_SUFFIX__VERSION_1_0;
1682
1683	extern CL_API_ENTRY void * CL_API_CALL
1684	clEnqueueMapBuffer(cl_command_queue command_queue,
1685	cl_mem buffer,
1686	cl_bool blocking_map,
1687	cl_map_flags map_flags,
1688	size_t offset,
1689	size_t size,
1690	cl_uint num_events_in_wait_list,
1691	const cl_event * event_wait_list,
1692	cl_event * event,
1693	cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_0;
1694
1695	extern CL_API_ENTRY void * CL_API_CALL
1696	clEnqueueMapImage(cl_command_queue command_queue,
1697	cl_mem image,
1698	cl_bool blocking_map,
1699	cl_map_flags map_flags,
1700	const size_t * origin,
1701	const size_t * region,
1702	size_t * image_row_pitch,
1703	size_t * image_slice_pitch,
1704	cl_uint num_events_in_wait_list,
1705	const cl_event * event_wait_list,
1706	cl_event * event,
1707	cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_0;
1708
1709	extern CL_API_ENTRY cl_int CL_API_CALL
1710	clEnqueueUnmapMemObject(cl_command_queue command_queue,
1711	cl_mem memobj,
1712	void * mapped_ptr,
1713	cl_uint num_events_in_wait_list,
1714	const cl_event * event_wait_list,
1715	cl_event * event) CL_API_SUFFIX__VERSION_1_0;
1716
1717	#ifdef CL_VERSION_1_2
1718
1719	extern CL_API_ENTRY cl_int CL_API_CALL
1720	clEnqueueMigrateMemObjects(cl_command_queue command_queue,
1721	cl_uint num_mem_objects,
1722	const cl_mem * mem_objects,
1723	cl_mem_migration_flags flags,
1724	cl_uint num_events_in_wait_list,
1725	const cl_event * event_wait_list,
1726	cl_event * event) CL_API_SUFFIX__VERSION_1_2;
1727
1728	#endif
1729
1730	extern CL_API_ENTRY cl_int CL_API_CALL
1731	clEnqueueNDRangeKernel(cl_command_queue command_queue,
1732	cl_kernel kernel,
1733	cl_uint work_dim,
1734	const size_t * global_work_offset,
1735	const size_t * global_work_size,
1736	const size_t * local_work_size,
1737	cl_uint num_events_in_wait_list,
1738	const cl_event * event_wait_list,
1739	cl_event * event) CL_API_SUFFIX__VERSION_1_0;
1740
1741	extern CL_API_ENTRY cl_int CL_API_CALL
1742	clEnqueueNativeKernel(cl_command_queue command_queue,
1743	void (CL_CALLBACK * user_func)(void *),
1744	void * args,
1745	size_t cb_args,
1746	cl_uint num_mem_objects,
1747	const cl_mem * mem_list,
1748	const void ** args_mem_loc,
1749	cl_uint num_events_in_wait_list,
1750	const cl_event * event_wait_list,
1751	cl_event * event) CL_API_SUFFIX__VERSION_1_0;
1752
1753	#ifdef CL_VERSION_1_2
1754
1755	extern CL_API_ENTRY cl_int CL_API_CALL
1756	clEnqueueMarkerWithWaitList(cl_command_queue command_queue,
1757	cl_uint num_events_in_wait_list,
1758	const cl_event * event_wait_list,
1759	cl_event * event) CL_API_SUFFIX__VERSION_1_2;
1760
1761	extern CL_API_ENTRY cl_int CL_API_CALL
1762	clEnqueueBarrierWithWaitList(cl_command_queue command_queue,
1763	cl_uint num_events_in_wait_list,
1764	const cl_event * event_wait_list,
1765	cl_event * event) CL_API_SUFFIX__VERSION_1_2;
1766
1767	#endif
1768
1769	#ifdef CL_VERSION_2_0
1770
1771	extern CL_API_ENTRY cl_int CL_API_CALL
1772	clEnqueueSVMFree(cl_command_queue command_queue,
1773	cl_uint num_svm_pointers,
1774	void * svm_pointers[],
1775	void (CL_CALLBACK * pfn_free_func)(cl_command_queue queue,
1776	cl_uint num_svm_pointers,
1777	void * svm_pointers[],
1778	void * user_data),
1779	void * user_data,
1780	cl_uint num_events_in_wait_list,
1781	const cl_event * event_wait_list,
1782	cl_event * event) CL_API_SUFFIX__VERSION_2_0;
1783
1784	extern CL_API_ENTRY cl_int CL_API_CALL
1785	clEnqueueSVMMemcpy(cl_command_queue command_queue,
1786	cl_bool blocking_copy,
1787	void * dst_ptr,
1788	const void * src_ptr,
1789	size_t size,
1790	cl_uint num_events_in_wait_list,
1791	const cl_event * event_wait_list,
1792	cl_event * event) CL_API_SUFFIX__VERSION_2_0;
1793
1794	extern CL_API_ENTRY cl_int CL_API_CALL
1795	clEnqueueSVMMemFill(cl_command_queue command_queue,
1796	void * svm_ptr,
1797	const void * pattern,
1798	size_t pattern_size,
1799	size_t size,
1800	cl_uint num_events_in_wait_list,
1801	const cl_event * event_wait_list,
1802	cl_event * event) CL_API_SUFFIX__VERSION_2_0;
1803
1804	extern CL_API_ENTRY cl_int CL_API_CALL
1805	clEnqueueSVMMap(cl_command_queue command_queue,
1806	cl_bool blocking_map,
1807	cl_map_flags flags,
1808	void * svm_ptr,
1809	size_t size,
1810	cl_uint num_events_in_wait_list,
1811	const cl_event * event_wait_list,
1812	cl_event * event) CL_API_SUFFIX__VERSION_2_0;
1813
1814	extern CL_API_ENTRY cl_int CL_API_CALL
1815	clEnqueueSVMUnmap(cl_command_queue command_queue,
1816	void * svm_ptr,
1817	cl_uint num_events_in_wait_list,
1818	const cl_event * event_wait_list,
1819	cl_event * event) CL_API_SUFFIX__VERSION_2_0;
1820
1821	#endif
1822
1823	#ifdef CL_VERSION_2_1
1824
1825	extern CL_API_ENTRY cl_int CL_API_CALL
1826	clEnqueueSVMMigrateMem(cl_command_queue command_queue,
1827	cl_uint num_svm_pointers,
1828	const void ** svm_pointers,
1829	const size_t * sizes,
1830	cl_mem_migration_flags flags,
1831	cl_uint num_events_in_wait_list,
1832	const cl_event * event_wait_list,
1833	cl_event * event) CL_API_SUFFIX__VERSION_2_1;
1834
1835	#endif
1836
1837	#ifdef CL_VERSION_1_2
1838
1839	/* Extension function access
1840	*
1841	* Returns the extension function address for the given function name,
1842	* or NULL if a valid function can not be found. The client must
1843	* check to make sure the address is not NULL, before using or
1844	* calling the returned function address.
1845	*/
1846	extern CL_API_ENTRY void * CL_API_CALL
1847	clGetExtensionFunctionAddressForPlatform(cl_platform_id platform,
1848	const char * func_name) CL_API_SUFFIX__VERSION_1_2;
1849
1850	#endif
1851
1852	#ifdef CL_USE_DEPRECATED_OPENCL_1_0_APIS
1853	/*
1854	* WARNING:
1855	* This API introduces mutable state into the OpenCL implementation. It has been REMOVED
1856	* to better facilitate thread safety. The 1.0 API is not thread safe. It is not tested by the
1857	* OpenCL 1.1 conformance test, and consequently may not work or may not work dependably.
1858	* It is likely to be non-performant. Use of this API is not advised. Use at your own risk.
1859	*
1860	* Software developers previously relying on this API are instructed to set the command queue
1861	* properties when creating the queue, instead.
1862	*/
1863	extern CL_API_ENTRY cl_int CL_API_CALL
1864	clSetCommandQueueProperty(cl_command_queue command_queue,
1865	cl_command_queue_properties properties,
1866	cl_bool enable,
1867	cl_command_queue_properties * old_properties) CL_API_SUFFIX__VERSION_1_0_DEPRECATED;
1868	#endif /* CL_USE_DEPRECATED_OPENCL_1_0_APIS */
1869
1870	/* Deprecated OpenCL 1.1 APIs */
1871	extern CL_API_ENTRY CL_API_PREFIX__VERSION_1_1_DEPRECATED cl_mem CL_API_CALL
1872	clCreateImage2D(cl_context context,
1873	cl_mem_flags flags,
1874	const cl_image_format * image_format,
1875	size_t image_width,
1876	size_t image_height,
1877	size_t image_row_pitch,
1878	void * host_ptr,
1879	cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_1_DEPRECATED;
1880
1881	extern CL_API_ENTRY CL_API_PREFIX__VERSION_1_1_DEPRECATED cl_mem CL_API_CALL
1882	clCreateImage3D(cl_context context,
1883	cl_mem_flags flags,
1884	const cl_image_format * image_format,
1885	size_t image_width,
1886	size_t image_height,
1887	size_t image_depth,
1888	size_t image_row_pitch,
1889	size_t image_slice_pitch,
1890	void * host_ptr,
1891	cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_1_DEPRECATED;
1892
1893	extern CL_API_ENTRY CL_API_PREFIX__VERSION_1_1_DEPRECATED cl_int CL_API_CALL
1894	clEnqueueMarker(cl_command_queue command_queue,
1895	cl_event * event) CL_API_SUFFIX__VERSION_1_1_DEPRECATED;
1896
1897	extern CL_API_ENTRY CL_API_PREFIX__VERSION_1_1_DEPRECATED cl_int CL_API_CALL
1898	clEnqueueWaitForEvents(cl_command_queue command_queue,
1899	cl_uint num_events,
1900	const cl_event * event_list) CL_API_SUFFIX__VERSION_1_1_DEPRECATED;
1901
1902	extern CL_API_ENTRY CL_API_PREFIX__VERSION_1_1_DEPRECATED cl_int CL_API_CALL
1903	clEnqueueBarrier(cl_command_queue command_queue) CL_API_SUFFIX__VERSION_1_1_DEPRECATED;
1904
1905	extern CL_API_ENTRY CL_API_PREFIX__VERSION_1_1_DEPRECATED cl_int CL_API_CALL
1906	clUnloadCompiler(void) CL_API_SUFFIX__VERSION_1_1_DEPRECATED;
1907
1908	extern CL_API_ENTRY CL_API_PREFIX__VERSION_1_1_DEPRECATED void * CL_API_CALL
1909	clGetExtensionFunctionAddress(const char * func_name) CL_API_SUFFIX__VERSION_1_1_DEPRECATED;
1910
1911	/* Deprecated OpenCL 2.0 APIs */
1912	extern CL_API_ENTRY CL_API_PREFIX__VERSION_1_2_DEPRECATED cl_command_queue CL_API_CALL
1913	clCreateCommandQueue(cl_context context,
1914	cl_device_id device,
1915	cl_command_queue_properties properties,
1916	cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_2_DEPRECATED;
1917
1918	extern CL_API_ENTRY CL_API_PREFIX__VERSION_1_2_DEPRECATED cl_sampler CL_API_CALL
1919	clCreateSampler(cl_context context,
1920	cl_bool normalized_coords,
1921	cl_addressing_mode addressing_mode,
1922	cl_filter_mode filter_mode,
1923	cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_2_DEPRECATED;
1924
1925	extern CL_API_ENTRY CL_API_PREFIX__VERSION_1_2_DEPRECATED cl_int CL_API_CALL
1926	clEnqueueTask(cl_command_queue command_queue,
1927	cl_kernel kernel,
1928	cl_uint num_events_in_wait_list,
1929	const cl_event * event_wait_list,
1930	cl_event * event) CL_API_SUFFIX__VERSION_1_2_DEPRECATED;
1931
1932	#ifdef __cplusplus
1933	}
1934	#endif
1935
1936	#endif /* __OPENCL_CL_H */

注意: 瀏覽 TracBrowser 來幫助您使用儲存庫瀏覽器

source: vbox/trunk/src/VBox/Additions/3D/mesa/mesa-24.0.2/include/CL/cl.h@ 105856

以其他格式下載: