| /******************************************************************************* |
| * Copyright (c) 2008-2010 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. |
| ******************************************************************************/ |
| |
| #ifndef __OPENCL_CL_ICD_H |
| #define __OPENCL_CL_ICD_H |
| |
| #include <CL/cl.h> |
| #include <CL/cl_gl.h> |
| |
| #define cl_khr_icd 1 |
| |
| #ifdef __cplusplus |
| extern "C" { |
| #endif /* __cplusplus */ |
| |
| typedef cl_int(CL_API_CALL* clGetPlatformIDs_fn)( |
| cl_uint /* num_entries */, cl_platform_id* /* platforms */, |
| cl_uint* /* num_platforms */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clGetPlatformInfo_fn)( |
| cl_platform_id /* platform */, cl_platform_info /* param_name */, size_t /* param_value_size */, |
| void* /* param_value */, size_t* /* param_value_size_ret */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clGetDeviceIDs_fn)( |
| cl_platform_id /* platform */, cl_device_type /* device_type */, cl_uint /* num_entries */, |
| cl_device_id* /* devices */, cl_uint* /* num_devices */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clGetDeviceInfo_fn)( |
| cl_device_id /* device */, cl_device_info /* param_name */, size_t /* param_value_size */, |
| void* /* param_value */, size_t* /* param_value_size_ret */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_context(CL_API_CALL* clCreateContext_fn)( |
| const cl_context_properties* /* properties */, cl_uint /* num_devices */, |
| const cl_device_id* /* devices */, |
| void(CL_CALLBACK* /* pfn_notify */)(const char*, const void*, size_t, void*), |
| void* /* user_data */, cl_int* /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_context(CL_API_CALL* clCreateContextFromType_fn)( |
| const cl_context_properties* /* properties */, cl_device_type /* device_type */, |
| void(CL_CALLBACK* /* pfn_notify*/)(const char*, const void*, size_t, void*), |
| void* /* user_data */, cl_int* /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clRetainContext_fn)(cl_context /* context */) |
| CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clReleaseContext_fn)(cl_context /* context */) |
| CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clGetContextInfo_fn)( |
| cl_context /* context */, cl_context_info /* param_name */, size_t /* param_value_size */, |
| void* /* param_value */, size_t* /* param_value_size_ret */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_command_queue(CL_API_CALL* clCreateCommandQueue_fn)( |
| cl_context /* context */, cl_device_id /* device */, |
| cl_command_queue_properties /* properties */, |
| cl_int* /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clRetainCommandQueue_fn)(cl_command_queue /* command_queue */) |
| CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clReleaseCommandQueue_fn)(cl_command_queue /* command_queue */) |
| CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clGetCommandQueueInfo_fn)( |
| 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_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clSetCommandQueueProperty_fn)( |
| cl_command_queue /* command_queue */, cl_command_queue_properties /* properties */, |
| cl_bool /* enable */, |
| cl_command_queue_properties* /* old_properties */) /*CL_EXT_SUFFIX__VERSION_1_0_DEPRECATED*/; |
| |
| typedef cl_mem(CL_API_CALL* clCreateBuffer_fn)( |
| cl_context /* context */, cl_mem_flags /* flags */, size_t /* size */, void* /* host_ptr */, |
| cl_int* /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_mem(CL_API_CALL* clCreateSubBuffer_fn)( |
| cl_mem /* buffer */, cl_mem_flags /* flags */, cl_buffer_create_type /* buffer_create_type */, |
| const void* /* buffer_create_info */, cl_int* /* errcode_ret */) CL_API_SUFFIX__VERSION_1_1; |
| |
| typedef cl_mem(CL_API_CALL* clCreateImage2D_fn)( |
| 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_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_mem(CL_API_CALL* clCreateImage3D_fn)( |
| 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_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clRetainMemObject_fn)(cl_mem /* memobj */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clReleaseMemObject_fn)(cl_mem /* memobj */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clGetSupportedImageFormats_fn)( |
| 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_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clGetMemObjectInfo_fn)( |
| cl_mem /* memobj */, cl_mem_info /* param_name */, size_t /* param_value_size */, |
| void* /* param_value */, size_t* /* param_value_size_ret */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clGetImageInfo_fn)( |
| cl_mem /* image */, cl_image_info /* param_name */, size_t /* param_value_size */, |
| void* /* param_value */, size_t* /* param_value_size_ret */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clSetMemObjectDestructorCallback_fn)( |
| cl_mem /* memobj */, |
| void(CL_CALLBACK* /*pfn_notify*/)(cl_mem /* memobj */, void* /*user_data*/), |
| void* /*user_data */) CL_API_SUFFIX__VERSION_1_1; |
| |
| /* Sampler APIs */ |
| typedef cl_sampler(CL_API_CALL* clCreateSampler_fn)( |
| cl_context /* context */, cl_bool /* normalized_coords */, |
| cl_addressing_mode /* addressing_mode */, cl_filter_mode /* filter_mode */, |
| cl_int* /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clRetainSampler_fn)(cl_sampler /* sampler */) |
| CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clReleaseSampler_fn)(cl_sampler /* sampler */) |
| CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clGetSamplerInfo_fn)( |
| cl_sampler /* sampler */, cl_sampler_info /* param_name */, size_t /* param_value_size */, |
| void* /* param_value */, size_t* /* param_value_size_ret */) CL_API_SUFFIX__VERSION_1_0; |
| |
| /* Program Object APIs */ |
| typedef cl_program(CL_API_CALL* clCreateProgramWithSource_fn)( |
| cl_context /* context */, cl_uint /* count */, const char** /* strings */, |
| const size_t* /* lengths */, cl_int* /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0; |
| |
| extern CL_API_ENTRY cl_program CL_API_CALL |
| clCreateProgramWithIL(cl_context /* context */, |
| const void * /* strings */, size_t /* lengths */, |
| cl_int * /* errcode_ret */) CL_EXT_SUFFIX__VERSION_2_0; |
| |
| typedef cl_program(CL_API_CALL* clCreateProgramWithILKHR_fn)( |
| cl_context /* context */, const void* /* il */, size_t /* length */, |
| cl_int* /* errcode_ret */) CL_API_SUFFIX__VERSION_1_2; |
| |
| typedef cl_program(CL_API_CALL* clCreateProgramWithBinary_fn)( |
| cl_context /* context */, cl_uint /* num_devices */, const cl_device_id* /* device_list */, |
| const size_t* /* lengths */, const unsigned char** /* binaries */, cl_int* /* binary_status */, |
| cl_int* /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clRetainProgram_fn)(cl_program /* program */) |
| CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clReleaseProgram_fn)(cl_program /* program */) |
| CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clBuildProgram_fn)( |
| cl_program /* program */, cl_uint /* num_devices */, const cl_device_id* /* device_list */, |
| const char* /* options */, |
| void(CL_CALLBACK* /* pfn_notify */)(cl_program /* program */, void* /* user_data */), |
| void* /* user_data */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clUnloadCompiler_fn)(void) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clGetProgramInfo_fn)( |
| cl_program /* program */, cl_program_info /* param_name */, size_t /* param_value_size */, |
| void* /* param_value */, size_t* /* param_value_size_ret */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clGetProgramBuildInfo_fn)( |
| 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 */) CL_API_SUFFIX__VERSION_1_0; |
| |
| /* Kernel Object APIs */ |
| typedef cl_kernel(CL_API_CALL* clCreateKernel_fn)( |
| cl_program /* program */, const char* /* kernel_name */, |
| cl_int* /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clCreateKernelsInProgram_fn)( |
| cl_program /* program */, cl_uint /* num_kernels */, cl_kernel* /* kernels */, |
| cl_uint* /* num_kernels_ret */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clRetainKernel_fn)(cl_kernel /* kernel */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clReleaseKernel_fn)(cl_kernel /* kernel */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clSetKernelArg_fn)(cl_kernel /* kernel */, cl_uint /* arg_index */, |
| size_t /* arg_size */, const void* /* arg_value */) |
| CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clGetKernelInfo_fn)( |
| cl_kernel /* kernel */, cl_kernel_info /* param_name */, size_t /* param_value_size */, |
| void* /* param_value */, size_t* /* param_value_size_ret */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clGetKernelWorkGroupInfo_fn)( |
| 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 */) CL_API_SUFFIX__VERSION_1_0; |
| |
| /* Event Object APIs */ |
| typedef cl_int(CL_API_CALL* clWaitForEvents_fn)( |
| cl_uint /* num_events */, const cl_event* /* event_list */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clGetEventInfo_fn)( |
| cl_event /* event */, cl_event_info /* param_name */, size_t /* param_value_size */, |
| void* /* param_value */, size_t* /* param_value_size_ret */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_event(CL_API_CALL* clCreateUserEvent_fn)( |
| cl_context /* context */, cl_int* /* errcode_ret */) CL_API_SUFFIX__VERSION_1_1; |
| |
| typedef cl_int(CL_API_CALL* clRetainEvent_fn)(cl_event /* event */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clReleaseEvent_fn)(cl_event /* event */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clSetUserEventStatus_fn)( |
| cl_event /* event */, cl_int /* execution_status */) CL_API_SUFFIX__VERSION_1_1; |
| |
| typedef cl_int(CL_API_CALL* clSetEventCallback_fn)( |
| cl_event /* event */, cl_int /* command_exec_callback_type */, |
| void(CL_CALLBACK* /* pfn_notify */)(cl_event, cl_int, void*), |
| void* /* user_data */) CL_API_SUFFIX__VERSION_1_1; |
| |
| /* Profiling APIs */ |
| typedef cl_int(CL_API_CALL* clGetEventProfilingInfo_fn)( |
| cl_event /* event */, cl_profiling_info /* param_name */, size_t /* param_value_size */, |
| void* /* param_value */, size_t* /* param_value_size_ret */) CL_API_SUFFIX__VERSION_1_0; |
| |
| /* Flush and Finish APIs */ |
| typedef cl_int(CL_API_CALL* clFlush_fn)(cl_command_queue /* command_queue */) |
| CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clFinish_fn)(cl_command_queue /* command_queue */) |
| CL_API_SUFFIX__VERSION_1_0; |
| |
| /* Enqueued Commands APIs */ |
| typedef cl_int(CL_API_CALL* clEnqueueReadBuffer_fn)( |
| 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_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clEnqueueReadBufferRect_fn)( |
| cl_command_queue /* command_queue */, cl_mem /* buffer */, cl_bool /* blocking_read */, |
| const size_t* /* buffer_offset */, const size_t* /* host_offset */, const size_t* /* region */, |
| size_t /* buffer_row_pitch */, size_t /* buffer_slice_pitch */, size_t /* host_row_pitch */, |
| size_t /* host_slice_pitch */, void* /* ptr */, cl_uint /* num_events_in_wait_list */, |
| const cl_event* /* event_wait_list */, cl_event* /* event */) CL_API_SUFFIX__VERSION_1_1; |
| |
| typedef cl_int(CL_API_CALL* clEnqueueWriteBuffer_fn)( |
| 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_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clEnqueueWriteBufferRect_fn)( |
| cl_command_queue /* command_queue */, cl_mem /* buffer */, cl_bool /* blocking_read */, |
| const size_t* /* buffer_offset */, const size_t* /* host_offset */, const size_t* /* region */, |
| size_t /* buffer_row_pitch */, size_t /* buffer_slice_pitch */, size_t /* host_row_pitch */, |
| size_t /* host_slice_pitch */, const void* /* ptr */, cl_uint /* num_events_in_wait_list */, |
| const cl_event* /* event_wait_list */, cl_event* /* event */) CL_API_SUFFIX__VERSION_1_1; |
| |
| typedef cl_int(CL_API_CALL* clEnqueueCopyBuffer_fn)( |
| 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_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clEnqueueCopyBufferRect_fn)( |
| cl_command_queue /* command_queue */, cl_mem /* src_buffer */, cl_mem /* dst_buffer */, |
| const size_t* /* src_origin */, const size_t* /* dst_origin */, const size_t* /* region */, |
| size_t /* src_row_pitch */, size_t /* src_slice_pitch */, size_t /* dst_row_pitch */, |
| size_t /* dst_slice_pitch */, cl_uint /* num_events_in_wait_list */, |
| const cl_event* /* event_wait_list */, cl_event* /* event */) CL_API_SUFFIX__VERSION_1_1; |
| |
| typedef cl_int(CL_API_CALL* clEnqueueReadImage_fn)( |
| 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_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clEnqueueWriteImage_fn)( |
| 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_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clEnqueueCopyImage_fn)( |
| 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_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clEnqueueCopyImageToBuffer_fn)( |
| 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_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clEnqueueCopyBufferToImage_fn)( |
| 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 */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef void*(CL_API_CALL* clEnqueueMapBuffer_fn)( |
| 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 */)CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef void*(CL_API_CALL* clEnqueueMapImage_fn)( |
| 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_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clEnqueueUnmapMemObject_fn)( |
| 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_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clEnqueueNDRangeKernel_fn)( |
| 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_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clEnqueueTask_fn)(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_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clEnqueueNativeKernel_fn)( |
| cl_command_queue /* command_queue */, void(CL_CALLBACK* user_func)(void*), 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_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clEnqueueMarker_fn)(cl_command_queue /* command_queue */, |
| cl_event* /* event */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clEnqueueWaitForEvents_fn)( |
| cl_command_queue /* command_queue */, cl_uint /* num_events */, |
| const cl_event* /* event_list */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clEnqueueBarrier_fn)(cl_command_queue /* command_queue */) |
| CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef void*(CL_API_CALL* clGetExtensionFunctionAddress_fn)(const char* /* func_name */) |
| CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_mem(CL_API_CALL* clCreateFromGLBuffer_fn)( |
| cl_context /* context */, cl_mem_flags /* flags */, cl_GLuint /* bufobj */, |
| int* /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_mem(CL_API_CALL* clCreateFromGLTexture2D_fn)( |
| cl_context /* context */, cl_mem_flags /* flags */, cl_GLenum /* target */, |
| cl_GLint /* miplevel */, cl_GLuint /* texture */, |
| cl_int* /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_mem(CL_API_CALL* clCreateFromGLTexture3D_fn)( |
| cl_context /* context */, cl_mem_flags /* flags */, cl_GLenum /* target */, |
| cl_GLint /* miplevel */, cl_GLuint /* texture */, |
| cl_int* /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_mem(CL_API_CALL* clCreateFromGLRenderbuffer_fn)( |
| cl_context /* context */, cl_mem_flags /* flags */, cl_GLuint /* renderbuffer */, |
| cl_int* /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clGetGLObjectInfo_fn)( |
| cl_mem /* memobj */, cl_gl_object_type* /* gl_object_type */, |
| cl_GLuint* /* gl_object_name */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clGetGLTextureInfo_fn)( |
| cl_mem /* memobj */, cl_gl_texture_info /* param_name */, size_t /* param_value_size */, |
| void* /* param_value */, size_t* /* param_value_size_ret */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_event(CL_API_CALL* clCreateEventFromGLsyncKHR_fn)( |
| cl_context /* context */, cl_GLsync /* cl_GLsync */, |
| cl_int* /* errcode_ret */) CL_API_SUFFIX__VERSION_1_1; |
| |
| typedef cl_int(CL_API_CALL* clEnqueueAcquireGLObjects_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 */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clEnqueueReleaseGLObjects_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 */) CL_API_SUFFIX__VERSION_1_0; |
| |
| typedef cl_int(CL_API_CALL* clCreateSubDevices_fn)( |
| cl_device_id /* in_device */, const cl_device_partition_property* /* properties */, |
| cl_uint /* num_entries */, cl_device_id* /* out_devices */, |
| cl_uint* /* num_devices */) CL_API_SUFFIX__VERSION_1_2; |
| |
| typedef cl_int(CL_API_CALL* clRetainDevice_fn)(cl_device_id /* device */) |
| CL_API_SUFFIX__VERSION_1_2; |
| |
| typedef cl_int(CL_API_CALL* clReleaseDevice_fn)(cl_device_id /* device */) |
| CL_API_SUFFIX__VERSION_1_2; |
| |
| typedef cl_mem(CL_API_CALL* clCreateImage_fn)(cl_context /* context */, cl_mem_flags /* flags */, |
| const cl_image_format* /* image_format*/, |
| const cl_image_desc* /* image_desc*/, |
| void* /* host_ptr */, |
| cl_int* /* errcode_ret */) CL_API_SUFFIX__VERSION_1_2; |
| |
| typedef cl_program(CL_API_CALL* clCreateProgramWithBuiltInKernels_fn)( |
| cl_context /* context */, cl_uint /* num_devices */, const cl_device_id* /* device_list */, |
| const char* /* kernel_names */, cl_int* /* errcode_ret */) CL_API_SUFFIX__VERSION_1_2; |
| |
| typedef cl_int(CL_API_CALL* clCompileProgram_fn)( |
| cl_program /* program */, cl_uint /* num_devices */, const cl_device_id* /* device_list */, |
| const char* /* options */, cl_uint /* num_input_headers */, |
| const cl_program* /* input_headers */, const char** /* header_include_names */, |
| void(CL_CALLBACK* pfn_notify)(cl_program program, void* user_data), |
| void* /* user_data */) CL_API_SUFFIX__VERSION_1_2; |
| |
| typedef cl_program(CL_API_CALL* clLinkProgram_fn)( |
| cl_context /* context */, cl_uint /* num_devices */, const cl_device_id* /* device_list */, |
| const char* /* options */, cl_uint /* num_input_programs */, |
| const cl_program* /* input_programs */, |
| void(CL_CALLBACK* pfn_notify)(cl_program program, void* user_data), void* /* user_data */, |
| cl_int* /* errcode_ret */) CL_API_SUFFIX__VERSION_1_2; |
| |
| typedef cl_int(CL_API_CALL* clUnloadPlatformCompiler_fn)(cl_platform_id /* platform */) |
| CL_API_SUFFIX__VERSION_1_2; |
| |
| typedef cl_int(CL_API_CALL* clGetKernelArgInfo_fn)( |
| cl_kernel /* kernel */, cl_uint /* arg_indx */, cl_kernel_arg_info /* param_name */, |
| size_t /* param_value_size */, void* /* param_value */, |
| size_t* /* param_value_size_ret */) CL_API_SUFFIX__VERSION_1_2; |
| |
| typedef cl_int(CL_API_CALL* clEnqueueFillBuffer_fn)( |
| cl_command_queue /* command_queue */, cl_mem /* buffer */, const void* /* pattern */, |
| size_t /* pattern_size */, size_t /* offset */, size_t /* size */, |
| cl_uint /* num_events_in_wait_list */, const cl_event* /* event_wait_list */, |
| cl_event* /* event */) CL_API_SUFFIX__VERSION_1_2; |
| |
| typedef cl_int(CL_API_CALL* clEnqueueFillImage_fn)( |
| cl_command_queue /* command_queue */, cl_mem /* image */, const void* /* fill_color */, |
| const size_t* /* origin */, const size_t* /* region */, cl_uint /* num_events_in_wait_list */, |
| const cl_event* /* event_wait_list */, cl_event* /* event */) CL_API_SUFFIX__VERSION_1_2; |
| |
| typedef cl_int(CL_API_CALL* clEnqueueMigrateMemObjects_fn)( |
| cl_command_queue /* command_queue */, cl_uint /* num_mem_objects */, |
| const cl_mem* /* mem_objects */, cl_mem_migration_flags /* flags */, |
| cl_uint /* num_events_in_wait_list */, const cl_event* /* event_wait_list */, |
| cl_event* /* event */) CL_API_SUFFIX__VERSION_1_2; |
| |
| typedef cl_int(CL_API_CALL* clEnqueueMarkerWithWaitList_fn)( |
| cl_command_queue /* command_queue */, cl_uint /* num_events_in_wait_list */, |
| const cl_event* /* event_wait_list */, cl_event* /* event */) CL_API_SUFFIX__VERSION_1_2; |
| |
| typedef cl_int(CL_API_CALL* clEnqueueBarrierWithWaitList_fn)( |
| cl_command_queue /* command_queue */, cl_uint /* num_events_in_wait_list */, |
| const cl_event* /* event_wait_list */, cl_event* /* event */) CL_API_SUFFIX__VERSION_1_2; |
| |
| typedef void*(CL_API_CALL* clGetExtensionFunctionAddressForPlatform_fn)( |
| cl_platform_id /* platform */, const char* /* funcname */)CL_API_SUFFIX__VERSION_1_2; |
| |
| typedef cl_mem(CL_API_CALL* clCreateFromGLTexture_fn)( |
| cl_context /* context */, cl_mem_flags /* flags */, cl_GLenum /* texture_target */, |
| cl_GLint /* miplevel */, cl_GLuint /* texture */, |
| cl_int* /* errcode_ret */) CL_API_SUFFIX__VERSION_1_2; |
| |
| typedef cl_command_queue(CL_API_CALL* clCreateCommandQueueWithProperties_fn)( |
| cl_context /* context */, cl_device_id /* device */, |
| const cl_queue_properties* /* properties */, |
| cl_int* /* errcode_ret */) CL_API_SUFFIX__VERSION_2_0; |
| |
| typedef cl_sampler(CL_API_CALL* clCreateSamplerWithProperties_fn)( |
| cl_context /* context */, const cl_sampler_properties* /* properties */, |
| cl_int* /* errcode_ret */) CL_API_SUFFIX__VERSION_2_0; |
| |
| typedef void*(CL_API_CALL* clSVMAlloc_fn)(cl_context /* context */, cl_svm_mem_flags /* flags */, |
| size_t /* size */, |
| cl_uint /* alignment */)CL_API_SUFFIX__VERSION_2_0; |
| |
| typedef void(CL_API_CALL* clSVMFree_fn)(cl_context /* context */, |
| void* /* svm_pointer */) CL_API_SUFFIX__VERSION_2_0; |
| |
| typedef cl_int(CL_API_CALL* clSetKernelArgSVMPointer_fn)( |
| cl_kernel /* kernel */, cl_uint /* arg_index */, |
| const void* /* arg_value */) CL_API_SUFFIX__VERSION_2_0; |
| |
| typedef cl_int(CL_API_CALL* clSetKernelExecInfo_fn)( |
| cl_kernel /* kernel */, cl_kernel_exec_info /* param_name */, size_t /* param_value_size */, |
| const void* /* param_value */) CL_API_SUFFIX__VERSION_2_0; |
| |
| typedef cl_int(CL_API_CALL* clEnqueueSVMFree_fn)( |
| cl_command_queue /* command_queue */, cl_uint /* num_svm_pointers */, |
| void* [] /* svm_pointers */, |
| void(CL_CALLBACK* /* pfn_free_func */)(cl_command_queue /* queue */, |
| cl_uint /* num_svm_pointers */, |
| void* [] /* svm_pointers */, void* /* user_data */), |
| void* /* user_data */, cl_uint /* num_events_in_wait_list */, |
| const cl_event* /* event_wait_list */, cl_event* /* event */) CL_API_SUFFIX__VERSION_2_0; |
| |
| typedef cl_int(CL_API_CALL* clEnqueueSVMMemcpy_fn)( |
| cl_command_queue /* command_queue */, cl_bool /* blocking_copy */, void* /* dst_ptr */, |
| const void* /* src_ptr */, size_t /* size */, cl_uint /* num_events_in_wait_list */, |
| const cl_event* /* event_wait_list */, cl_event* /* event */) CL_API_SUFFIX__VERSION_2_0; |
| |
| typedef cl_int(CL_API_CALL* clEnqueueSVMMemFill_fn)( |
| cl_command_queue /* command_queue */, void* /* svm_ptr */, const void* /* pattern */, |
| size_t /* pattern_size */, size_t /* size */, cl_uint /* num_events_in_wait_list */, |
| const cl_event* /* event_wait_list */, cl_event* /* event */) CL_API_SUFFIX__VERSION_2_0; |
| |
| typedef cl_int(CL_API_CALL* clEnqueueSVMMap_fn)( |
| cl_command_queue /* command_queue */, cl_bool /* blocking_map */, cl_map_flags /* flags */, |
| void* /* svm_ptr */, size_t /* size */, cl_uint /* num_events_in_wait_list */, |
| const cl_event* /* event_wait_list */, cl_event* /* event */) CL_API_SUFFIX__VERSION_2_0; |
| |
| typedef cl_int(CL_API_CALL* clEnqueueSVMUnmap_fn)(cl_command_queue /* command_queue */, |
| void* /* svm_ptr */, |
| cl_uint /* num_events_in_wait_list */, |
| const cl_event* /* event_wait_list */, |
| cl_event* /* event */) CL_API_SUFFIX__VERSION_2_0; |
| |
| typedef cl_mem(CL_API_CALL* clCreatePipe_fn)(cl_context /* context */, cl_mem_flags /* flags */, |
| cl_uint /* pipe_packet_size */, |
| cl_uint /* pipe_max_packets */, |
| const cl_pipe_properties* /* properties */, |
| cl_int* /* errcode_ret */) CL_API_SUFFIX__VERSION_2_0; |
| |
| typedef cl_int(CL_API_CALL* clGetPipeInfo_fn)( |
| cl_mem /* pipe */, cl_pipe_info /* param_name */, size_t /* param_value_size */, |
| void* /* param_value */, size_t* /* param_value_size_ret */) CL_API_SUFFIX__VERSION_2_0; |
| |
| typedef cl_int(CL_API_CALL* clGetKernelSubGroupInfoKHR_fn)( |
| cl_kernel /* kernel */, cl_device_id /* device */, cl_kernel_sub_group_info /* param_name */, |
| size_t /* input_value_size */, const void* /* input_value */, size_t /* param_value_size */, |
| void* /* param_value */, size_t* /* param_value_size_ret */) CL_API_SUFFIX__VERSION_2_0; |
| |
| |
| typedef cl_int(CL_API_CALL* clSetDefaultDeviceCommandQueue_fn)( |
| cl_context /* context */, cl_device_id /* device */, |
| cl_command_queue /* command_queue */) CL_API_SUFFIX__VERSION_2_1; |
| |
| typedef cl_kernel(CL_API_CALL* clCloneKernel_fn)( |
| cl_kernel /* source_kernel */, cl_int * /* errcode_ret */) CL_API_SUFFIX__VERSION_2_1; |
| |
| typedef cl_int (CL_API_CALL* clEnqueueSVMMigrateMem_fn)( |
| cl_command_queue /* command_queue */, cl_uint /* num_svm_pointers */, |
| const void ** /* svm_pointers */, const size_t * /* sizes */, |
| cl_mem_migration_flags /* flags */, cl_uint /* num_events_in_wait_list */, |
| const cl_event * /* event_wait_list */, cl_event * /* event */) CL_API_SUFFIX__VERSION_2_1; |
| |
| typedef cl_int (CL_API_CALL* clGetDeviceAndHostTimer_fn)( |
| cl_device_id /* device */, cl_ulong * /* device_timestamp */, |
| cl_ulong * /* host_timestamp */) CL_API_SUFFIX__VERSION_2_1; |
| |
| typedef cl_int (CL_API_CALL* clGetHostTimer_fn)( |
| cl_device_id /* device */, cl_ulong * /* host_timestamp */) CL_API_SUFFIX__VERSION_2_1; |
| |
| typedef cl_int (CL_API_CALL* clSetProgramSpecializationConstant_fn)( |
| cl_program /* program */, cl_uint /* spec_id */, size_t /* spec_size */, |
| const void* /* spec_value */) CL_API_SUFFIX__VERSION_2_2; |
| |
| typedef cl_int (CL_API_CALL* clSetProgramReleaseCallback_fn)( |
| cl_program /* program */, |
| void (CL_CALLBACK * /* pfn_notify */)(cl_program program, void * user_data), |
| void * /* user_data */) CL_API_SUFFIX__VERSION_2_2; |
| |
| typedef struct _cl_icd_dispatch_table { |
| /* OpenCL 1.0 */ |
| clGetPlatformIDs_fn GetPlatformIDs; |
| clGetPlatformInfo_fn GetPlatformInfo; |
| clGetDeviceIDs_fn GetDeviceIDs; |
| clGetDeviceInfo_fn GetDeviceInfo; |
| clCreateContext_fn CreateContext; |
| clCreateContextFromType_fn CreateContextFromType; |
| clRetainContext_fn RetainContext; |
| clReleaseContext_fn ReleaseContext; |
| clGetContextInfo_fn GetContextInfo; |
| clCreateCommandQueue_fn CreateCommandQueue; |
| clRetainCommandQueue_fn RetainCommandQueue; |
| clReleaseCommandQueue_fn ReleaseCommandQueue; |
| clGetCommandQueueInfo_fn GetCommandQueueInfo; |
| clSetCommandQueueProperty_fn SetCommandQueueProperty; |
| clCreateBuffer_fn CreateBuffer; |
| clCreateImage2D_fn CreateImage2D; |
| clCreateImage3D_fn CreateImage3D; |
| clRetainMemObject_fn RetainMemObject; |
| clReleaseMemObject_fn ReleaseMemObject; |
| clGetSupportedImageFormats_fn GetSupportedImageFormats; |
| clGetMemObjectInfo_fn GetMemObjectInfo; |
| clGetImageInfo_fn GetImageInfo; |
| clCreateSampler_fn CreateSampler; |
| clRetainSampler_fn RetainSampler; |
| clReleaseSampler_fn ReleaseSampler; |
| clGetSamplerInfo_fn GetSamplerInfo; |
| clCreateProgramWithSource_fn CreateProgramWithSource; |
| clCreateProgramWithBinary_fn CreateProgramWithBinary; |
| clRetainProgram_fn RetainProgram; |
| clReleaseProgram_fn ReleaseProgram; |
| clBuildProgram_fn BuildProgram; |
| clUnloadCompiler_fn UnloadCompiler; |
| clGetProgramInfo_fn GetProgramInfo; |
| clGetProgramBuildInfo_fn GetProgramBuildInfo; |
| clCreateKernel_fn CreateKernel; |
| clCreateKernelsInProgram_fn CreateKernelsInProgram; |
| clRetainKernel_fn RetainKernel; |
| clReleaseKernel_fn ReleaseKernel; |
| clSetKernelArg_fn SetKernelArg; |
| clGetKernelInfo_fn GetKernelInfo; |
| clGetKernelWorkGroupInfo_fn GetKernelWorkGroupInfo; |
| clWaitForEvents_fn WaitForEvents; |
| clGetEventInfo_fn GetEventInfo; |
| clRetainEvent_fn RetainEvent; |
| clReleaseEvent_fn ReleaseEvent; |
| clGetEventProfilingInfo_fn GetEventProfilingInfo; |
| clFlush_fn Flush; |
| clFinish_fn Finish; |
| clEnqueueReadBuffer_fn EnqueueReadBuffer; |
| clEnqueueWriteBuffer_fn EnqueueWriteBuffer; |
| clEnqueueCopyBuffer_fn EnqueueCopyBuffer; |
| clEnqueueReadImage_fn EnqueueReadImage; |
| clEnqueueWriteImage_fn EnqueueWriteImage; |
| clEnqueueCopyImage_fn EnqueueCopyImage; |
| clEnqueueCopyImageToBuffer_fn EnqueueCopyImageToBuffer; |
| clEnqueueCopyBufferToImage_fn EnqueueCopyBufferToImage; |
| clEnqueueMapBuffer_fn EnqueueMapBuffer; |
| clEnqueueMapImage_fn EnqueueMapImage; |
| clEnqueueUnmapMemObject_fn EnqueueUnmapMemObject; |
| clEnqueueNDRangeKernel_fn EnqueueNDRangeKernel; |
| clEnqueueTask_fn EnqueueTask; |
| clEnqueueNativeKernel_fn EnqueueNativeKernel; |
| clEnqueueMarker_fn EnqueueMarker; |
| clEnqueueWaitForEvents_fn EnqueueWaitForEvents; |
| clEnqueueBarrier_fn EnqueueBarrier; |
| clGetExtensionFunctionAddress_fn GetExtensionFunctionAddress; |
| clCreateFromGLBuffer_fn CreateFromGLBuffer; |
| clCreateFromGLTexture2D_fn CreateFromGLTexture2D; |
| clCreateFromGLTexture3D_fn CreateFromGLTexture3D; |
| clCreateFromGLRenderbuffer_fn CreateFromGLRenderbuffer; |
| clGetGLObjectInfo_fn GetGLObjectInfo; |
| clGetGLTextureInfo_fn GetGLTextureInfo; |
| clEnqueueAcquireGLObjects_fn EnqueueAcquireGLObjects; |
| clEnqueueReleaseGLObjects_fn EnqueueReleaseGLObjects; |
| clGetGLContextInfoKHR_fn GetGLContextInfoKHR; |
| void* _reservedForD3D10KHR[6]; |
| /* OpenCL 1.1 */ |
| clSetEventCallback_fn SetEventCallback; |
| clCreateSubBuffer_fn CreateSubBuffer; |
| clSetMemObjectDestructorCallback_fn SetMemObjectDestructorCallback; |
| clCreateUserEvent_fn CreateUserEvent; |
| clSetUserEventStatus_fn SetUserEventStatus; |
| clEnqueueReadBufferRect_fn EnqueueReadBufferRect; |
| clEnqueueWriteBufferRect_fn EnqueueWriteBufferRect; |
| clEnqueueCopyBufferRect_fn EnqueueCopyBufferRect; |
| |
| void* _reservedForDeviceFissionEXT[3]; |
| clCreateEventFromGLsyncKHR_fn CreateEventFromGLsyncKHR; |
| |
| /* OpenCL 1.2 */ |
| clCreateSubDevices_fn CreateSubDevices; |
| clRetainDevice_fn RetainDevice; |
| clReleaseDevice_fn ReleaseDevice; |
| clCreateImage_fn CreateImage; |
| clCreateProgramWithBuiltInKernels_fn CreateProgramWithBuiltInKernels; |
| clCompileProgram_fn CompileProgram; |
| clLinkProgram_fn LinkProgram; |
| clUnloadPlatformCompiler_fn UnloadPlatformCompiler; |
| clGetKernelArgInfo_fn GetKernelArgInfo; |
| clEnqueueFillBuffer_fn EnqueueFillBuffer; |
| clEnqueueFillImage_fn EnqueueFillImage; |
| clEnqueueMigrateMemObjects_fn EnqueueMigrateMemObjects; |
| clEnqueueMarkerWithWaitList_fn EnqueueMarkerWithWaitList; |
| clEnqueueBarrierWithWaitList_fn EnqueueBarrierWithWaitList; |
| clGetExtensionFunctionAddressForPlatform_fn GetExtensionFunctionAddressForPlatform; |
| clCreateFromGLTexture_fn CreateFromGLTexture; |
| |
| /* cl_khr_d3d11_sharing, cl_khr_dx9_media_sharing */ |
| void* _reservedD3DExtensions[10]; |
| |
| /* cl_khr_egl_image, cl_khr_egl_event */ |
| void* _reservedEGLExtensions[4]; |
| |
| /* OpenCL 2.0 */ |
| clCreateCommandQueueWithProperties_fn CreateCommandQueueWithProperties; |
| clCreatePipe_fn CreatePipe; |
| clGetPipeInfo_fn GetPipeInfo; |
| clSVMAlloc_fn SVMAlloc; |
| clSVMFree_fn SVMFree; |
| clEnqueueSVMFree_fn EnqueueSVMFree; |
| clEnqueueSVMMemcpy_fn EnqueueSVMMemcpy; |
| clEnqueueSVMMemFill_fn EnqueueSVMMemFill; |
| clEnqueueSVMMap_fn EnqueueSVMMap; |
| clEnqueueSVMUnmap_fn EnqueueSVMUnmap; |
| clCreateSamplerWithProperties_fn CreateSamplerWithProperties; |
| clSetKernelArgSVMPointer_fn SetKernelArgSVMPointer; |
| clSetKernelExecInfo_fn SetKernelExecInfo; |
| |
| /* cl_khr_sub_groups */ |
| clGetKernelSubGroupInfoKHR_fn clGetKernelSubGroupInfoKHR; |
| |
| /* OpenCL 2.1 */ |
| clCloneKernel_fn clCloneKernel; |
| clCreateProgramWithILKHR_fn clCreateProgramWithIL; |
| clEnqueueSVMMigrateMem_fn clEnqueueSVMMigrateMem; |
| clGetDeviceAndHostTimer_fn clGetDeviceAndHostTimer; |
| clGetHostTimer_fn clGetHostTimer; |
| clGetKernelSubGroupInfoKHR_fn clGetKernelSubGroupInfo; |
| clSetDefaultDeviceCommandQueue_fn clSetDefaultDeviceCommandQueue; |
| |
| /* OpenCL 2.2 */ |
| clSetProgramReleaseCallback_fn clSetProgramReleaseCallback; |
| clSetProgramSpecializationConstant_fn clSetProgramSpecializationConstant; |
| |
| } cl_icd_dispatch_table; |
| |
| #ifdef __cplusplus |
| } |
| #endif /* __cplusplus */ |
| |
| #endif /* __OPENCL_CL_ICD_H */ |
