Mercurial > projects > cl4d
changeset 1:5b5ace425b37
* moved c.opencl to c.cl
* updated c.cl_gl
+ c.d3d10
| author | Trass3r |
|---|---|
| date | Wed, 14 Apr 2010 13:52:17 +0200 |
| parents | 3cea44337083 |
| children | 01d502efe0c4 |
| files | opencl/c/cl.d opencl/c/cl_gl.d opencl/c/d3d10.d opencl/c/opencl.d |
| diffstat | 4 files changed, 1152 insertions(+), 990 deletions(-) [+] |
line wrap: on
line diff
--- /dev/null Thu Jan 01 00:00:00 1970 +0000 +++ b/opencl/c/cl.d Wed Apr 14 13:52:17 2010 +0200 @@ -0,0 +1,937 @@ +/******************************************************************************* + * Copyright (c) 2008-2009 The Khronos Group Inc. + * + * Permission is hereby granted, free of charge, to any person obtaining a + * copy of this software and/or associated documentation files (the + * "Materials"), to deal in the Materials without restriction, including + * without limitation the rights to use, copy, modify, merge, publish, + * distribute, sublicense, and/or sell copies of the Materials, and to + * permit persons to whom the Materials are furnished to do so, subject to + * the following conditions: + * + * The above copyright notice and this permission notice shall be included + * in all copies or substantial portions of the Materials. + * + * THE MATERIALS ARE PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND, + * EXPRESS OR IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF + * MERCHANTABILITY, FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT. + * IN NO EVENT SHALL THE AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY + * CLAIM, DAMAGES OR OTHER LIABILITY, WHETHER IN AN ACTION OF CONTRACT, + * TORT OR OTHERWISE, ARISING FROM, OUT OF OR IN CONNECTION WITH THE + * MATERIALS OR THE USE OR OTHER DEALINGS IN THE MATERIALS. + ******************************************************************************/ + +// $Revision: 9283 $ on $Date: 2009-10-14 10:18:57 -0700 (Wed, 14 Oct 2009) $ + +module opencl.c.opencl; + +public import opencl.c.platform; + +extern(C): + +alias const(void)* + cl_platform_id, + cl_device_id, + cl_context, + cl_command_queue, + cl_mem, + cl_program, + cl_kernel, + cl_event, + cl_sampler; + +alias 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. +alias cl_ulong cl_bitfield; +alias cl_bitfield cl_device_type; +alias cl_uint cl_platform_info; +alias cl_uint cl_device_info; +alias cl_bitfield cl_device_address_info; +alias cl_bitfield cl_device_fp_config; +alias cl_uint cl_device_mem_cache_type; +alias cl_uint cl_device_local_mem_type; +alias cl_bitfield cl_device_exec_capabilities; +alias cl_bitfield cl_command_queue_properties; + +alias cl_bitfield cl_context_properties; +alias cl_uint cl_context_info; +alias cl_uint cl_command_queue_info; +alias cl_uint cl_channel_order; +alias cl_uint cl_channel_type; +alias cl_bitfield cl_mem_flags; +alias cl_uint cl_mem_object_type; +alias cl_uint cl_mem_info; +alias cl_uint cl_image_info; +alias cl_uint cl_addressing_mode; +alias cl_uint cl_filter_mode; +alias cl_uint cl_sampler_info; +alias cl_bitfield cl_map_flags; +alias cl_uint cl_program_info; +alias cl_uint cl_program_build_info; +alias cl_uint cl_build_status; +alias cl_uint cl_kernel_info; +alias cl_uint cl_kernel_work_group_info; +alias cl_uint cl_event_info; +alias cl_uint cl_command_type; +alias cl_uint cl_profiling_info; + +struct cl_image_format +{ + cl_channel_order image_channel_order; + cl_channel_type image_channel_data_type; +} + +/******************************************************************************/ + +enum +{ + // Error Codes + CL_SUCCESS = 0, + CL_DEVICE_NOT_FOUND = -1, + CL_DEVICE_NOT_AVAILABLE = -2, + CL_COMPILER_NOT_AVAILABLE = -3, + CL_MEM_OBJECT_ALLOCATION_FAILURE = -4, + CL_OUT_OF_RESOURCES = -5, + CL_OUT_OF_HOST_MEMORY = -6, + CL_PROFILING_INFO_NOT_AVAILABLE = -7, + CL_MEM_COPY_OVERLAP = -8, + CL_IMAGE_FORMAT_MISMATCH = -9, + CL_IMAGE_FORMAT_NOT_SUPPORTED = -10, + CL_BUILD_PROGRAM_FAILURE = -11, + CL_MAP_FAILURE = -12, + + CL_INVALID_VALUE = -30, + CL_INVALID_DEVICE_TYPE = -31, + CL_INVALID_PLATFORM = -32, + CL_INVALID_DEVICE = -33, + CL_INVALID_CONTEXT = -34, + CL_INVALID_QUEUE_PROPERTIES = -35, + CL_INVALID_COMMAND_QUEUE = -36, + CL_INVALID_HOST_PTR = -37, + CL_INVALID_MEM_OBJECT = -38, + CL_INVALID_IMAGE_FORMAT_DESCRIPTOR = -39, + CL_INVALID_IMAGE_SIZE = -40, + CL_INVALID_SAMPLER = -41, + CL_INVALID_BINARY = -42, + CL_INVALID_BUILD_OPTIONS = -43, + CL_INVALID_PROGRAM = -44, + CL_INVALID_PROGRAM_EXECUTABLE = -45, + CL_INVALID_KERNEL_NAME = -46, + CL_INVALID_KERNEL_DEFINITION = -47, + CL_INVALID_KERNEL = -48, + CL_INVALID_ARG_INDEX = -49, + CL_INVALID_ARG_VALUE = -50, + CL_INVALID_ARG_SIZE = -51, + CL_INVALID_KERNEL_ARGS = -52, + CL_INVALID_WORK_DIMENSION = -53, + CL_INVALID_WORK_GROUP_SIZE = -54, + CL_INVALID_WORK_ITEM_SIZE = -55, + CL_INVALID_GLOBAL_OFFSET = -56, + CL_INVALID_EVENT_WAIT_LIST = -57, + CL_INVALID_EVENT = -58, + CL_INVALID_OPERATION = -59, + CL_INVALID_GL_OBJECT = -60, + CL_INVALID_BUFFER_SIZE = -61, + CL_INVALID_MIP_LEVEL = -62, + CL_INVALID_GLOBAL_WORK_SIZE = -63, + + // OpenCL Version + CL_VERSION_1_0 = 1, + + // cl_bool + CL_FALSE = 0, + CL_TRUE = 1, + + // cl_platform_info + CL_PLATFORM_PROFILE = 0x0900, + CL_PLATFORM_VERSION = 0x0901, + CL_PLATFORM_NAME = 0x0902, + CL_PLATFORM_VENDOR = 0x0903, + CL_PLATFORM_EXTENSIONS = 0x0904, + + // cl_device_type - bitfield + CL_DEVICE_TYPE_DEFAULT = (1 << 0), + CL_DEVICE_TYPE_CPU = (1 << 1), + CL_DEVICE_TYPE_GPU = (1 << 2), + CL_DEVICE_TYPE_ACCELERATOR = (1 << 3), + CL_DEVICE_TYPE_ALL = 0xFFFFFFFF, + + // cl_device_info + CL_DEVICE_TYPE = 0x1000, + CL_DEVICE_VENDOR_ID = 0x1001, + CL_DEVICE_MAX_COMPUTE_UNITS = 0x1002, + CL_DEVICE_MAX_WORK_ITEM_DIMENSIONS = 0x1003, + CL_DEVICE_MAX_WORK_GROUP_SIZE = 0x1004, + CL_DEVICE_MAX_WORK_ITEM_SIZES = 0x1005, + CL_DEVICE_PREFERRED_VECTOR_WIDTH_CHAR = 0x1006, + CL_DEVICE_PREFERRED_VECTOR_WIDTH_SHORT = 0x1007, + CL_DEVICE_PREFERRED_VECTOR_WIDTH_INT = 0x1008, + CL_DEVICE_PREFERRED_VECTOR_WIDTH_LONG = 0x1009, + CL_DEVICE_PREFERRED_VECTOR_WIDTH_FLOAT = 0x100A, + CL_DEVICE_PREFERRED_VECTOR_WIDTH_DOUBLE = 0x100B, + CL_DEVICE_MAX_CLOCK_FREQUENCY = 0x100C, + CL_DEVICE_ADDRESS_BITS = 0x100D, + CL_DEVICE_MAX_READ_IMAGE_ARGS = 0x100E, + CL_DEVICE_MAX_WRITE_IMAGE_ARGS = 0x100F, + CL_DEVICE_MAX_MEM_ALLOC_SIZE = 0x1010, + CL_DEVICE_IMAGE2D_MAX_WIDTH = 0x1011, + CL_DEVICE_IMAGE2D_MAX_HEIGHT = 0x1012, + CL_DEVICE_IMAGE3D_MAX_WIDTH = 0x1013, + CL_DEVICE_IMAGE3D_MAX_HEIGHT = 0x1014, + CL_DEVICE_IMAGE3D_MAX_DEPTH = 0x1015, + CL_DEVICE_IMAGE_SUPPORT = 0x1016, + CL_DEVICE_MAX_PARAMETER_SIZE = 0x1017, + CL_DEVICE_MAX_SAMPLERS = 0x1018, + CL_DEVICE_MEM_BASE_ADDR_ALIGN = 0x1019, + CL_DEVICE_MIN_DATA_TYPE_ALIGN_SIZE = 0x101A, + CL_DEVICE_SINGLE_FP_CONFIG = 0x101B, + CL_DEVICE_GLOBAL_MEM_CACHE_TYPE = 0x101C, + CL_DEVICE_GLOBAL_MEM_CACHELINE_SIZE = 0x101D, + CL_DEVICE_GLOBAL_MEM_CACHE_SIZE = 0x101E, + CL_DEVICE_GLOBAL_MEM_SIZE = 0x101F, + CL_DEVICE_MAX_CONSTANT_BUFFER_SIZE = 0x1020, + CL_DEVICE_MAX_CONSTANT_ARGS = 0x1021, + CL_DEVICE_LOCAL_MEM_TYPE = 0x1022, + CL_DEVICE_LOCAL_MEM_SIZE = 0x1023, + CL_DEVICE_ERROR_CORRECTION_SUPPORT = 0x1024, + CL_DEVICE_PROFILING_TIMER_RESOLUTION = 0x1025, + CL_DEVICE_ENDIAN_LITTLE = 0x1026, + CL_DEVICE_AVAILABLE = 0x1027, + CL_DEVICE_COMPILER_AVAILABLE = 0x1028, + CL_DEVICE_EXECUTION_CAPABILITIES = 0x1029, + CL_DEVICE_QUEUE_PROPERTIES = 0x102A, + CL_DEVICE_NAME = 0x102B, + CL_DEVICE_VENDOR = 0x102C, + CL_DRIVER_VERSION = 0x102D, + CL_DEVICE_PROFILE = 0x102E, + CL_DEVICE_VERSION = 0x102F, + CL_DEVICE_EXTENSIONS = 0x1030, + CL_DEVICE_PLATFORM = 0x1031, + + // cl_device_fp_config - bitfield + CL_FP_DENORM = (1 << 0), + CL_FP_INF_NAN = (1 << 1), + CL_FP_ROUND_TO_NEAREST = (1 << 2), + CL_FP_ROUND_TO_ZERO = (1 << 3), + CL_FP_ROUND_TO_INF = (1 << 4), + CL_FP_FMA = (1 << 5), + + // cl_device_mem_cache_type + CL_NONE = 0x0, + CL_READ_ONLY_CACHE = 0x1, + CL_READ_WRITE_CACHE = 0x2, + + // cl_device_local_mem_type + CL_LOCAL = 0x1, + CL_GLOBAL = 0x2, + + // cl_device_exec_capabilities - bitfield + CL_EXEC_KERNEL = (1 << 0), + CL_EXEC_NATIVE_KERNEL = (1 << 1), + + // cl_command_queue_properties - bitfield + CL_QUEUE_OUT_OF_ORDER_EXEC_MODE_ENABLE = (1 << 0), + CL_QUEUE_PROFILING_ENABLE = (1 << 1), + + // cl_context_info + CL_CONTEXT_REFERENCE_COUNT = 0x1080, + CL_CONTEXT_DEVICES = 0x1081, + CL_CONTEXT_PROPERTIES = 0x1082, + + // cl_context_properties + CL_CONTEXT_PLATFORM = 0x1084, + + // cl_command_queue_info + CL_QUEUE_CONTEXT = 0x1090, + CL_QUEUE_DEVICE = 0x1091, + CL_QUEUE_REFERENCE_COUNT = 0x1092, + CL_QUEUE_PROPERTIES = 0x1093, + + // cl_mem_flags - bitfield + CL_MEM_READ_WRITE = (1 << 0), + CL_MEM_WRITE_ONLY = (1 << 1), + CL_MEM_READ_ONLY = (1 << 2), + CL_MEM_USE_HOST_PTR = (1 << 3), + CL_MEM_ALLOC_HOST_PTR = (1 << 4), + CL_MEM_COPY_HOST_PTR = (1 << 5), + + // cl_channel_order + CL_R = 0x10B0, + CL_A = 0x10B1, + CL_RG = 0x10B2, + CL_RA = 0x10B3, + CL_RGB = 0x10B4, + CL_RGBA = 0x10B5, + CL_BGRA = 0x10B6, + CL_ARGB = 0x10B7, + CL_INTENSITY = 0x10B8, + CL_LUMINANCE = 0x10B9, + + // cl_channel_type + CL_SNORM_INT8 = 0x10D0, + CL_SNORM_INT16 = 0x10D1, + CL_UNORM_INT8 = 0x10D2, + CL_UNORM_INT16 = 0x10D3, + CL_UNORM_SHORT_565 = 0x10D4, + CL_UNORM_SHORT_555 = 0x10D5, + CL_UNORM_INT_101010 = 0x10D6, + CL_SIGNED_INT8 = 0x10D7, + CL_SIGNED_INT16 = 0x10D8, + CL_SIGNED_INT32 = 0x10D9, + CL_UNSIGNED_INT8 = 0x10DA, + CL_UNSIGNED_INT16 = 0x10DB, + CL_UNSIGNED_INT32 = 0x10DC, + CL_HALF_FLOAT = 0x10DD, + CL_FLOAT = 0x10DE, + + // cl_mem_object_type + CL_MEM_OBJECT_BUFFER = 0x10F0, + CL_MEM_OBJECT_IMAGE2D = 0x10F1, + CL_MEM_OBJECT_IMAGE3D = 0x10F2, + + // cl_mem_info + CL_MEM_TYPE = 0x1100, + CL_MEM_FLAGS = 0x1101, + CL_MEM_SIZE = 0x1102, + CL_MEM_HOST_PTR = 0x1103, + CL_MEM_MAP_COUNT = 0x1104, + CL_MEM_REFERENCE_COUNT = 0x1105, + CL_MEM_CONTEXT = 0x1106, + + // cl_image_info + CL_IMAGE_FORMAT = 0x1110, + CL_IMAGE_ELEMENT_SIZE = 0x1111, + CL_IMAGE_ROW_PITCH = 0x1112, + CL_IMAGE_SLICE_PITCH = 0x1113, + CL_IMAGE_WIDTH = 0x1114, + CL_IMAGE_HEIGHT = 0x1115, + CL_IMAGE_DEPTH = 0x1116, + + // cl_addressing_mode + CL_ADDRESS_NONE = 0x1130, + CL_ADDRESS_CLAMP_TO_EDGE = 0x1131, + CL_ADDRESS_CLAMP = 0x1132, + CL_ADDRESS_REPEAT = 0x1133, + + // cl_filter_mode + CL_FILTER_NEAREST = 0x1140, + CL_FILTER_LINEAR = 0x1141, + + // cl_sampler_info + CL_SAMPLER_REFERENCE_COUNT = 0x1150, + CL_SAMPLER_CONTEXT = 0x1151, + CL_SAMPLER_NORMALIZED_COORDS = 0x1152, + CL_SAMPLER_ADDRESSING_MODE = 0x1153, + CL_SAMPLER_FILTER_MODE = 0x1154, + + // cl_map_flags - bitfield + CL_MAP_READ = (1 << 0), + CL_MAP_WRITE = (1 << 1), + + // cl_program_info + CL_PROGRAM_REFERENCE_COUNT = 0x1160, + CL_PROGRAM_CONTEXT = 0x1161, + CL_PROGRAM_NUM_DEVICES = 0x1162, + CL_PROGRAM_DEVICES = 0x1163, + CL_PROGRAM_SOURCE = 0x1164, + CL_PROGRAM_BINARY_SIZES = 0x1165, + CL_PROGRAM_BINARIES = 0x1166, + + // cl_program_build_info + CL_PROGRAM_BUILD_STATUS = 0x1181, + CL_PROGRAM_BUILD_OPTIONS = 0x1182, + CL_PROGRAM_BUILD_LOG = 0x1183, + + // cl_build_status + CL_BUILD_SUCCESS = 0, + CL_BUILD_NONE = -1, + CL_BUILD_ERROR = -2, + CL_BUILD_IN_PROGRESS = -3, + + // cl_kernel_info + CL_KERNEL_FUNCTION_NAME = 0x1190, + CL_KERNEL_NUM_ARGS = 0x1191, + CL_KERNEL_REFERENCE_COUNT = 0x1192, + CL_KERNEL_CONTEXT = 0x1193, + CL_KERNEL_PROGRAM = 0x1194, + + // cl_kernel_work_group_info + CL_KERNEL_WORK_GROUP_SIZE = 0x11B0, + CL_KERNEL_COMPILE_WORK_GROUP_SIZE = 0x11B1, + CL_KERNEL_LOCAL_MEM_SIZE = 0x11B2, + + // cl_event_info + CL_EVENT_COMMAND_QUEUE = 0x11D0, + CL_EVENT_COMMAND_TYPE = 0x11D1, + CL_EVENT_REFERENCE_COUNT = 0x11D2, + CL_EVENT_COMMAND_EXECUTION_STATUS = 0x11D3, + + // cl_command_type + CL_COMMAND_NDRANGE_KERNEL = 0x11F0, + CL_COMMAND_TASK = 0x11F1, + CL_COMMAND_NATIVE_KERNEL = 0x11F2, + CL_COMMAND_READ_BUFFER = 0x11F3, + CL_COMMAND_WRITE_BUFFER = 0x11F4, + CL_COMMAND_COPY_BUFFER = 0x11F5, + CL_COMMAND_READ_IMAGE = 0x11F6, + CL_COMMAND_WRITE_IMAGE = 0x11F7, + CL_COMMAND_COPY_IMAGE = 0x11F8, + CL_COMMAND_COPY_IMAGE_TO_BUFFER = 0x11F9, + CL_COMMAND_COPY_BUFFER_TO_IMAGE = 0x11FA, + CL_COMMAND_MAP_BUFFER = 0x11FB, + CL_COMMAND_MAP_IMAGE = 0x11FC, + CL_COMMAND_UNMAP_MEM_OBJECT = 0x11FD, + CL_COMMAND_MARKER = 0x11FE, + CL_COMMAND_ACQUIRE_GL_OBJECTS = 0x11FF, + CL_COMMAND_RELEASE_GL_OBJECTS = 0x1200, + + // command execution status + CL_COMPLETE = 0x0, + CL_RUNNING = 0x1, + CL_SUBMITTED = 0x2, + CL_QUEUED = 0x3, + + // cl_profiling_info + CL_PROFILING_COMMAND_QUEUED = 0x1280, + CL_PROFILING_COMMAND_SUBMIT = 0x1281, + CL_PROFILING_COMMAND_START = 0x1282, + CL_PROFILING_COMMAND_END = 0x1283 +} + +/********************************************************************************************************/ + +// Platform API +cl_int clGetPlatformIDs( + cl_uint num_entries, + cl_platform_id* platforms, + cl_uint* num_platforms +); + +cl_int clGetPlatformInfo( + cl_platform_id platform, + cl_platform_info param_name, + size_t param_value_size, + void* param_value, + size_t* param_value_size_ret +); + +// Device APIs +cl_int clGetDeviceIDs( + cl_platform_id platform, + cl_device_type device_type, + cl_uint num_entries, + cl_device_id* devices, + cl_uint* num_devices +); + +cl_int clGetDeviceInfo( + cl_device_id device, + cl_device_info param_name, + size_t param_value_size, + void* param_value, + size_t* param_value_size_ret +); + +// Context APIs + +typedef void function( + const(char)*, + const(void)*, + size_t, + const(void)* +) cl_logging_fn; + +cl_context clCreateContext( + const(cl_context_properties)* properties, + cl_uint num_devices, + const(cl_device_id)* devices, + cl_logging_fn pfn_notify, + void* user_data, + cl_int* errcode_ret +); + +cl_context clCreateContextFromType( + const(cl_context_properties)* properties, + cl_device_type device_type, + cl_logging_fn pfn_notify, + void* user_data, + cl_int* errcode_ret +); + +cl_int clRetainContext( + cl_context context +); + +cl_int clReleaseContext( + cl_context context +); + +cl_int clGetContextInfo( + cl_context context, + cl_context_info param_name, + size_t param_value_size, + void* param_value, + size_t* param_value_size_ret +); + +// Command Queue APIs +cl_command_queue clCreateCommandQueue( + cl_context context, + cl_device_id device, + cl_command_queue_properties properties, + cl_int* errcode_ret +); + +cl_int clRetainCommandQueue( + cl_command_queue command_queue +); + +cl_int clReleaseCommandQueue( + cl_command_queue command_queue +); + +cl_int clGetCommandQueueInfo( + cl_command_queue command_queue, + cl_command_queue_info param_name, + size_t param_value_size, + void * param_value, + size_t * param_value_size_ret +); + +cl_int clSetCommandQueueProperty( + cl_command_queue command_queue, + cl_command_queue_properties properties, + cl_bool enable, + cl_command_queue_properties* old_properties +); + +// Memory Object APIs +cl_mem clCreateBuffer( + cl_context context, + cl_mem_flags flags, + size_t size, + void * host_ptr, + cl_int * errcode_ret +); + +cl_mem clCreateImage2D( + cl_context context, + cl_mem_flags flags, + const(cl_image_format)* image_format, + size_t image_width, + size_t image_height, + size_t image_row_pitch, + void* host_ptr, + cl_int* errcode_ret +); + +cl_mem clCreateImage3D( + cl_context context, + cl_mem_flags flags, + const(cl_image_format)* image_format, + size_t image_width, + size_t image_height, + size_t image_depth, + size_t image_row_pitch, + size_t image_slice_pitch, + void* host_ptr, + cl_int* errcode_ret +); + +cl_int clRetainMemObject( + cl_mem memobj +); + +cl_int clReleaseMemObject( + cl_mem memobj +); + +cl_int clGetSupportedImageFormats( + cl_context context, + cl_mem_flags flags, + cl_mem_object_type image_type, + cl_uint num_entries, + cl_image_format* image_formats, + cl_uint* num_image_formats +); + +cl_int clGetMemObjectInfo( + cl_mem memobj, + cl_mem_info param_name, + size_t param_value_size, + void* param_value, + size_t* param_value_size_ret +); + +cl_int clGetImageInfo( + cl_mem image, + cl_image_info param_name, + size_t param_value_size, + void * param_value, + size_t * param_value_size_ret +); + +// Sampler APIs +cl_sampler clCreateSampler( + cl_context context, + cl_bool normalized_coords, + cl_addressing_mode addressing_mode, + cl_filter_mode filter_mode, + cl_int* errcode_ret +); + +cl_int clRetainSampler( + cl_sampler sampler +); + +cl_int clReleaseSampler( + cl_sampler sampler +); + +cl_int clGetSamplerInfo( + cl_sampler sampler, + cl_sampler_info param_name, + size_t param_value_size, + void* param_value, + size_t* param_value_size_ret +); + +// Program Object APIs +cl_program clCreateProgramWithSource( + cl_context context, + cl_uint count, + const(char*)* strings, + const(size_t)* lengths, + cl_int* errcode_ret +); + +cl_program clCreateProgramWithBinary( + cl_context context, + cl_uint num_devices, + const(cl_device_id)* device_list, + const(size_t)* lengths, + const(ubyte*)* binaries, + cl_int* binary_status, + cl_int* errcode_ret +); + +cl_int clRetainProgram( + cl_program program +); + +cl_int clReleaseProgram( + cl_program program +); + +cl_int clBuildProgram( + cl_program program, + cl_uint num_devices, + const(cl_device_id)* device_list, + const(char)* options, + void function( + cl_program program, + void* user_data + ) pfn_notify, + void* user_data +); + +cl_int clUnloadCompiler(); + +cl_int clGetProgramInfo( + cl_program program, + cl_program_info param_name, + size_t param_value_size, + void* param_value, + size_t* param_value_size_ret +); + +cl_int clGetProgramBuildInfo( + cl_program program, + cl_device_id device, + cl_program_build_info param_name, + size_t param_value_size, + void* param_value, + size_t* param_value_size_ret +); + +// Kernel Object APIs +cl_kernel clCreateKernel( + cl_program program, + const(char)* kernel_name, + cl_int* errcode_ret +); + +cl_int clCreateKernelsInProgram( + cl_program program, + cl_uint num_kernels, + cl_kernel* kernels, + cl_uint* num_kernels_ret +); + +cl_int clRetainKernel( + cl_kernel kernel +); + +cl_int clReleaseKernel( + cl_kernel kernel +); + +cl_int clSetKernelArg( + cl_kernel kernel, + cl_uint arg_indx, + size_t arg_size, + const(void)* arg_value +); + +cl_int clGetKernelInfo( + cl_kernel kernel, + cl_kernel_info param_name, + size_t param_value_size, + void* param_value, + size_t* param_value_size_ret +); + +cl_int clGetKernelWorkGroupInfo( + cl_kernel kernel, + cl_device_id device, + cl_kernel_work_group_info param_name, + size_t param_value_size, + void* param_value, + size_t* param_value_size_ret +); + +// Event Object APIs +cl_int clWaitForEvents( + cl_uint num_events, + const(cl_event)* event_list +); + +cl_int clGetEventInfo( + cl_event event, + cl_event_info param_name, + size_t param_value_size, + void* param_value, + size_t* param_value_size_ret +); + +cl_int clRetainEvent( + cl_event event +); + +cl_int clReleaseEvent( + cl_event event +); + +// Profiling APIs +cl_int clGetEventProfilingInfo( + cl_event event, + cl_profiling_info param_name, + size_t param_value_size, + void* param_value, + size_t* param_value_size_ret +); + +// Flush and Finish APIs +cl_int clFlush( + cl_command_queue command_queue +); + +cl_int clFinish( + cl_command_queue command_queue +); + +// Enqueued Commands APIs +cl_int clEnqueueReadBuffer( + cl_command_queue command_queue, + cl_mem buffer, + cl_bool blocking_read, + size_t offset, + size_t cb, + void * ptr, + cl_uint num_events_in_wait_list, + const(cl_event)* event_wait_list, + cl_event* event +); + +cl_int clEnqueueWriteBuffer( + cl_command_queue command_queue, + cl_mem buffer, + cl_bool blocking_write, + size_t offset, + size_t cb, + const(void)* ptr, + cl_uint num_events_in_wait_list, + const(cl_event)* event_wait_list, + cl_event* event +); + +cl_int clEnqueueCopyBuffer( + cl_command_queue command_queue, + cl_mem src_buffer, + cl_mem dst_buffer, + size_t src_offset, + size_t dst_offset, + size_t cb, + cl_uint num_events_in_wait_list, + const(cl_event)* event_wait_list, + cl_event* event +); + +cl_int clEnqueueReadImage( + cl_command_queue command_queue, + cl_mem image, + cl_bool blocking_read, + const(size_t)* origin[3], + const(size_t)* region[3], + size_t row_pitch, + size_t slice_pitch, + void* ptr, + cl_uint num_events_in_wait_list, + const(cl_event)* event_wait_list, + cl_event* event +); + +cl_int clEnqueueWriteImage( + cl_command_queue command_queue, + cl_mem image, + cl_bool blocking_write, + const(size_t)* origin[3], + const(size_t)* region[3], + size_t input_row_pitch, + size_t input_slice_pitch, + const(void)* ptr, + cl_uint num_events_in_wait_list, + const(cl_event)* event_wait_list, + cl_event* event +); + +cl_int clEnqueueCopyImage( + cl_command_queue command_queue, + cl_mem src_image, + cl_mem dst_image, + const(size_t)* src_origin[3], + const(size_t)* dst_origin[3], + const(size_t)* region[3], + cl_uint num_events_in_wait_list, + const(cl_event)* event_wait_list, + cl_event* event +); + +cl_int clEnqueueCopyImageToBuffer( + cl_command_queue command_queue, + cl_mem src_image, + cl_mem dst_buffer, + const(size_t)* src_origin[3], + const(size_t)* region[3], + size_t dst_offset, + cl_uint num_events_in_wait_list, + const(cl_event)* event_wait_list, + cl_event* event +); + +cl_int clEnqueueCopyBufferToImage( + cl_command_queue command_queue, + cl_mem src_buffer, + cl_mem dst_image, + size_t src_offset, + const(size_t)* dst_origin[3], + const(size_t)* region[3], + cl_uint num_events_in_wait_list, + const(cl_event)* event_wait_list, + cl_event* event +); + +void* clEnqueueMapBuffer( + cl_command_queue command_queue, + cl_mem buffer, + cl_bool blocking_map, + cl_map_flags map_flags, + size_t offset, + size_t cb, + cl_uint num_events_in_wait_list, + const(cl_event)* event_wait_list, + cl_event* event, + cl_int* errcode_ret +); + +void* clEnqueueMapImage( + cl_command_queue command_queue, + cl_mem image, + cl_bool blocking_map, + cl_map_flags map_flags, + const(size_t)* origin[3], + const(size_t)* region[3], + size_t* image_row_pitch, + size_t* image_slice_pitch, + cl_uint num_events_in_wait_list, + const(cl_event)* event_wait_list, + cl_event* event, + cl_int* errcode_ret +); + +cl_int clEnqueueUnmapMemObject( + cl_command_queue command_queue, + cl_mem memobj, + void* mapped_ptr, + cl_uint num_events_in_wait_list, + const(cl_event)* event_wait_list, + cl_event* event +); + +cl_int clEnqueueNDRangeKernel( + cl_command_queue command_queue, + cl_kernel kernel, + cl_uint work_dim, + const(size_t)* global_work_offset, + const(size_t)* global_work_size, + const(size_t)* local_work_size, + cl_uint num_events_in_wait_list, + const(cl_event)* event_wait_list, + cl_event* event +); + +cl_int clEnqueueTask( + cl_command_queue command_queue, + cl_kernel kernel, + cl_uint num_events_in_wait_list, + const(cl_event)* event_wait_list, + cl_event* event +); + +cl_int clEnqueueNativeKernel( + cl_command_queue command_queue, + void function( + void* + ) user_func, + void* args, + size_t cb_args, + cl_uint num_mem_objects, + const(cl_mem)* mem_list, + const(void*)* args_mem_loc, + cl_uint num_events_in_wait_list, + const(cl_event)* event_wait_list, + cl_event* event +); + +cl_int clEnqueueMarker( + cl_command_queue command_queue, + cl_event* event +); + +cl_int clEnqueueWaitForEvents( + cl_command_queue command_queue, + cl_uint num_events, + const(cl_event)* event_list +); + +cl_int clEnqueueBarrier( + cl_command_queue command_queue +); + +//Extension function access +// +// Returns the extension function address for the given function name, +// or NULL if a valid function can not be found. The client must +// check to make sure the address is not NULL, before using or +// calling the returned function address. +// +void* clGetExtensionFunctionAddress(const(char)* func_name); \ No newline at end of file
--- a/opencl/c/cl_gl.d Wed Dec 02 17:40:59 2009 +0100 +++ b/opencl/c/cl_gl.d Wed Apr 14 13:52:17 2010 +0200 @@ -21,92 +21,129 @@ * MATERIALS OR THE USE OR OTHER DEALINGS IN THE MATERIALS. **********************************************************************************/ -// $Revision: 8748 $ on $Date: 2009-08-27 04:24:36 -0700 (Thu, 27 Aug 2009) $ +// $Revision: 10424 $ on $Date: 2010-02-17 14:34:49 -0800 (Wed, 17 Feb 2010) $ +/** + * cl_gl.h contains Khronos-approved (KHR) OpenCL extensions which have + * OpenGL dependencies. The application is responsible for #including + * OpenGL or OpenGL ES headers before #including cl_gl.h. + */ module opencl.c.cl_gl; -import opencl.c.platform; -import opencl.c.opencl; +//import opencl.c.platform; +import opencl.c.cl; extern(C): -alias cl_uint cl_gl_object_type; -alias cl_uint cl_gl_texture_info; -alias cl_uint cl_gl_platform_info; +typedef cl_uint cl_gl_object_type; +typedef cl_uint cl_gl_texture_info; +typedef cl_uint cl_gl_platform_info; enum { // cl_gl_object_type - CL_GL_OBJECT_BUFFER = 0x2000, - CL_GL_OBJECT_TEXTURE2D = 0x2001, - CL_GL_OBJECT_TEXTURE3D = 0x2002, - CL_GL_OBJECT_RENDERBUFFER = 0x2003, + CL_GL_OBJECT_BUFFER = 0x2000, + CL_GL_OBJECT_TEXTURE2D = 0x2001, + CL_GL_OBJECT_TEXTURE3D = 0x2002, + CL_GL_OBJECT_RENDERBUFFER = 0x2003, // cl_gl_texture_info - CL_GL_TEXTURE_TARGET = 0x2004, - CL_GL_MIPMAP_LEVEL = 0x2005, + CL_GL_TEXTURE_TARGET = 0x2004, + CL_GL_MIPMAP_LEVEL = 0x2005, } cl_mem clCreateFromGLBuffer( - cl_context /* context */, - cl_mem_flags /* flags */, - GLuint /* bufobj */, - int* /* errcode_ret */ + cl_context context, + cl_mem_flags flags, + cl_GLuint bufobj, + int* errcode_ret ); cl_mem clCreateFromGLTexture2D( - cl_context /* context */, - cl_mem_flags /* flags */, - GLenum /* target */, - GLint /* miplevel */, - GLuint /* texture */, - cl_int* /* errcode_ret */ + cl_context context, + cl_mem_flags flags, + cl_GLenum target, + cl_GLint miplevel, + cl_GLuint texture, + cl_int* errcode_ret ); cl_mem clCreateFromGLTexture3D( - cl_context /* context */, - cl_mem_flags /* flags */, - GLenum /* target */, - GLint /* miplevel */, - GLuint /* texture */, - cl_int* /* errcode_ret */ + cl_context context, + cl_mem_flags flags, + cl_GLenum target, + cl_GLint miplevel, + cl_GLuint texture, + cl_int* errcode_ret ); cl_mem clCreateFromGLRenderbuffer( - cl_context /* context */, - cl_mem_flags /* flags */, - GLuint /* renderbuffer */, - cl_int* /* errcode_ret */ + cl_context context, + cl_mem_flags flags, + cl_GLuint renderbuffer, + cl_int* errcode_ret ); cl_int clGetGLObjectInfo( - cl_mem /* memobj */, - cl_gl_object_type* /* gl_object_type */, - GLuint* /* gl_object_name */ + cl_mem memobj, + cl_gl_object_type* gl_object_type, + cl_GLuint* gl_object_name ); - + cl_int clGetGLTextureInfo( - cl_mem /* memobj */, - cl_gl_texture_info /* param_name */, - size_t /* param_value_size */, - void* /* param_value */, - size_t* /* param_value_size_ret */ + cl_mem memobj, + cl_gl_texture_info param_name, + size_t param_value_size, + void* param_value, + size_t* param_value_size_ret ); cl_int clEnqueueAcquireGLObjects( - cl_command_queue /* queue */, - cl_uint /* num_objects */, - const(cl_mem)* /* mem_objects */, - cl_uint /* num_events_in_wait_list */, - const(cl_event)* /* event_wait_list */, - cl_event* /* event */ + cl_command_queue queue, + cl_uint num_objects, + const(cl_mem)* mem_objects, + cl_uint num_events_in_wait_list, + const(cl_event)* event_wait_list, + cl_event* event ); cl_int clEnqueueReleaseGLObjects( - cl_command_queue /* queue */, - cl_uint /* num_objects */, - const(cl_mem)* /* mem_objects */, - cl_uint /* num_events_in_wait_list */, - const(cl_event)* /* event_wait_list */, - cl_event* /* event */ + cl_command_queue queue, + cl_uint num_objects, + const(cl_mem)* mem_objects, + cl_uint num_events_in_wait_list, + const(cl_event)* event_wait_list, + cl_event* event +); + + +// cl_khr_gl_sharing extension + +const cl_khr_gl_sharing = 1; + +typedef cl_uint cl_gl_context_info; + +enum +{ + // Additional Error Codes + CL_INVALID_GL_SHAREGROUP_REFERENCE_KHR = -1000, + + // cl_gl_context_info + CL_CURRENT_DEVICE_FOR_GL_CONTEXT_KHR = 0x2006, + CL_DEVICES_FOR_GL_CONTEXT_KHR = 0x2007, + + // Additional cl_context_properties + CL_GL_CONTEXT_KHR = 0x2008, + CL_EGL_DISPLAY_KHR = 0x2009, + CL_GLX_DISPLAY_KHR = 0x200A, + CL_WGL_HDC_KHR = 0x200B, + CL_CGL_SHAREGROUP_KHR = 0x200C, +} + +cl_int clGetGLContextInfoKHR( + const(cl_context_properties)* properties, + cl_gl_context_info param_name, + size_t param_value_size, + void* param_value, + size_t* param_value_size_ret ); \ No newline at end of file
--- /dev/null Thu Jan 01 00:00:00 1970 +0000 +++ b/opencl/c/d3d10.d Wed Apr 14 13:52:17 2010 +0200 @@ -0,0 +1,125 @@ +/********************************************************************************** + * Copyright (c) 2008-2009 The Khronos Group Inc. + * + * Permission is hereby granted, free of charge, to any person obtaining a + * copy of this software and/or associated documentation files (the + * "Materials"), to deal in the Materials without restriction, including + * without limitation the rights to use, copy, modify, merge, publish, + * distribute, sublicense, and/or sell copies of the Materials, and to + * permit persons to whom the Materials are furnished to do so, subject to + * the following conditions: + * + * The above copyright notice and this permission notice shall be included + * in all copies or substantial portions of the Materials. + * + * THE MATERIALS ARE PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND, + * EXPRESS OR IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF + * MERCHANTABILITY, FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT. + * IN NO EVENT SHALL THE AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY + * CLAIM, DAMAGES OR OTHER LIABILITY, WHETHER IN AN ACTION OF CONTRACT, + * TORT OR OTHERWISE, ARISING FROM, OUT OF OR IN CONNECTION WITH THE + * MATERIALS OR THE USE OR OTHER DEALINGS IN THE MATERIALS. + **********************************************************************************/ + +// $Revision: 10911 $ on $Date: 2010-04-05 14:41:26 -0700 (Mon, 05 Apr 2010) $ + +module opencl.c.d3d10; + +//import d3d10; +import opencl.c.cl; +import opencl.c.platform; + +extern(C): + +/******************************************************************************/ + +const cl_khr_d3d10_sharing = 1; + +typedef cl_uint cl_d3d10_device_source_khr; +typedef cl_uint cl_d3d10_device_set_khr; + +/******************************************************************************/ + +enum +{ +// Error Codes + CL_INVALID_D3D10_DEVICE_KHR = -1002, + CL_INVALID_D3D10_RESOURCE_KHR = -1003, + CL_D3D10_RESOURCE_ALREADY_ACQUIRED_KHR = -1004, + CL_D3D10_RESOURCE_NOT_ACQUIRED_KHR = -1005, + +// cl_d3d10_device_source_nv + CL_D3D10_DEVICE_KHR = 0x4010, + CL_D3D10_DXGI_ADAPTER_KHR = 0x4011, + +// cl_d3d10_device_set_nv + CL_PREFERRED_DEVICES_FOR_D3D10_KHR = 0x4012, + CL_ALL_DEVICES_FOR_D3D10_KHR = 0x4013, + +// cl_context_info + CL_CONTEXT_D3D10_DEVICE_KHR = 0x4014, + CL_CONTEXT_D3D10_PREFER_SHARED_RESOURCES_KHR = 0x402C, + +// cl_mem_info + CL_MEM_D3D10_RESOURCE_KHR = 0x4015, + +// cl_image_info + CL_IMAGE_D3D10_SUBRESOURCE_KHR = 0x4016, + +// cl_command_type + CL_COMMAND_ACQUIRE_D3D10_OBJECTS_KHR = 0x4017, + CL_COMMAND_RELEASE_D3D10_OBJECTS_KHR = 0x4018, +} + +/******************************************************************************/ + +typedef cl_int (*clGetDeviceIDsFromD3D10KHR_fn)( + cl_platform_id platform, + cl_d3d10_device_source_khr d3d_device_source, + void* d3d_object, + cl_d3d10_device_set_khr d3d_device_set, + cl_uint num_entries, + cl_device_id* devices, + cl_uint* num_devices +); + +typedef cl_mem (*clCreateFromD3D10BufferKHR_fn)( + cl_context context, + cl_mem_flags flags, + void* resource, // ID3D10Buffer* + cl_int* errcode_ret +); + +typedef cl_mem (*clCreateFromD3D10Texture2DKHR_fn)( + cl_context context, + cl_mem_flags flags, + void* resource, // ID3D10Texture2D* + UINT subresource, + cl_int* errcode_ret +); + +typedef cl_mem (*clCreateFromD3D10Texture3DKHR_fn)( + cl_context context, + cl_mem_flags flags, + void* resource, // ID3D10Texture3D* + UINT subresource, + cl_int* errcode_ret +); + +typedef cl_int (*clEnqueueAcquireD3D10ObjectsKHR_fn)( + cl_command_queue command_queue, + cl_uint num_objects, + const(cl_mem)* mem_objects, + cl_uint num_events_in_wait_list, + const(cl_event)* event_wait_list, + cl_event* event +); + +typedef cl_int (*clEnqueueReleaseD3D10ObjectsKHR_fn)( + cl_command_queue command_queue, + cl_uint num_objects, + cl_mem* mem_objects, + cl_uint num_events_in_wait_list, + const(cl_event)* event_wait_list, + cl_event* event +); \ No newline at end of file
--- a/opencl/c/opencl.d Wed Dec 02 17:40:59 2009 +0100 +++ /dev/null Thu Jan 01 00:00:00 1970 +0000 @@ -1,937 +0,0 @@ -/******************************************************************************* - * Copyright (c) 2008-2009 The Khronos Group Inc. - * - * Permission is hereby granted, free of charge, to any person obtaining a - * copy of this software and/or associated documentation files (the - * "Materials"), to deal in the Materials without restriction, including - * without limitation the rights to use, copy, modify, merge, publish, - * distribute, sublicense, and/or sell copies of the Materials, and to - * permit persons to whom the Materials are furnished to do so, subject to - * the following conditions: - * - * The above copyright notice and this permission notice shall be included - * in all copies or substantial portions of the Materials. - * - * THE MATERIALS ARE PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND, - * EXPRESS OR IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF - * MERCHANTABILITY, FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT. - * IN NO EVENT SHALL THE AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY - * CLAIM, DAMAGES OR OTHER LIABILITY, WHETHER IN AN ACTION OF CONTRACT, - * TORT OR OTHERWISE, ARISING FROM, OUT OF OR IN CONNECTION WITH THE - * MATERIALS OR THE USE OR OTHER DEALINGS IN THE MATERIALS. - ******************************************************************************/ - -// $Revision: 9283 $ on $Date: 2009-10-14 10:18:57 -0700 (Wed, 14 Oct 2009) $ - -module opencl.c.opencl; - -public import opencl.c.platform; - -extern(C): - -alias const(void)* - cl_platform_id, - cl_device_id, - cl_context, - cl_command_queue, - cl_mem, - cl_program, - cl_kernel, - cl_event, - cl_sampler; - -alias 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. -alias cl_ulong cl_bitfield; -alias cl_bitfield cl_device_type; -alias cl_uint cl_platform_info; -alias cl_uint cl_device_info; -alias cl_bitfield cl_device_address_info; -alias cl_bitfield cl_device_fp_config; -alias cl_uint cl_device_mem_cache_type; -alias cl_uint cl_device_local_mem_type; -alias cl_bitfield cl_device_exec_capabilities; -alias cl_bitfield cl_command_queue_properties; - -alias cl_bitfield cl_context_properties; -alias cl_uint cl_context_info; -alias cl_uint cl_command_queue_info; -alias cl_uint cl_channel_order; -alias cl_uint cl_channel_type; -alias cl_bitfield cl_mem_flags; -alias cl_uint cl_mem_object_type; -alias cl_uint cl_mem_info; -alias cl_uint cl_image_info; -alias cl_uint cl_addressing_mode; -alias cl_uint cl_filter_mode; -alias cl_uint cl_sampler_info; -alias cl_bitfield cl_map_flags; -alias cl_uint cl_program_info; -alias cl_uint cl_program_build_info; -alias cl_uint cl_build_status; -alias cl_uint cl_kernel_info; -alias cl_uint cl_kernel_work_group_info; -alias cl_uint cl_event_info; -alias cl_uint cl_command_type; -alias cl_uint cl_profiling_info; - -struct cl_image_format -{ - cl_channel_order image_channel_order; - cl_channel_type image_channel_data_type; -} - -/******************************************************************************/ - -enum -{ - // Error Codes - CL_SUCCESS = 0, - CL_DEVICE_NOT_FOUND = -1, - CL_DEVICE_NOT_AVAILABLE = -2, - CL_COMPILER_NOT_AVAILABLE = -3, - CL_MEM_OBJECT_ALLOCATION_FAILURE = -4, - CL_OUT_OF_RESOURCES = -5, - CL_OUT_OF_HOST_MEMORY = -6, - CL_PROFILING_INFO_NOT_AVAILABLE = -7, - CL_MEM_COPY_OVERLAP = -8, - CL_IMAGE_FORMAT_MISMATCH = -9, - CL_IMAGE_FORMAT_NOT_SUPPORTED = -10, - CL_BUILD_PROGRAM_FAILURE = -11, - CL_MAP_FAILURE = -12, - - CL_INVALID_VALUE = -30, - CL_INVALID_DEVICE_TYPE = -31, - CL_INVALID_PLATFORM = -32, - CL_INVALID_DEVICE = -33, - CL_INVALID_CONTEXT = -34, - CL_INVALID_QUEUE_PROPERTIES = -35, - CL_INVALID_COMMAND_QUEUE = -36, - CL_INVALID_HOST_PTR = -37, - CL_INVALID_MEM_OBJECT = -38, - CL_INVALID_IMAGE_FORMAT_DESCRIPTOR = -39, - CL_INVALID_IMAGE_SIZE = -40, - CL_INVALID_SAMPLER = -41, - CL_INVALID_BINARY = -42, - CL_INVALID_BUILD_OPTIONS = -43, - CL_INVALID_PROGRAM = -44, - CL_INVALID_PROGRAM_EXECUTABLE = -45, - CL_INVALID_KERNEL_NAME = -46, - CL_INVALID_KERNEL_DEFINITION = -47, - CL_INVALID_KERNEL = -48, - CL_INVALID_ARG_INDEX = -49, - CL_INVALID_ARG_VALUE = -50, - CL_INVALID_ARG_SIZE = -51, - CL_INVALID_KERNEL_ARGS = -52, - CL_INVALID_WORK_DIMENSION = -53, - CL_INVALID_WORK_GROUP_SIZE = -54, - CL_INVALID_WORK_ITEM_SIZE = -55, - CL_INVALID_GLOBAL_OFFSET = -56, - CL_INVALID_EVENT_WAIT_LIST = -57, - CL_INVALID_EVENT = -58, - CL_INVALID_OPERATION = -59, - CL_INVALID_GL_OBJECT = -60, - CL_INVALID_BUFFER_SIZE = -61, - CL_INVALID_MIP_LEVEL = -62, - CL_INVALID_GLOBAL_WORK_SIZE = -63, - - // OpenCL Version - CL_VERSION_1_0 = 1, - - // cl_bool - CL_FALSE = 0, - CL_TRUE = 1, - - // cl_platform_info - CL_PLATFORM_PROFILE = 0x0900, - CL_PLATFORM_VERSION = 0x0901, - CL_PLATFORM_NAME = 0x0902, - CL_PLATFORM_VENDOR = 0x0903, - CL_PLATFORM_EXTENSIONS = 0x0904, - - // cl_device_type - bitfield - CL_DEVICE_TYPE_DEFAULT = (1 << 0), - CL_DEVICE_TYPE_CPU = (1 << 1), - CL_DEVICE_TYPE_GPU = (1 << 2), - CL_DEVICE_TYPE_ACCELERATOR = (1 << 3), - CL_DEVICE_TYPE_ALL = 0xFFFFFFFF, - - // cl_device_info - CL_DEVICE_TYPE = 0x1000, - CL_DEVICE_VENDOR_ID = 0x1001, - CL_DEVICE_MAX_COMPUTE_UNITS = 0x1002, - CL_DEVICE_MAX_WORK_ITEM_DIMENSIONS = 0x1003, - CL_DEVICE_MAX_WORK_GROUP_SIZE = 0x1004, - CL_DEVICE_MAX_WORK_ITEM_SIZES = 0x1005, - CL_DEVICE_PREFERRED_VECTOR_WIDTH_CHAR = 0x1006, - CL_DEVICE_PREFERRED_VECTOR_WIDTH_SHORT = 0x1007, - CL_DEVICE_PREFERRED_VECTOR_WIDTH_INT = 0x1008, - CL_DEVICE_PREFERRED_VECTOR_WIDTH_LONG = 0x1009, - CL_DEVICE_PREFERRED_VECTOR_WIDTH_FLOAT = 0x100A, - CL_DEVICE_PREFERRED_VECTOR_WIDTH_DOUBLE = 0x100B, - CL_DEVICE_MAX_CLOCK_FREQUENCY = 0x100C, - CL_DEVICE_ADDRESS_BITS = 0x100D, - CL_DEVICE_MAX_READ_IMAGE_ARGS = 0x100E, - CL_DEVICE_MAX_WRITE_IMAGE_ARGS = 0x100F, - CL_DEVICE_MAX_MEM_ALLOC_SIZE = 0x1010, - CL_DEVICE_IMAGE2D_MAX_WIDTH = 0x1011, - CL_DEVICE_IMAGE2D_MAX_HEIGHT = 0x1012, - CL_DEVICE_IMAGE3D_MAX_WIDTH = 0x1013, - CL_DEVICE_IMAGE3D_MAX_HEIGHT = 0x1014, - CL_DEVICE_IMAGE3D_MAX_DEPTH = 0x1015, - CL_DEVICE_IMAGE_SUPPORT = 0x1016, - CL_DEVICE_MAX_PARAMETER_SIZE = 0x1017, - CL_DEVICE_MAX_SAMPLERS = 0x1018, - CL_DEVICE_MEM_BASE_ADDR_ALIGN = 0x1019, - CL_DEVICE_MIN_DATA_TYPE_ALIGN_SIZE = 0x101A, - CL_DEVICE_SINGLE_FP_CONFIG = 0x101B, - CL_DEVICE_GLOBAL_MEM_CACHE_TYPE = 0x101C, - CL_DEVICE_GLOBAL_MEM_CACHELINE_SIZE = 0x101D, - CL_DEVICE_GLOBAL_MEM_CACHE_SIZE = 0x101E, - CL_DEVICE_GLOBAL_MEM_SIZE = 0x101F, - CL_DEVICE_MAX_CONSTANT_BUFFER_SIZE = 0x1020, - CL_DEVICE_MAX_CONSTANT_ARGS = 0x1021, - CL_DEVICE_LOCAL_MEM_TYPE = 0x1022, - CL_DEVICE_LOCAL_MEM_SIZE = 0x1023, - CL_DEVICE_ERROR_CORRECTION_SUPPORT = 0x1024, - CL_DEVICE_PROFILING_TIMER_RESOLUTION = 0x1025, - CL_DEVICE_ENDIAN_LITTLE = 0x1026, - CL_DEVICE_AVAILABLE = 0x1027, - CL_DEVICE_COMPILER_AVAILABLE = 0x1028, - CL_DEVICE_EXECUTION_CAPABILITIES = 0x1029, - CL_DEVICE_QUEUE_PROPERTIES = 0x102A, - CL_DEVICE_NAME = 0x102B, - CL_DEVICE_VENDOR = 0x102C, - CL_DRIVER_VERSION = 0x102D, - CL_DEVICE_PROFILE = 0x102E, - CL_DEVICE_VERSION = 0x102F, - CL_DEVICE_EXTENSIONS = 0x1030, - CL_DEVICE_PLATFORM = 0x1031, - - // cl_device_fp_config - bitfield - CL_FP_DENORM = (1 << 0), - CL_FP_INF_NAN = (1 << 1), - CL_FP_ROUND_TO_NEAREST = (1 << 2), - CL_FP_ROUND_TO_ZERO = (1 << 3), - CL_FP_ROUND_TO_INF = (1 << 4), - CL_FP_FMA = (1 << 5), - - // cl_device_mem_cache_type - CL_NONE = 0x0, - CL_READ_ONLY_CACHE = 0x1, - CL_READ_WRITE_CACHE = 0x2, - - // cl_device_local_mem_type - CL_LOCAL = 0x1, - CL_GLOBAL = 0x2, - - // cl_device_exec_capabilities - bitfield - CL_EXEC_KERNEL = (1 << 0), - CL_EXEC_NATIVE_KERNEL = (1 << 1), - - // cl_command_queue_properties - bitfield - CL_QUEUE_OUT_OF_ORDER_EXEC_MODE_ENABLE = (1 << 0), - CL_QUEUE_PROFILING_ENABLE = (1 << 1), - - // cl_context_info - CL_CONTEXT_REFERENCE_COUNT = 0x1080, - CL_CONTEXT_DEVICES = 0x1081, - CL_CONTEXT_PROPERTIES = 0x1082, - - // cl_context_properties - CL_CONTEXT_PLATFORM = 0x1084, - - // cl_command_queue_info - CL_QUEUE_CONTEXT = 0x1090, - CL_QUEUE_DEVICE = 0x1091, - CL_QUEUE_REFERENCE_COUNT = 0x1092, - CL_QUEUE_PROPERTIES = 0x1093, - - // cl_mem_flags - bitfield - CL_MEM_READ_WRITE = (1 << 0), - CL_MEM_WRITE_ONLY = (1 << 1), - CL_MEM_READ_ONLY = (1 << 2), - CL_MEM_USE_HOST_PTR = (1 << 3), - CL_MEM_ALLOC_HOST_PTR = (1 << 4), - CL_MEM_COPY_HOST_PTR = (1 << 5), - - // cl_channel_order - CL_R = 0x10B0, - CL_A = 0x10B1, - CL_RG = 0x10B2, - CL_RA = 0x10B3, - CL_RGB = 0x10B4, - CL_RGBA = 0x10B5, - CL_BGRA = 0x10B6, - CL_ARGB = 0x10B7, - CL_INTENSITY = 0x10B8, - CL_LUMINANCE = 0x10B9, - - // cl_channel_type - CL_SNORM_INT8 = 0x10D0, - CL_SNORM_INT16 = 0x10D1, - CL_UNORM_INT8 = 0x10D2, - CL_UNORM_INT16 = 0x10D3, - CL_UNORM_SHORT_565 = 0x10D4, - CL_UNORM_SHORT_555 = 0x10D5, - CL_UNORM_INT_101010 = 0x10D6, - CL_SIGNED_INT8 = 0x10D7, - CL_SIGNED_INT16 = 0x10D8, - CL_SIGNED_INT32 = 0x10D9, - CL_UNSIGNED_INT8 = 0x10DA, - CL_UNSIGNED_INT16 = 0x10DB, - CL_UNSIGNED_INT32 = 0x10DC, - CL_HALF_FLOAT = 0x10DD, - CL_FLOAT = 0x10DE, - - // cl_mem_object_type - CL_MEM_OBJECT_BUFFER = 0x10F0, - CL_MEM_OBJECT_IMAGE2D = 0x10F1, - CL_MEM_OBJECT_IMAGE3D = 0x10F2, - - // cl_mem_info - CL_MEM_TYPE = 0x1100, - CL_MEM_FLAGS = 0x1101, - CL_MEM_SIZE = 0x1102, - CL_MEM_HOST_PTR = 0x1103, - CL_MEM_MAP_COUNT = 0x1104, - CL_MEM_REFERENCE_COUNT = 0x1105, - CL_MEM_CONTEXT = 0x1106, - - // cl_image_info - CL_IMAGE_FORMAT = 0x1110, - CL_IMAGE_ELEMENT_SIZE = 0x1111, - CL_IMAGE_ROW_PITCH = 0x1112, - CL_IMAGE_SLICE_PITCH = 0x1113, - CL_IMAGE_WIDTH = 0x1114, - CL_IMAGE_HEIGHT = 0x1115, - CL_IMAGE_DEPTH = 0x1116, - - // cl_addressing_mode - CL_ADDRESS_NONE = 0x1130, - CL_ADDRESS_CLAMP_TO_EDGE = 0x1131, - CL_ADDRESS_CLAMP = 0x1132, - CL_ADDRESS_REPEAT = 0x1133, - - // cl_filter_mode - CL_FILTER_NEAREST = 0x1140, - CL_FILTER_LINEAR = 0x1141, - - // cl_sampler_info - CL_SAMPLER_REFERENCE_COUNT = 0x1150, - CL_SAMPLER_CONTEXT = 0x1151, - CL_SAMPLER_NORMALIZED_COORDS = 0x1152, - CL_SAMPLER_ADDRESSING_MODE = 0x1153, - CL_SAMPLER_FILTER_MODE = 0x1154, - - // cl_map_flags - bitfield - CL_MAP_READ = (1 << 0), - CL_MAP_WRITE = (1 << 1), - - // cl_program_info - CL_PROGRAM_REFERENCE_COUNT = 0x1160, - CL_PROGRAM_CONTEXT = 0x1161, - CL_PROGRAM_NUM_DEVICES = 0x1162, - CL_PROGRAM_DEVICES = 0x1163, - CL_PROGRAM_SOURCE = 0x1164, - CL_PROGRAM_BINARY_SIZES = 0x1165, - CL_PROGRAM_BINARIES = 0x1166, - - // cl_program_build_info - CL_PROGRAM_BUILD_STATUS = 0x1181, - CL_PROGRAM_BUILD_OPTIONS = 0x1182, - CL_PROGRAM_BUILD_LOG = 0x1183, - - // cl_build_status - CL_BUILD_SUCCESS = 0, - CL_BUILD_NONE = -1, - CL_BUILD_ERROR = -2, - CL_BUILD_IN_PROGRESS = -3, - - // cl_kernel_info - CL_KERNEL_FUNCTION_NAME = 0x1190, - CL_KERNEL_NUM_ARGS = 0x1191, - CL_KERNEL_REFERENCE_COUNT = 0x1192, - CL_KERNEL_CONTEXT = 0x1193, - CL_KERNEL_PROGRAM = 0x1194, - - // cl_kernel_work_group_info - CL_KERNEL_WORK_GROUP_SIZE = 0x11B0, - CL_KERNEL_COMPILE_WORK_GROUP_SIZE = 0x11B1, - CL_KERNEL_LOCAL_MEM_SIZE = 0x11B2, - - // cl_event_info - CL_EVENT_COMMAND_QUEUE = 0x11D0, - CL_EVENT_COMMAND_TYPE = 0x11D1, - CL_EVENT_REFERENCE_COUNT = 0x11D2, - CL_EVENT_COMMAND_EXECUTION_STATUS = 0x11D3, - - // cl_command_type - CL_COMMAND_NDRANGE_KERNEL = 0x11F0, - CL_COMMAND_TASK = 0x11F1, - CL_COMMAND_NATIVE_KERNEL = 0x11F2, - CL_COMMAND_READ_BUFFER = 0x11F3, - CL_COMMAND_WRITE_BUFFER = 0x11F4, - CL_COMMAND_COPY_BUFFER = 0x11F5, - CL_COMMAND_READ_IMAGE = 0x11F6, - CL_COMMAND_WRITE_IMAGE = 0x11F7, - CL_COMMAND_COPY_IMAGE = 0x11F8, - CL_COMMAND_COPY_IMAGE_TO_BUFFER = 0x11F9, - CL_COMMAND_COPY_BUFFER_TO_IMAGE = 0x11FA, - CL_COMMAND_MAP_BUFFER = 0x11FB, - CL_COMMAND_MAP_IMAGE = 0x11FC, - CL_COMMAND_UNMAP_MEM_OBJECT = 0x11FD, - CL_COMMAND_MARKER = 0x11FE, - CL_COMMAND_ACQUIRE_GL_OBJECTS = 0x11FF, - CL_COMMAND_RELEASE_GL_OBJECTS = 0x1200, - - // command execution status - CL_COMPLETE = 0x0, - CL_RUNNING = 0x1, - CL_SUBMITTED = 0x2, - CL_QUEUED = 0x3, - - // cl_profiling_info - CL_PROFILING_COMMAND_QUEUED = 0x1280, - CL_PROFILING_COMMAND_SUBMIT = 0x1281, - CL_PROFILING_COMMAND_START = 0x1282, - CL_PROFILING_COMMAND_END = 0x1283 -} - -/********************************************************************************************************/ - -// Platform API -cl_int clGetPlatformIDs( - cl_uint num_entries, - cl_platform_id* platforms, - cl_uint* num_platforms -); - -cl_int clGetPlatformInfo( - cl_platform_id platform, - cl_platform_info param_name, - size_t param_value_size, - void* param_value, - size_t* param_value_size_ret -); - -// Device APIs -cl_int clGetDeviceIDs( - cl_platform_id platform, - cl_device_type device_type, - cl_uint num_entries, - cl_device_id* devices, - cl_uint* num_devices -); - -cl_int clGetDeviceInfo( - cl_device_id device, - cl_device_info param_name, - size_t param_value_size, - void* param_value, - size_t* param_value_size_ret -); - -// Context APIs - -typedef void function( - const(char)*, - const(void)*, - size_t, - const(void)* -) cl_logging_fn; - -cl_context clCreateContext( - const(cl_context_properties)* properties, - cl_uint num_devices, - const(cl_device_id)* devices, - cl_logging_fn pfn_notify, - void* user_data, - cl_int* errcode_ret -); - -cl_context clCreateContextFromType( - const(cl_context_properties)* properties, - cl_device_type device_type, - cl_logging_fn pfn_notify, - void* user_data, - cl_int* errcode_ret -); - -cl_int clRetainContext( - cl_context context -); - -cl_int clReleaseContext( - cl_context context -); - -cl_int clGetContextInfo( - cl_context context, - cl_context_info param_name, - size_t param_value_size, - void* param_value, - size_t* param_value_size_ret -); - -// Command Queue APIs -cl_command_queue clCreateCommandQueue( - cl_context context, - cl_device_id device, - cl_command_queue_properties properties, - cl_int* errcode_ret -); - -cl_int clRetainCommandQueue( - cl_command_queue command_queue -); - -cl_int clReleaseCommandQueue( - cl_command_queue command_queue -); - -cl_int clGetCommandQueueInfo( - cl_command_queue command_queue, - cl_command_queue_info param_name, - size_t param_value_size, - void * param_value, - size_t * param_value_size_ret -); - -cl_int clSetCommandQueueProperty( - cl_command_queue command_queue, - cl_command_queue_properties properties, - cl_bool enable, - cl_command_queue_properties* old_properties -); - -// Memory Object APIs -cl_mem clCreateBuffer( - cl_context context, - cl_mem_flags flags, - size_t size, - void * host_ptr, - cl_int * errcode_ret -); - -cl_mem clCreateImage2D( - cl_context context, - cl_mem_flags flags, - const(cl_image_format)* image_format, - size_t image_width, - size_t image_height, - size_t image_row_pitch, - void* host_ptr, - cl_int* errcode_ret -); - -cl_mem clCreateImage3D( - cl_context context, - cl_mem_flags flags, - const(cl_image_format)* image_format, - size_t image_width, - size_t image_height, - size_t image_depth, - size_t image_row_pitch, - size_t image_slice_pitch, - void* host_ptr, - cl_int* errcode_ret -); - -cl_int clRetainMemObject( - cl_mem memobj -); - -cl_int clReleaseMemObject( - cl_mem memobj -); - -cl_int clGetSupportedImageFormats( - cl_context context, - cl_mem_flags flags, - cl_mem_object_type image_type, - cl_uint num_entries, - cl_image_format* image_formats, - cl_uint* num_image_formats -); - -cl_int clGetMemObjectInfo( - cl_mem memobj, - cl_mem_info param_name, - size_t param_value_size, - void* param_value, - size_t* param_value_size_ret -); - -cl_int clGetImageInfo( - cl_mem image, - cl_image_info param_name, - size_t param_value_size, - void * param_value, - size_t * param_value_size_ret -); - -// Sampler APIs -cl_sampler clCreateSampler( - cl_context context, - cl_bool normalized_coords, - cl_addressing_mode addressing_mode, - cl_filter_mode filter_mode, - cl_int* errcode_ret -); - -cl_int clRetainSampler( - cl_sampler sampler -); - -cl_int clReleaseSampler( - cl_sampler sampler -); - -cl_int clGetSamplerInfo( - cl_sampler sampler, - cl_sampler_info param_name, - size_t param_value_size, - void* param_value, - size_t* param_value_size_ret -); - -// Program Object APIs -cl_program clCreateProgramWithSource( - cl_context context, - cl_uint count, - const(char*)* strings, - const(size_t)* lengths, - cl_int* errcode_ret -); - -cl_program clCreateProgramWithBinary( - cl_context context, - cl_uint num_devices, - const(cl_device_id)* device_list, - const(size_t)* lengths, - const(ubyte*)* binaries, - cl_int* binary_status, - cl_int* errcode_ret -); - -cl_int clRetainProgram( - cl_program program -); - -cl_int clReleaseProgram( - cl_program program -); - -cl_int clBuildProgram( - cl_program program, - cl_uint num_devices, - const(cl_device_id)* device_list, - const(char)* options, - void function( - cl_program program, - void* user_data - ) pfn_notify, - void* user_data -); - -cl_int clUnloadCompiler(); - -cl_int clGetProgramInfo( - cl_program program, - cl_program_info param_name, - size_t param_value_size, - void* param_value, - size_t* param_value_size_ret -); - -cl_int clGetProgramBuildInfo( - cl_program program, - cl_device_id device, - cl_program_build_info param_name, - size_t param_value_size, - void* param_value, - size_t* param_value_size_ret -); - -// Kernel Object APIs -cl_kernel clCreateKernel( - cl_program program, - const(char)* kernel_name, - cl_int* errcode_ret -); - -cl_int clCreateKernelsInProgram( - cl_program program, - cl_uint num_kernels, - cl_kernel* kernels, - cl_uint* num_kernels_ret -); - -cl_int clRetainKernel( - cl_kernel kernel -); - -cl_int clReleaseKernel( - cl_kernel kernel -); - -cl_int clSetKernelArg( - cl_kernel kernel, - cl_uint arg_indx, - size_t arg_size, - const(void)* arg_value -); - -cl_int clGetKernelInfo( - cl_kernel kernel, - cl_kernel_info param_name, - size_t param_value_size, - void* param_value, - size_t* param_value_size_ret -); - -cl_int clGetKernelWorkGroupInfo( - cl_kernel kernel, - cl_device_id device, - cl_kernel_work_group_info param_name, - size_t param_value_size, - void* param_value, - size_t* param_value_size_ret -); - -// Event Object APIs -cl_int clWaitForEvents( - cl_uint num_events, - const(cl_event)* event_list -); - -cl_int clGetEventInfo( - cl_event event, - cl_event_info param_name, - size_t param_value_size, - void* param_value, - size_t* param_value_size_ret -); - -cl_int clRetainEvent( - cl_event event -); - -cl_int clReleaseEvent( - cl_event event -); - -// Profiling APIs -cl_int clGetEventProfilingInfo( - cl_event event, - cl_profiling_info param_name, - size_t param_value_size, - void* param_value, - size_t* param_value_size_ret -); - -// Flush and Finish APIs -cl_int clFlush( - cl_command_queue command_queue -); - -cl_int clFinish( - cl_command_queue command_queue -); - -// Enqueued Commands APIs -cl_int clEnqueueReadBuffer( - cl_command_queue command_queue, - cl_mem buffer, - cl_bool blocking_read, - size_t offset, - size_t cb, - void * ptr, - cl_uint num_events_in_wait_list, - const(cl_event)* event_wait_list, - cl_event* event -); - -cl_int clEnqueueWriteBuffer( - cl_command_queue command_queue, - cl_mem buffer, - cl_bool blocking_write, - size_t offset, - size_t cb, - const(void)* ptr, - cl_uint num_events_in_wait_list, - const(cl_event)* event_wait_list, - cl_event* event -); - -cl_int clEnqueueCopyBuffer( - cl_command_queue command_queue, - cl_mem src_buffer, - cl_mem dst_buffer, - size_t src_offset, - size_t dst_offset, - size_t cb, - cl_uint num_events_in_wait_list, - const(cl_event)* event_wait_list, - cl_event* event -); - -cl_int clEnqueueReadImage( - cl_command_queue command_queue, - cl_mem image, - cl_bool blocking_read, - const(size_t)* origin[3], - const(size_t)* region[3], - size_t row_pitch, - size_t slice_pitch, - void* ptr, - cl_uint num_events_in_wait_list, - const(cl_event)* event_wait_list, - cl_event* event -); - -cl_int clEnqueueWriteImage( - cl_command_queue command_queue, - cl_mem image, - cl_bool blocking_write, - const(size_t)* origin[3], - const(size_t)* region[3], - size_t input_row_pitch, - size_t input_slice_pitch, - const(void)* ptr, - cl_uint num_events_in_wait_list, - const(cl_event)* event_wait_list, - cl_event* event -); - -cl_int clEnqueueCopyImage( - cl_command_queue command_queue, - cl_mem src_image, - cl_mem dst_image, - const(size_t)* src_origin[3], - const(size_t)* dst_origin[3], - const(size_t)* region[3], - cl_uint num_events_in_wait_list, - const(cl_event)* event_wait_list, - cl_event* event -); - -cl_int clEnqueueCopyImageToBuffer( - cl_command_queue command_queue, - cl_mem src_image, - cl_mem dst_buffer, - const(size_t)* src_origin[3], - const(size_t)* region[3], - size_t dst_offset, - cl_uint num_events_in_wait_list, - const(cl_event)* event_wait_list, - cl_event* event -); - -cl_int clEnqueueCopyBufferToImage( - cl_command_queue command_queue, - cl_mem src_buffer, - cl_mem dst_image, - size_t src_offset, - const(size_t)* dst_origin[3], - const(size_t)* region[3], - cl_uint num_events_in_wait_list, - const(cl_event)* event_wait_list, - cl_event* event -); - -void* clEnqueueMapBuffer( - cl_command_queue command_queue, - cl_mem buffer, - cl_bool blocking_map, - cl_map_flags map_flags, - size_t offset, - size_t cb, - cl_uint num_events_in_wait_list, - const(cl_event)* event_wait_list, - cl_event* event, - cl_int* errcode_ret -); - -void* clEnqueueMapImage( - cl_command_queue command_queue, - cl_mem image, - cl_bool blocking_map, - cl_map_flags map_flags, - const(size_t)* origin[3], - const(size_t)* region[3], - size_t* image_row_pitch, - size_t* image_slice_pitch, - cl_uint num_events_in_wait_list, - const(cl_event)* event_wait_list, - cl_event* event, - cl_int* errcode_ret -); - -cl_int clEnqueueUnmapMemObject( - cl_command_queue command_queue, - cl_mem memobj, - void* mapped_ptr, - cl_uint num_events_in_wait_list, - const(cl_event)* event_wait_list, - cl_event* event -); - -cl_int clEnqueueNDRangeKernel( - cl_command_queue command_queue, - cl_kernel kernel, - cl_uint work_dim, - const(size_t)* global_work_offset, - const(size_t)* global_work_size, - const(size_t)* local_work_size, - cl_uint num_events_in_wait_list, - const(cl_event)* event_wait_list, - cl_event* event -); - -cl_int clEnqueueTask( - cl_command_queue command_queue, - cl_kernel kernel, - cl_uint num_events_in_wait_list, - const(cl_event)* event_wait_list, - cl_event* event -); - -cl_int clEnqueueNativeKernel( - cl_command_queue command_queue, - void function( - void* - ) user_func, - void* args, - size_t cb_args, - cl_uint num_mem_objects, - const(cl_mem)* mem_list, - const(void*)* args_mem_loc, - cl_uint num_events_in_wait_list, - const(cl_event)* event_wait_list, - cl_event* event -); - -cl_int clEnqueueMarker( - cl_command_queue command_queue, - cl_event* event -); - -cl_int clEnqueueWaitForEvents( - cl_command_queue command_queue, - cl_uint num_events, - const(cl_event)* event_list -); - -cl_int clEnqueueBarrier( - cl_command_queue command_queue -); - -//Extension function access -// -// Returns the extension function address for the given function name, -// or NULL if a valid function can not be found. The client must -// check to make sure the address is not NULL, before using or -// calling the returned function address. -// -void* clGetExtensionFunctionAddress(const(char)* func_name); \ No newline at end of file