| // |
| // Copyright 2013 Francisco Jerez |
| // |
| // Permission is hereby granted, free of charge, to any person obtaining a |
| // copy of this software and associated documentation files (the "Software"), |
| // to deal in the Software without restriction, including without limitation |
| // the rights to use, copy, modify, merge, publish, distribute, sublicense, |
| // and/or sell copies of the Software, and to permit persons to whom the |
| // Software is 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 Software. |
| // |
| // THE SOFTWARE IS 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 SOFTWARE OR THE USE OR |
| // OTHER DEALINGS IN THE SOFTWARE. |
| // |
| |
| #ifndef API_DISPATCH_HPP |
| #define API_DISPATCH_HPP |
| |
| #define CL_USE_DEPRECATED_OPENCL_1_1_APIS |
| |
| #include "CL/cl.h" |
| #include "CL/cl_ext.h" |
| #include "CL/cl_gl.h" |
| |
| /// |
| /// OpenCL ICD vendor dispatch table. |
| /// |
| /// The entry point ordering should always be in agreement with |
| /// Khronos' ICD loader. |
| /// |
| struct _cl_icd_dispatch { |
| CL_API_ENTRY cl_int (CL_API_CALL *clGetPlatformIDs)( |
| cl_uint num_entries, |
| cl_platform_id *platforms, |
| cl_uint *num_platforms); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clGetPlatformInfo)( |
| 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_ENTRY cl_int (CL_API_CALL *clGetDeviceIDs)( |
| cl_platform_id platform, |
| cl_device_type device_type, |
| cl_uint num_entries, |
| cl_device_id *devices, |
| cl_uint *num_devices); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clGetDeviceInfo)( |
| 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_ENTRY cl_context (CL_API_CALL *clCreateContext)( |
| 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_ENTRY cl_context (CL_API_CALL *clCreateContextFromType)( |
| 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_ENTRY cl_int (CL_API_CALL *clRetainContext)( |
| cl_context context); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clReleaseContext)( |
| cl_context context); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clGetContextInfo)( |
| cl_context context, |
| cl_context_info param_name, |
| size_t param_value_size, |
| void *param_value, |
| size_t *param_value_size_ret); |
| |
| CL_API_ENTRY cl_command_queue (CL_API_CALL *clCreateCommandQueue)( |
| cl_context context, |
| cl_device_id device, |
| cl_command_queue_properties properties, |
| cl_int *errcode_ret); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clRetainCommandQueue)( |
| cl_command_queue command_queue); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clReleaseCommandQueue)( |
| cl_command_queue command_queue); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *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_API_ENTRY cl_int (CL_API_CALL *clSetCommandQueueProperty)( |
| cl_command_queue command_queue, |
| cl_command_queue_properties properties, |
| cl_bool enable, |
| cl_command_queue_properties *old_properties); |
| |
| CL_API_ENTRY cl_mem (CL_API_CALL *clCreateBuffer)( |
| cl_context context, |
| cl_mem_flags flags, |
| size_t size, |
| void *host_ptr, |
| cl_int *errcode_ret); |
| |
| CL_API_ENTRY cl_mem (CL_API_CALL *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_API_ENTRY cl_mem (CL_API_CALL *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_API_ENTRY cl_int (CL_API_CALL *clRetainMemObject)( |
| cl_mem memobj); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clReleaseMemObject)( |
| cl_mem memobj); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *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_API_ENTRY cl_int (CL_API_CALL *clGetMemObjectInfo)( |
| cl_mem memobj, |
| cl_mem_info param_name, |
| size_t param_value_size, |
| void *param_value, |
| size_t *param_value_size_ret); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clGetImageInfo)( |
| cl_mem image, |
| cl_image_info param_name, |
| size_t param_value_size, |
| void *param_value, |
| size_t *param_value_size_ret); |
| |
| CL_API_ENTRY cl_sampler (CL_API_CALL *clCreateSampler)( |
| cl_context context, |
| cl_bool normalized_coords, |
| cl_addressing_mode addressing_mode, |
| cl_filter_mode filter_mode, |
| cl_int *errcode_ret); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clRetainSampler)( |
| cl_sampler sampler); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clReleaseSampler)( |
| cl_sampler sampler); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clGetSamplerInfo)( |
| cl_sampler sampler, |
| cl_sampler_info param_name, |
| size_t param_value_size, |
| void *param_value, |
| size_t *param_value_size_ret); |
| |
| CL_API_ENTRY cl_program (CL_API_CALL *clCreateProgramWithSource)( |
| cl_context context, |
| cl_uint count, |
| const char **strings, |
| const size_t *lengths, |
| cl_int *errcode_ret); |
| |
| CL_API_ENTRY cl_program (CL_API_CALL *clCreateProgramWithBinary)( |
| 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_ENTRY cl_int (CL_API_CALL *clRetainProgram)( |
| cl_program program); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clReleaseProgram)( |
| cl_program program); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clBuildProgram)( |
| cl_program program, |
| cl_uint num_devices, |
| const cl_device_id *device_list, |
| const char *options, |
| void (CL_CALLBACK *pfn_notify)(cl_program, void *), |
| void *user_data); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clUnloadCompiler)( |
| void); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clGetProgramInfo)( |
| cl_program program, |
| cl_program_info param_name, |
| size_t param_value_size, |
| void *param_value, |
| size_t *param_value_size_ret); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *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); |
| |
| CL_API_ENTRY cl_kernel (CL_API_CALL *clCreateKernel)( |
| cl_program program, |
| const char *kernel_name, |
| cl_int *errcode_ret); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clCreateKernelsInProgram)( |
| cl_program program, |
| cl_uint num_kernels, |
| cl_kernel *kernels, |
| cl_uint *num_kernels_ret); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clRetainKernel)( |
| cl_kernel kernel); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clReleaseKernel)( |
| cl_kernel kernel); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clSetKernelArg)( |
| cl_kernel kernel, |
| cl_uint arg_index, |
| size_t arg_size, |
| const void *arg_value); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clGetKernelInfo)( |
| cl_kernel kernel, |
| cl_kernel_info param_name, |
| size_t param_value_size, |
| void *param_value, |
| size_t *param_value_size_ret); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *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); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clWaitForEvents)( |
| cl_uint num_events, |
| const cl_event *event_list); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clGetEventInfo)( |
| cl_event event, |
| cl_event_info param_name, |
| size_t param_value_size, |
| void *param_value, |
| size_t *param_value_size_ret); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clRetainEvent)( |
| cl_event event); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clReleaseEvent)( |
| cl_event event); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clGetEventProfilingInfo)( |
| cl_event event, |
| cl_profiling_info param_name, |
| size_t param_value_size, |
| void *param_value, |
| size_t *param_value_size_ret); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clFlush)( |
| cl_command_queue command_queue); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clFinish)( |
| cl_command_queue command_queue); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *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_API_ENTRY cl_int (CL_API_CALL *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_API_ENTRY cl_int (CL_API_CALL *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_API_ENTRY cl_int (CL_API_CALL *clEnqueueReadImage)( |
| cl_command_queue command_queue, |
| cl_mem image, |
| cl_bool blocking_read, |
| const size_t *origin, |
| const size_t *region, |
| 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_ENTRY cl_int (CL_API_CALL *clEnqueueWriteImage)( |
| cl_command_queue command_queue, |
| cl_mem image, |
| cl_bool blocking_write, |
| const size_t *origin, |
| const size_t *region, |
| 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_ENTRY cl_int (CL_API_CALL *clEnqueueCopyImage)( |
| cl_command_queue command_queue, |
| cl_mem src_image, |
| cl_mem dst_image, |
| const size_t *src_origin, |
| const size_t *dst_origin, |
| const size_t *region, |
| cl_uint num_events_in_wait_list, |
| const cl_event *event_wait_list, |
| cl_event *event); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clEnqueueCopyImageToBuffer)( |
| cl_command_queue command_queue, |
| cl_mem src_image, |
| cl_mem dst_buffer, |
| const size_t *src_origin, |
| const size_t *region, |
| size_t dst_offset, |
| cl_uint num_events_in_wait_list, |
| const cl_event *event_wait_list, |
| cl_event *event); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clEnqueueCopyBufferToImage)( |
| cl_command_queue command_queue, |
| cl_mem src_buffer, |
| cl_mem dst_image, |
| size_t src_offset, |
| const size_t *dst_origin, |
| const size_t *region, |
| cl_uint num_events_in_wait_list, |
| const cl_event *event_wait_list, |
| cl_event *event); |
| |
| CL_API_ENTRY void *(CL_API_CALL *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); |
| |
| CL_API_ENTRY void *(CL_API_CALL *clEnqueueMapImage)( |
| cl_command_queue command_queue, |
| cl_mem image, |
| cl_bool blocking_map, |
| cl_map_flags map_flags, |
| const size_t *origin, |
| const size_t *region, |
| 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_ENTRY cl_int (CL_API_CALL *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_API_ENTRY cl_int (CL_API_CALL *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_API_ENTRY cl_int (CL_API_CALL *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_API_ENTRY cl_int (CL_API_CALL *clEnqueueNativeKernel)( |
| 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_ENTRY cl_int (CL_API_CALL *clEnqueueMarker)( |
| cl_command_queue command_queue, |
| cl_event *event); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clEnqueueWaitForEvents)( |
| cl_command_queue command_queue, |
| cl_uint num_events, |
| const cl_event *event_list); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clEnqueueBarrier)( |
| cl_command_queue command_queue); |
| |
| CL_API_ENTRY void *(CL_API_CALL *clGetExtensionFunctionAddress)( |
| const char *function_name); |
| |
| CL_API_ENTRY cl_mem (CL_API_CALL *clCreateFromGLBuffer)( |
| cl_context context, |
| cl_mem_flags flags, |
| cl_GLuint bufobj, |
| int *errcode_ret); |
| |
| CL_API_ENTRY cl_mem (CL_API_CALL *clCreateFromGLTexture2D)( |
| cl_context context, |
| cl_mem_flags flags, |
| cl_GLenum target, |
| cl_GLint miplevel, |
| cl_GLuint texture, |
| cl_int *errcode_ret); |
| |
| CL_API_ENTRY cl_mem (CL_API_CALL *clCreateFromGLTexture3D)( |
| cl_context context, |
| cl_mem_flags flags, |
| cl_GLenum target, |
| cl_GLint miplevel, |
| cl_GLuint texture, |
| cl_int *errcode_ret); |
| |
| CL_API_ENTRY cl_mem (CL_API_CALL *clCreateFromGLRenderbuffer)( |
| cl_context context, |
| cl_mem_flags flags, |
| cl_GLuint renderbuffer, |
| cl_int *errcode_ret); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clGetGLObjectInfo)( |
| cl_mem memobj, |
| cl_gl_object_type *gl_object_type, |
| cl_GLuint *gl_object_name); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *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_API_ENTRY cl_int (CL_API_CALL *clEnqueueAcquireGLObjects)( |
| 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_ENTRY cl_int (CL_API_CALL *clEnqueueReleaseGLObjects)( |
| 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_ENTRY cl_int (CL_API_CALL *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); |
| |
| void *clGetDeviceIDsFromD3D10KHR; |
| void *clCreateFromD3D10BufferKHR; |
| void *clCreateFromD3D10Texture2DKHR; |
| void *clCreateFromD3D10Texture3DKHR; |
| void *clEnqueueAcquireD3D10ObjectsKHR; |
| void *clEnqueueReleaseD3D10ObjectsKHR; |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clSetEventCallback)( |
| cl_event event, |
| cl_int type, |
| void (CL_CALLBACK *pfn_notify)(cl_event, cl_int, void *), |
| void *user_data); |
| |
| CL_API_ENTRY cl_mem (CL_API_CALL *clCreateSubBuffer)( |
| 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_ENTRY cl_int (CL_API_CALL *clSetMemObjectDestructorCallback)( |
| cl_mem memobj, |
| void (CL_CALLBACK *pfn_notify)(cl_mem, void *), |
| void *user_data); |
| |
| CL_API_ENTRY cl_event (CL_API_CALL *clCreateUserEvent)( |
| cl_context context, |
| cl_int *errcode_ret); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clSetUserEventStatus)( |
| cl_event event, |
| cl_int status); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clEnqueueReadBufferRect)( |
| cl_command_queue command_queue, |
| cl_mem buffer, |
| cl_bool blocking_read, |
| const size_t *buffer_origin, |
| const size_t *host_origin, |
| 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_ENTRY cl_int (CL_API_CALL *clEnqueueWriteBufferRect)( |
| cl_command_queue command_queue, |
| cl_mem buffer, |
| cl_bool blocking_read, |
| const size_t *buffer_origin, |
| const size_t *host_origin, |
| 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_ENTRY cl_int (CL_API_CALL *clEnqueueCopyBufferRect)( |
| 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_ENTRY cl_int (CL_API_CALL *clCreateSubDevicesEXT)( |
| cl_device_id in_device, |
| const cl_device_partition_property_ext *partition_properties, |
| cl_uint num_entries, |
| cl_device_id *out_devices, |
| cl_uint *num_devices); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clRetainDeviceEXT)( |
| cl_device_id device); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clReleaseDeviceEXT)( |
| cl_device_id device); |
| |
| CL_API_ENTRY cl_event (CL_API_CALL *clCreateEventFromGLsyncKHR)( |
| cl_context context, |
| cl_GLsync sync, |
| cl_int *errcode_ret); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clCreateSubDevices)( |
| cl_device_id in_device, |
| const cl_device_partition_property *partition_properties, |
| cl_uint num_entries, |
| cl_device_id *out_devices, |
| cl_uint *num_devices); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clRetainDevice)( |
| cl_device_id device); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clReleaseDevice)( |
| cl_device_id device); |
| |
| CL_API_ENTRY cl_mem (CL_API_CALL *clCreateImage)( |
| 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_ENTRY cl_program (CL_API_CALL *clCreateProgramWithBuiltInKernels)( |
| cl_context context, |
| cl_uint num_devices, |
| const cl_device_id *device_list, |
| const char *kernel_names, |
| cl_int *errcode_ret); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clCompileProgram)( |
| 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, void *), |
| void *user_data); |
| |
| CL_API_ENTRY cl_program (CL_API_CALL *clLinkProgram)( |
| 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, void *), |
| void *user_data, |
| cl_int *errcode_ret); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clUnloadPlatformCompiler)( |
| cl_platform_id platform); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clGetKernelArgInfo)( |
| 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_ENTRY cl_int (CL_API_CALL *clEnqueueFillBuffer)( |
| 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_ENTRY cl_int (CL_API_CALL *clEnqueueFillImage)( |
| 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_ENTRY cl_int (CL_API_CALL *clEnqueueMigrateMemObjects)( |
| 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_ENTRY cl_int (CL_API_CALL *clEnqueueMarkerWithWaitList)( |
| cl_command_queue command_queue, |
| cl_uint num_events_in_wait_list, |
| const cl_event *event_wait_list, |
| cl_event *event); |
| |
| CL_API_ENTRY cl_int (CL_API_CALL *clEnqueueBarrierWithWaitList)( |
| cl_command_queue command_queue, |
| cl_uint num_events_in_wait_list, |
| const cl_event *event_wait_list, |
| cl_event *event); |
| |
| CL_API_ENTRY void *(CL_API_CALL *clGetExtensionFunctionAddressForPlatform)( |
| cl_platform_id platform, |
| const char *function_name); |
| |
| CL_API_ENTRY cl_mem (CL_API_CALL *clCreateFromGLTexture)( |
| cl_context context, |
| cl_mem_flags flags, |
| cl_GLenum target, |
| cl_GLint miplevel, |
| cl_GLuint texture, |
| cl_int *errcode_ret); |
| |
| void *clGetDeviceIDsFromD3D11KHR; |
| void *clCreateFromD3D11BufferKHR; |
| void *clCreateFromD3D11Texture2DKHR; |
| void *clCreateFromD3D11Texture3DKHR; |
| void *clCreateFromDX9MediaSurfaceKHR; |
| void *clEnqueueAcquireD3D11ObjectsKHR; |
| void *clEnqueueReleaseD3D11ObjectsKHR; |
| void *clGetDeviceIDsFromDX9MediaAdapterKHR; |
| void *clEnqueueAcquireDX9MediaSurfacesKHR; |
| void *clEnqueueReleaseDX9MediaSurfacesKHR; |
| }; |
| |
| namespace clover { |
| extern const _cl_icd_dispatch _dispatch; |
| |
| cl_int |
| GetPlatformInfo(cl_platform_id d_platform, cl_platform_info param, |
| size_t size, void *r_buf, size_t *r_size); |
| |
| void * |
| GetExtensionFunctionAddress(const char *p_name); |
| |
| void * |
| GetExtensionFunctionAddressForPlatform(cl_platform_id d_platform, |
| const char *p_name); |
| |
| cl_int |
| IcdGetPlatformIDsKHR(cl_uint num_entries, cl_platform_id *rd_platforms, |
| cl_uint *rnum_platforms); |
| } |
| |
| #endif |
