| OLD | NEW |
|---|
| (Empty) |
| 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 bo
ol 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__VE
RSION_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__VERSI
ON_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__V
ERSION_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_SU
FFIX__VERSION_1_0; | |
| 509 | |
| 510 extern CL_API_ENTRY cl_int CL_API_CALL | |
| 511 clRetainCommandQueue(cl_command_queue /* command_queue */) CL_API_SUFFIX__VERSIO
N_1_0; | |
| 512 | |
| 513 extern CL_API_ENTRY cl_int CL_API_CALL | |
| 514 clReleaseCommandQueue(cl_command_queue /* command_queue */) CL_API_SUFFIX__VERSI
ON_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_S
UFFIX__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 unsupporte
d 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 n
ot tested by the | |
| 529 * OpenCL 1.1 conformance test, and consequently may not work or may not work d
ependably. | |
| 530 * It is likely to be non-performant. Use of this API is not advised. Use at yo
ur 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__VER
SION_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__VERSIO
N_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__VERSIO
N_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__V
ERSION_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__VERSI
ON_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_S
UFFIX__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__V
ERSION_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__VE
RSION_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_A
PI_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__V
ERSION_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_S
UFFIX__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__VE
RSION_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__VERSI
ON_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__VERSI
ON_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_S
UFFIX__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 | |
| OLD | NEW |
|---|
Chromium Code Reviews
Issue 608893002:
Remove headers for CL, EGL, GLES2, KHR, VG (Closed)
Base URL: svn://svn.chromium.org/chrome/trunk/deps/third_party/mesa/