diff options
Diffstat (limited to 'src')
| -rw-r--r-- | src/gallium/state_trackers/clover/api/dispatch.cpp | 2 | ||||
| -rw-r--r-- | src/gallium/state_trackers/clover/api/dispatch.hpp | 930 | ||||
| -rw-r--r-- | src/gallium/state_trackers/clover/core/object.hpp | 2 |
3 files changed, 4 insertions, 930 deletions
diff --git a/src/gallium/state_trackers/clover/api/dispatch.cpp b/src/gallium/state_trackers/clover/api/dispatch.cpp index 8be4d3cb261..5671fe39814 100644 --- a/src/gallium/state_trackers/clover/api/dispatch.cpp +++ b/src/gallium/state_trackers/clover/api/dispatch.cpp @@ -23,7 +23,7 @@ #include "api/dispatch.hpp" namespace clover { - const _cl_icd_dispatch _dispatch = { + const cl_icd_dispatch _dispatch = { clGetPlatformIDs, GetPlatformInfo, clGetDeviceIDs, diff --git a/src/gallium/state_trackers/clover/api/dispatch.hpp b/src/gallium/state_trackers/clover/api/dispatch.hpp index ec924fef7d7..808b760a36c 100644 --- a/src/gallium/state_trackers/clover/api/dispatch.hpp +++ b/src/gallium/state_trackers/clover/api/dispatch.hpp @@ -36,936 +36,10 @@ #include "CL/cl_ext.h" #include "CL/cl_egl.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; - - CL_API_ENTRY void (CL_API_CALL *clCreateFromEGLImageKHR)( - cl_context context, - CLeglDisplayKHR display, - CLeglImageKHR image, - cl_mem_flags flags, - const cl_egl_image_properties_khr *properties, - cl_int *errcode_ret); - - CL_API_ENTRY void (CL_API_CALL *clEnqueueAcquireEGLObjectsKHR)( - 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 void (CL_API_CALL *clEnqueueReleaseEGLObjectsKHR)( - 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 void (CL_API_CALL *clCreateEventFromEGLSyncKHR)( - cl_context context, - CLeglSyncKHR sync, - CLeglDisplayKHR display, - cl_int *errcode_ret); - - CL_API_ENTRY cl_command_queue (CL_API_CALL *clCreateCommandQueueWithProperties)( - cl_context context, - cl_device_id device, - const cl_queue_properties *properties, - cl_int *errcode_ret); - - CL_API_ENTRY void (CL_API_CALL *clCreatePipe)( - 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_ENTRY void (CL_API_CALL *clGetPipeInfo)( - cl_mem pipe, - cl_pipe_info param_name, - size_t param_value_size, - void *param_value, - size_t *param_value_size_ret); - - CL_API_ENTRY void (CL_API_CALL *clSVMAlloc)( - cl_context context, - cl_svm_mem_flags flags, - size_t size, - unsigned int alignment); - - CL_API_ENTRY void (CL_API_CALL *clSVMFree)( - cl_context context, - void *svm_pointer); - - CL_API_ENTRY cl_int (CL_API_CALL *clEnqueueSVMFree)( - cl_command_queue command_queue, - cl_uint num_svm_pointers, - void **svm_pointers, - void (CL_CALLBACK *pfn_free_func)(cl_command_queue, cl_uint, void **, void *), - void *user_data, - cl_uint num_events_in_wait_list, - const cl_event *event_wait_list, - cl_event *event); - - CL_API_ENTRY cl_int (CL_API_CALL *clEnqueueSVMMemcpy)( - 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_ENTRY cl_int (CL_API_CALL *clEnqueueSVMMemFill)( - 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_ENTRY cl_int (CL_API_CALL *clEnqueueSVMMap)( - cl_command_queue command_queue, - cl_bool blocking_map, - cl_map_flags map_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_ENTRY cl_int (CL_API_CALL *clEnqueueSVMUnmap)( - 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_ENTRY void (CL_API_CALL *clCreateSamplerWithProperties)( - cl_context context, - const cl_sampler_properties *sampler_properties, - cl_int *errcode_ret); - - CL_API_ENTRY cl_int (CL_API_CALL *clSetKernelArgSVMPointer)( - cl_kernel kernel, - cl_uint arg_index, - const void *arg_value); - - CL_API_ENTRY void (CL_API_CALL *clSetKernelExecInfo)( - cl_kernel kernel, - cl_kernel_exec_info param_name, - size_t param_value_size, - const void *param_value); - - CL_API_ENTRY void (CL_API_CALL *clGetKernelSubGroupInfoKHR)( - 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_ENTRY cl_kernel (CL_API_CALL *clCloneKernel)( - cl_kernel source_kernel, - cl_int *errcode_ret); - - CL_API_ENTRY cl_program (CL_API_CALL *clCreateProgramWithIL)( - cl_context context, - const void *il, - size_t length, - cl_int *errcode_ret); - - CL_API_ENTRY cl_int (CL_API_CALL *clEnqueueSVMMigrateMem)( - 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_ENTRY cl_int (CL_API_CALL *clGetDeviceAndHostTimer)( - cl_device_id device, - cl_ulong *device_timestamp, - cl_ulong *host_timestamp); - - CL_API_ENTRY cl_int (CL_API_CALL *clGetHostTimer)( - cl_device_id device, - cl_ulong *host_timestamp); - - CL_API_ENTRY void (CL_API_CALL *clGetKernelSubGroupInfo)( - 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_ENTRY cl_int (CL_API_CALL *clSetDefaultDeviceCommandQueue)( - cl_context context, - cl_device_id device, - cl_command_queue command_queue); - - CL_API_ENTRY cl_int (CL_API_CALL *clSetProgramReleaseCallback)( - cl_program program, - void (CL_CALLBACK *pfn_notify)(cl_program program, void *user_data), - void *user_data); - - CL_API_ENTRY cl_int (CL_API_CALL *clSetProgramSpecializationConstant)( - cl_program program, - cl_uint spec_id, - size_t spec_size, - const void *spec_value); -}; +#include "CL/cl_icd.h" namespace clover { - extern const _cl_icd_dispatch _dispatch; + extern const cl_icd_dispatch _dispatch; cl_int GetPlatformInfo(cl_platform_id d_platform, cl_platform_info param, diff --git a/src/gallium/state_trackers/clover/core/object.hpp b/src/gallium/state_trackers/clover/core/object.hpp index 748fe9a12e8..8ed8e35630f 100644 --- a/src/gallium/state_trackers/clover/core/object.hpp +++ b/src/gallium/state_trackers/clover/core/object.hpp @@ -52,7 +52,7 @@ namespace clover { "ICD requires CL API objects to be standard layout."); } - const _cl_icd_dispatch *dispatch; + const cl_icd_dispatch *dispatch; }; struct default_tag; |