~sergiusens/libhybris/autotests

« back to all changes in this revision

Viewing changes to hybris/include/CL/cl.h

  • Committer: Package Import Robot
  • Author(s): Ricardo Salveti de Araujo
  • Date: 2013-06-04 07:33:11 UTC
  • Revision ID: package-import@ubuntu.com-20130604073311-20ldi2hm1axkvjl1
Tags: upstream-0.1.0+git20130601+dfb2e26
ImportĀ upstreamĀ versionĀ 0.1.0+git20130601+dfb2e26

Show diffs side-by-side

added added

removed removed

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