wine/dlls/opencl/unixlib.h
Zebediah Figura 2a863f401f opencl: Use types with consistent alignment for unixlib params structures.
Wine-Bug: https://bugs.winehq.org/show_bug.cgi?id=52389
Signed-off-by: Zebediah Figura <zfigura@codeweavers.com>
Signed-off-by: Alexandre Julliard <julliard@winehq.org>
2022-01-13 10:14:49 +01:00

889 lines
18 KiB
C

/* Automatically generated from OpenCL registry files; DO NOT EDIT! */
struct clBuildProgram_params
{
cl_program program;
uint32_t num_devices;
const cl_device_id* device_list;
const char* options;
void (WINAPI* pfn_notify)(cl_program program, void* user_data);
void* user_data;
};
struct clCompileProgram_params
{
cl_program program;
uint32_t num_devices;
const cl_device_id* device_list;
const char* options;
uint32_t num_input_headers;
const cl_program* input_headers;
const char** header_include_names;
void (WINAPI* pfn_notify)(cl_program program, void* user_data);
void* user_data;
};
struct clCreateBuffer_params
{
cl_mem* __retval;
cl_context context;
ULONGLONG flags;
SIZE_T size;
void* host_ptr;
cl_int* errcode_ret;
};
struct clCreateCommandQueue_params
{
cl_command_queue* __retval;
cl_context context;
cl_device_id device;
ULONGLONG properties;
cl_int* errcode_ret;
};
struct clCreateContext_params
{
cl_context* __retval;
const cl_context_properties* properties;
uint32_t num_devices;
const cl_device_id* devices;
void (WINAPI* pfn_notify)(const char* errinfo, const void* private_info, size_t cb, void* user_data);
void* user_data;
cl_int* errcode_ret;
};
struct clCreateContextFromType_params
{
cl_context* __retval;
const cl_context_properties* properties;
ULONGLONG device_type;
void (WINAPI* pfn_notify)(const char* errinfo, const void* private_info, size_t cb, void* user_data);
void* user_data;
cl_int* errcode_ret;
};
struct clCreateImage_params
{
cl_mem* __retval;
cl_context context;
ULONGLONG flags;
const cl_image_format* image_format;
const cl_image_desc* image_desc;
void* host_ptr;
cl_int* errcode_ret;
};
struct clCreateImage2D_params
{
cl_mem* __retval;
cl_context context;
ULONGLONG 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;
};
struct clCreateImage3D_params
{
cl_mem* __retval;
cl_context context;
ULONGLONG 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;
};
struct clCreateKernel_params
{
cl_kernel* __retval;
cl_program program;
const char* kernel_name;
cl_int* errcode_ret;
};
struct clCreateKernelsInProgram_params
{
cl_program program;
uint32_t num_kernels;
cl_kernel* kernels;
cl_uint* num_kernels_ret;
};
struct clCreateProgramWithBinary_params
{
cl_program* __retval;
cl_context context;
uint32_t num_devices;
const cl_device_id* device_list;
const size_t* lengths;
const unsigned char** binaries;
cl_int* binary_status;
cl_int* errcode_ret;
};
struct clCreateProgramWithBuiltInKernels_params
{
cl_program* __retval;
cl_context context;
uint32_t num_devices;
const cl_device_id* device_list;
const char* kernel_names;
cl_int* errcode_ret;
};
struct clCreateProgramWithSource_params
{
cl_program* __retval;
cl_context context;
uint32_t count;
const char** strings;
const size_t* lengths;
cl_int* errcode_ret;
};
struct clCreateSampler_params
{
cl_sampler* __retval;
cl_context context;
uint32_t normalized_coords;
uint32_t addressing_mode;
uint32_t filter_mode;
cl_int* errcode_ret;
};
struct clCreateSubBuffer_params
{
cl_mem* __retval;
cl_mem buffer;
ULONGLONG flags;
uint32_t buffer_create_type;
const void* buffer_create_info;
cl_int* errcode_ret;
};
struct clCreateSubDevices_params
{
cl_device_id in_device;
const cl_device_partition_property* properties;
uint32_t num_devices;
cl_device_id* out_devices;
cl_uint* num_devices_ret;
};
struct clCreateUserEvent_params
{
cl_event* __retval;
cl_context context;
cl_int* errcode_ret;
};
struct clEnqueueBarrier_params
{
cl_command_queue command_queue;
};
struct clEnqueueBarrierWithWaitList_params
{
cl_command_queue command_queue;
uint32_t num_events_in_wait_list;
const cl_event* event_wait_list;
cl_event* event;
};
struct clEnqueueCopyBuffer_params
{
cl_command_queue command_queue;
cl_mem src_buffer;
cl_mem dst_buffer;
SIZE_T src_offset;
SIZE_T dst_offset;
SIZE_T size;
uint32_t num_events_in_wait_list;
const cl_event* event_wait_list;
cl_event* event;
};
struct clEnqueueCopyBufferRect_params
{
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;
uint32_t num_events_in_wait_list;
const cl_event* event_wait_list;
cl_event* event;
};
struct clEnqueueCopyBufferToImage_params
{
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;
uint32_t num_events_in_wait_list;
const cl_event* event_wait_list;
cl_event* event;
};
struct clEnqueueCopyImage_params
{
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;
uint32_t num_events_in_wait_list;
const cl_event* event_wait_list;
cl_event* event;
};
struct clEnqueueCopyImageToBuffer_params
{
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;
uint32_t num_events_in_wait_list;
const cl_event* event_wait_list;
cl_event* event;
};
struct clEnqueueFillBuffer_params
{
cl_command_queue command_queue;
cl_mem buffer;
const void* pattern;
SIZE_T pattern_size;
SIZE_T offset;
SIZE_T size;
uint32_t num_events_in_wait_list;
const cl_event* event_wait_list;
cl_event* event;
};
struct clEnqueueFillImage_params
{
cl_command_queue command_queue;
cl_mem image;
const void* fill_color;
const size_t* origin;
const size_t* region;
uint32_t num_events_in_wait_list;
const cl_event* event_wait_list;
cl_event* event;
};
struct clEnqueueMapBuffer_params
{
void** __retval;
cl_command_queue command_queue;
cl_mem buffer;
uint32_t blocking_map;
ULONGLONG map_flags;
SIZE_T offset;
SIZE_T size;
uint32_t num_events_in_wait_list;
const cl_event* event_wait_list;
cl_event* event;
cl_int* errcode_ret;
};
struct clEnqueueMapImage_params
{
void** __retval;
cl_command_queue command_queue;
cl_mem image;
uint32_t blocking_map;
ULONGLONG map_flags;
const size_t* origin;
const size_t* region;
size_t* image_row_pitch;
size_t* image_slice_pitch;
uint32_t num_events_in_wait_list;
const cl_event* event_wait_list;
cl_event* event;
cl_int* errcode_ret;
};
struct clEnqueueMarker_params
{
cl_command_queue command_queue;
cl_event* event;
};
struct clEnqueueMarkerWithWaitList_params
{
cl_command_queue command_queue;
uint32_t num_events_in_wait_list;
const cl_event* event_wait_list;
cl_event* event;
};
struct clEnqueueMigrateMemObjects_params
{
cl_command_queue command_queue;
uint32_t num_mem_objects;
const cl_mem* mem_objects;
ULONGLONG flags;
uint32_t num_events_in_wait_list;
const cl_event* event_wait_list;
cl_event* event;
};
struct clEnqueueNDRangeKernel_params
{
cl_command_queue command_queue;
cl_kernel kernel;
uint32_t work_dim;
const size_t* global_work_offset;
const size_t* global_work_size;
const size_t* local_work_size;
uint32_t num_events_in_wait_list;
const cl_event* event_wait_list;
cl_event* event;
};
struct clEnqueueNativeKernel_params
{
cl_command_queue command_queue;
void (WINAPI* user_func)(void*);
void* args;
SIZE_T cb_args;
uint32_t num_mem_objects;
const cl_mem* mem_list;
const void** args_mem_loc;
uint32_t num_events_in_wait_list;
const cl_event* event_wait_list;
cl_event* event;
};
struct clEnqueueReadBuffer_params
{
cl_command_queue command_queue;
cl_mem buffer;
uint32_t blocking_read;
SIZE_T offset;
SIZE_T size;
void* ptr;
uint32_t num_events_in_wait_list;
const cl_event* event_wait_list;
cl_event* event;
};
struct clEnqueueReadBufferRect_params
{
cl_command_queue command_queue;
cl_mem buffer;
uint32_t 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;
uint32_t num_events_in_wait_list;
const cl_event* event_wait_list;
cl_event* event;
};
struct clEnqueueReadImage_params
{
cl_command_queue command_queue;
cl_mem image;
uint32_t blocking_read;
const size_t* origin;
const size_t* region;
SIZE_T row_pitch;
SIZE_T slice_pitch;
void* ptr;
uint32_t num_events_in_wait_list;
const cl_event* event_wait_list;
cl_event* event;
};
struct clEnqueueTask_params
{
cl_command_queue command_queue;
cl_kernel kernel;
uint32_t num_events_in_wait_list;
const cl_event* event_wait_list;
cl_event* event;
};
struct clEnqueueUnmapMemObject_params
{
cl_command_queue command_queue;
cl_mem memobj;
void* mapped_ptr;
uint32_t num_events_in_wait_list;
const cl_event* event_wait_list;
cl_event* event;
};
struct clEnqueueWaitForEvents_params
{
cl_command_queue command_queue;
uint32_t num_events;
const cl_event* event_list;
};
struct clEnqueueWriteBuffer_params
{
cl_command_queue command_queue;
cl_mem buffer;
uint32_t blocking_write;
SIZE_T offset;
SIZE_T size;
const void* ptr;
uint32_t num_events_in_wait_list;
const cl_event* event_wait_list;
cl_event* event;
};
struct clEnqueueWriteBufferRect_params
{
cl_command_queue command_queue;
cl_mem buffer;
uint32_t blocking_write;
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;
uint32_t num_events_in_wait_list;
const cl_event* event_wait_list;
cl_event* event;
};
struct clEnqueueWriteImage_params
{
cl_command_queue command_queue;
cl_mem image;
uint32_t blocking_write;
const size_t* origin;
const size_t* region;
SIZE_T input_row_pitch;
SIZE_T input_slice_pitch;
const void* ptr;
uint32_t num_events_in_wait_list;
const cl_event* event_wait_list;
cl_event* event;
};
struct clFinish_params
{
cl_command_queue command_queue;
};
struct clFlush_params
{
cl_command_queue command_queue;
};
struct clGetCommandQueueInfo_params
{
cl_command_queue command_queue;
uint32_t param_name;
SIZE_T param_value_size;
void* param_value;
size_t* param_value_size_ret;
};
struct clGetContextInfo_params
{
cl_context context;
uint32_t param_name;
SIZE_T param_value_size;
void* param_value;
size_t* param_value_size_ret;
};
struct clGetDeviceIDs_params
{
cl_platform_id platform;
ULONGLONG device_type;
uint32_t num_entries;
cl_device_id* devices;
cl_uint* num_devices;
};
struct clGetDeviceInfo_params
{
cl_device_id device;
uint32_t param_name;
SIZE_T param_value_size;
void* param_value;
size_t* param_value_size_ret;
};
struct clGetEventInfo_params
{
cl_event event;
uint32_t param_name;
SIZE_T param_value_size;
void* param_value;
size_t* param_value_size_ret;
};
struct clGetEventProfilingInfo_params
{
cl_event event;
uint32_t param_name;
SIZE_T param_value_size;
void* param_value;
size_t* param_value_size_ret;
};
struct clGetImageInfo_params
{
cl_mem image;
uint32_t param_name;
SIZE_T param_value_size;
void* param_value;
size_t* param_value_size_ret;
};
struct clGetKernelArgInfo_params
{
cl_kernel kernel;
uint32_t arg_index;
uint32_t param_name;
SIZE_T param_value_size;
void* param_value;
size_t* param_value_size_ret;
};
struct clGetKernelInfo_params
{
cl_kernel kernel;
uint32_t param_name;
SIZE_T param_value_size;
void* param_value;
size_t* param_value_size_ret;
};
struct clGetKernelWorkGroupInfo_params
{
cl_kernel kernel;
cl_device_id device;
uint32_t param_name;
SIZE_T param_value_size;
void* param_value;
size_t* param_value_size_ret;
};
struct clGetMemObjectInfo_params
{
cl_mem memobj;
uint32_t param_name;
SIZE_T param_value_size;
void* param_value;
size_t* param_value_size_ret;
};
struct clGetPlatformIDs_params
{
uint32_t num_entries;
cl_platform_id* platforms;
cl_uint* num_platforms;
};
struct clGetPlatformInfo_params
{
cl_platform_id platform;
uint32_t param_name;
SIZE_T param_value_size;
void* param_value;
size_t* param_value_size_ret;
};
struct clGetProgramBuildInfo_params
{
cl_program program;
cl_device_id device;
uint32_t param_name;
SIZE_T param_value_size;
void* param_value;
size_t* param_value_size_ret;
};
struct clGetProgramInfo_params
{
cl_program program;
uint32_t param_name;
SIZE_T param_value_size;
void* param_value;
size_t* param_value_size_ret;
};
struct clGetSamplerInfo_params
{
cl_sampler sampler;
uint32_t param_name;
SIZE_T param_value_size;
void* param_value;
size_t* param_value_size_ret;
};
struct clGetSupportedImageFormats_params
{
cl_context context;
ULONGLONG flags;
uint32_t image_type;
uint32_t num_entries;
cl_image_format* image_formats;
cl_uint* num_image_formats;
};
struct clLinkProgram_params
{
cl_program* __retval;
cl_context context;
uint32_t num_devices;
const cl_device_id* device_list;
const char* options;
uint32_t num_input_programs;
const cl_program* input_programs;
void (WINAPI* pfn_notify)(cl_program program, void* user_data);
void* user_data;
cl_int* errcode_ret;
};
struct clReleaseCommandQueue_params
{
cl_command_queue command_queue;
};
struct clReleaseContext_params
{
cl_context context;
};
struct clReleaseDevice_params
{
cl_device_id device;
};
struct clReleaseEvent_params
{
cl_event event;
};
struct clReleaseKernel_params
{
cl_kernel kernel;
};
struct clReleaseMemObject_params
{
cl_mem memobj;
};
struct clReleaseProgram_params
{
cl_program program;
};
struct clReleaseSampler_params
{
cl_sampler sampler;
};
struct clRetainCommandQueue_params
{
cl_command_queue command_queue;
};
struct clRetainContext_params
{
cl_context context;
};
struct clRetainDevice_params
{
cl_device_id device;
};
struct clRetainEvent_params
{
cl_event event;
};
struct clRetainKernel_params
{
cl_kernel kernel;
};
struct clRetainMemObject_params
{
cl_mem memobj;
};
struct clRetainProgram_params
{
cl_program program;
};
struct clRetainSampler_params
{
cl_sampler sampler;
};
struct clSetEventCallback_params
{
cl_event event;
int32_t command_exec_callback_type;
void (WINAPI* pfn_notify)(cl_event event, cl_int event_command_status, void *user_data);
void* user_data;
};
struct clSetKernelArg_params
{
cl_kernel kernel;
uint32_t arg_index;
SIZE_T arg_size;
const void* arg_value;
};
struct clSetMemObjectDestructorCallback_params
{
cl_mem memobj;
void (WINAPI* pfn_notify)(cl_mem memobj, void* user_data);
void* user_data;
};
struct clSetUserEventStatus_params
{
cl_event event;
int32_t execution_status;
};
struct clUnloadCompiler_params
{
};
struct clUnloadPlatformCompiler_params
{
cl_platform_id platform;
};
struct clWaitForEvents_params
{
uint32_t num_events;
const cl_event* event_list;
};
enum opencl_funcs
{
unix_clBuildProgram,
unix_clCompileProgram,
unix_clCreateBuffer,
unix_clCreateCommandQueue,
unix_clCreateContext,
unix_clCreateContextFromType,
unix_clCreateImage,
unix_clCreateImage2D,
unix_clCreateImage3D,
unix_clCreateKernel,
unix_clCreateKernelsInProgram,
unix_clCreateProgramWithBinary,
unix_clCreateProgramWithBuiltInKernels,
unix_clCreateProgramWithSource,
unix_clCreateSampler,
unix_clCreateSubBuffer,
unix_clCreateSubDevices,
unix_clCreateUserEvent,
unix_clEnqueueBarrier,
unix_clEnqueueBarrierWithWaitList,
unix_clEnqueueCopyBuffer,
unix_clEnqueueCopyBufferRect,
unix_clEnqueueCopyBufferToImage,
unix_clEnqueueCopyImage,
unix_clEnqueueCopyImageToBuffer,
unix_clEnqueueFillBuffer,
unix_clEnqueueFillImage,
unix_clEnqueueMapBuffer,
unix_clEnqueueMapImage,
unix_clEnqueueMarker,
unix_clEnqueueMarkerWithWaitList,
unix_clEnqueueMigrateMemObjects,
unix_clEnqueueNDRangeKernel,
unix_clEnqueueNativeKernel,
unix_clEnqueueReadBuffer,
unix_clEnqueueReadBufferRect,
unix_clEnqueueReadImage,
unix_clEnqueueTask,
unix_clEnqueueUnmapMemObject,
unix_clEnqueueWaitForEvents,
unix_clEnqueueWriteBuffer,
unix_clEnqueueWriteBufferRect,
unix_clEnqueueWriteImage,
unix_clFinish,
unix_clFlush,
unix_clGetCommandQueueInfo,
unix_clGetContextInfo,
unix_clGetDeviceIDs,
unix_clGetDeviceInfo,
unix_clGetEventInfo,
unix_clGetEventProfilingInfo,
unix_clGetImageInfo,
unix_clGetKernelArgInfo,
unix_clGetKernelInfo,
unix_clGetKernelWorkGroupInfo,
unix_clGetMemObjectInfo,
unix_clGetPlatformIDs,
unix_clGetPlatformInfo,
unix_clGetProgramBuildInfo,
unix_clGetProgramInfo,
unix_clGetSamplerInfo,
unix_clGetSupportedImageFormats,
unix_clLinkProgram,
unix_clReleaseCommandQueue,
unix_clReleaseContext,
unix_clReleaseDevice,
unix_clReleaseEvent,
unix_clReleaseKernel,
unix_clReleaseMemObject,
unix_clReleaseProgram,
unix_clReleaseSampler,
unix_clRetainCommandQueue,
unix_clRetainContext,
unix_clRetainDevice,
unix_clRetainEvent,
unix_clRetainKernel,
unix_clRetainMemObject,
unix_clRetainProgram,
unix_clRetainSampler,
unix_clSetEventCallback,
unix_clSetKernelArg,
unix_clSetMemObjectDestructorCallback,
unix_clSetUserEventStatus,
unix_clUnloadCompiler,
unix_clUnloadPlatformCompiler,
unix_clWaitForEvents,
};