| // GENERATED FILE - DO NOT EDIT. |
| // Generated by generate_entry_points.py using data from cl.xml. |
| // |
| // Copyright 2020 The ANGLE Project Authors. All rights reserved. |
| // Use of this source code is governed by a BSD-style license that can be |
| // found in the LICENSE file. |
| // |
| // entry_points_cl_autogen.cpp: |
| // Defines the CL entry points. |
| |
| #include "libGLESv2/entry_points_cl_autogen.h" |
| |
| #include "libANGLE/validationCL_autogen.h" |
| #include "libGLESv2/cl_stubs_autogen.h" |
| #include "libGLESv2/entry_points_cl_utils.h" |
| |
| namespace cl |
| { |
| |
| // CL 1.0 |
| cl_int CL_API_CALL clGetPlatformIDs(cl_uint num_entries, |
| cl_platform_id *platforms, |
| cl_uint *num_platforms) |
| { |
| CL_EVENT(GetPlatformIDs, |
| "num_entries = %u, platforms = 0x%016" PRIxPTR ", num_platforms = 0x%016" PRIxPTR "", |
| num_entries, (uintptr_t)platforms, (uintptr_t)num_platforms); |
| |
| Platform **platformsPacked = PackParam<Platform **>(platforms); |
| |
| ANGLE_CL_VALIDATE_ERROR(GetPlatformIDs, num_entries, platformsPacked, num_platforms); |
| |
| return GetPlatformIDs(num_entries, platformsPacked, num_platforms); |
| } |
| |
| 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_EVENT(GetPlatformInfo, |
| "platform = 0x%016" PRIxPTR |
| ", param_name = %u, param_value_size = %zu, param_value = 0x%016" PRIxPTR |
| ", param_value_size_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)platform, param_name, param_value_size, (uintptr_t)param_value, |
| (uintptr_t)param_value_size_ret); |
| |
| Platform *platformPacked = PackParam<Platform *>(platform); |
| PlatformInfo param_namePacked = PackParam<PlatformInfo>(param_name); |
| |
| ANGLE_CL_VALIDATE_ERROR(GetPlatformInfo, platformPacked, param_namePacked, param_value_size, |
| param_value, param_value_size_ret); |
| |
| return GetPlatformInfo(platformPacked, param_namePacked, param_value_size, param_value, |
| param_value_size_ret); |
| } |
| |
| 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_EVENT(GetDeviceIDs, |
| "platform = 0x%016" PRIxPTR |
| ", device_type = %lu, num_entries = %u, devices = 0x%016" PRIxPTR |
| ", num_devices = 0x%016" PRIxPTR "", |
| (uintptr_t)platform, device_type, num_entries, (uintptr_t)devices, |
| (uintptr_t)num_devices); |
| |
| Platform *platformPacked = PackParam<Platform *>(platform); |
| Device **devicesPacked = PackParam<Device **>(devices); |
| |
| ANGLE_CL_VALIDATE_ERROR(GetDeviceIDs, platformPacked, device_type, num_entries, devicesPacked, |
| num_devices); |
| |
| return GetDeviceIDs(platformPacked, device_type, num_entries, devicesPacked, num_devices); |
| } |
| |
| 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_EVENT(GetDeviceInfo, |
| "device = 0x%016" PRIxPTR |
| ", param_name = %u, param_value_size = %zu, param_value = 0x%016" PRIxPTR |
| ", param_value_size_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)device, param_name, param_value_size, (uintptr_t)param_value, |
| (uintptr_t)param_value_size_ret); |
| |
| Device *devicePacked = PackParam<Device *>(device); |
| DeviceInfo param_namePacked = PackParam<DeviceInfo>(param_name); |
| |
| ANGLE_CL_VALIDATE_ERROR(GetDeviceInfo, devicePacked, param_namePacked, param_value_size, |
| param_value, param_value_size_ret); |
| |
| return GetDeviceInfo(devicePacked, param_namePacked, param_value_size, param_value, |
| param_value_size_ret); |
| } |
| |
| 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 *errinfo, |
| const void *private_info, |
| size_t cb, |
| void *user_data), |
| void *user_data, |
| cl_int *errcode_ret) |
| { |
| CL_EVENT(CreateContext, |
| "properties = 0x%016" PRIxPTR ", num_devices = %u, devices = 0x%016" PRIxPTR |
| ", pfn_notify = 0x%016" PRIxPTR ", user_data = 0x%016" PRIxPTR |
| ", errcode_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)properties, num_devices, (uintptr_t)devices, (uintptr_t)pfn_notify, |
| (uintptr_t)user_data, (uintptr_t)errcode_ret); |
| |
| Device *const *devicesPacked = PackParam<Device *const *>(devices); |
| |
| ANGLE_CL_VALIDATE_POINTER(CreateContext, properties, num_devices, devicesPacked, pfn_notify, |
| user_data, errcode_ret); |
| |
| return CreateContext(properties, num_devices, devicesPacked, pfn_notify, user_data, |
| errcode_ret); |
| } |
| |
| cl_context CL_API_CALL |
| clCreateContextFromType(const cl_context_properties *properties, |
| cl_device_type device_type, |
| void(CL_CALLBACK *pfn_notify)(const char *errinfo, |
| const void *private_info, |
| size_t cb, |
| void *user_data), |
| void *user_data, |
| cl_int *errcode_ret) |
| { |
| CL_EVENT(CreateContextFromType, |
| "properties = 0x%016" PRIxPTR ", device_type = %lu, pfn_notify = 0x%016" PRIxPTR |
| ", user_data = 0x%016" PRIxPTR ", errcode_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)properties, device_type, (uintptr_t)pfn_notify, (uintptr_t)user_data, |
| (uintptr_t)errcode_ret); |
| |
| ANGLE_CL_VALIDATE_POINTER(CreateContextFromType, properties, device_type, pfn_notify, user_data, |
| errcode_ret); |
| |
| return CreateContextFromType(properties, device_type, pfn_notify, user_data, errcode_ret); |
| } |
| |
| cl_int CL_API_CALL clRetainContext(cl_context context) |
| { |
| CL_EVENT(RetainContext, "context = 0x%016" PRIxPTR "", (uintptr_t)context); |
| |
| Context *contextPacked = PackParam<Context *>(context); |
| |
| ANGLE_CL_VALIDATE_ERROR(RetainContext, contextPacked); |
| |
| return RetainContext(contextPacked); |
| } |
| |
| cl_int CL_API_CALL clReleaseContext(cl_context context) |
| { |
| CL_EVENT(ReleaseContext, "context = 0x%016" PRIxPTR "", (uintptr_t)context); |
| |
| Context *contextPacked = PackParam<Context *>(context); |
| |
| ANGLE_CL_VALIDATE_ERROR(ReleaseContext, contextPacked); |
| |
| return ReleaseContext(contextPacked); |
| } |
| |
| 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_EVENT(GetContextInfo, |
| "context = 0x%016" PRIxPTR |
| ", param_name = %u, param_value_size = %zu, param_value = 0x%016" PRIxPTR |
| ", param_value_size_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)context, param_name, param_value_size, (uintptr_t)param_value, |
| (uintptr_t)param_value_size_ret); |
| |
| Context *contextPacked = PackParam<Context *>(context); |
| ContextInfo param_namePacked = PackParam<ContextInfo>(param_name); |
| |
| ANGLE_CL_VALIDATE_ERROR(GetContextInfo, contextPacked, param_namePacked, param_value_size, |
| param_value, param_value_size_ret); |
| |
| return GetContextInfo(contextPacked, param_namePacked, param_value_size, param_value, |
| param_value_size_ret); |
| } |
| |
| cl_int CL_API_CALL clRetainCommandQueue(cl_command_queue command_queue) |
| { |
| CL_EVENT(RetainCommandQueue, "command_queue = 0x%016" PRIxPTR "", (uintptr_t)command_queue); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| |
| ANGLE_CL_VALIDATE_ERROR(RetainCommandQueue, command_queuePacked); |
| |
| return RetainCommandQueue(command_queuePacked); |
| } |
| |
| cl_int CL_API_CALL clReleaseCommandQueue(cl_command_queue command_queue) |
| { |
| CL_EVENT(ReleaseCommandQueue, "command_queue = 0x%016" PRIxPTR "", (uintptr_t)command_queue); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| |
| ANGLE_CL_VALIDATE_ERROR(ReleaseCommandQueue, command_queuePacked); |
| |
| return ReleaseCommandQueue(command_queuePacked); |
| } |
| |
| 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_EVENT(GetCommandQueueInfo, |
| "command_queue = 0x%016" PRIxPTR |
| ", param_name = %u, param_value_size = %zu, param_value = 0x%016" PRIxPTR |
| ", param_value_size_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, param_name, param_value_size, (uintptr_t)param_value, |
| (uintptr_t)param_value_size_ret); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| CommandQueueInfo param_namePacked = PackParam<CommandQueueInfo>(param_name); |
| |
| ANGLE_CL_VALIDATE_ERROR(GetCommandQueueInfo, command_queuePacked, param_namePacked, |
| param_value_size, param_value, param_value_size_ret); |
| |
| return GetCommandQueueInfo(command_queuePacked, param_namePacked, param_value_size, param_value, |
| param_value_size_ret); |
| } |
| |
| cl_mem CL_API_CALL clCreateBuffer(cl_context context, |
| cl_mem_flags flags, |
| size_t size, |
| void *host_ptr, |
| cl_int *errcode_ret) |
| { |
| CL_EVENT(CreateBuffer, |
| "context = 0x%016" PRIxPTR ", flags = %lu, size = %zu, host_ptr = 0x%016" PRIxPTR |
| ", errcode_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)context, flags, size, (uintptr_t)host_ptr, (uintptr_t)errcode_ret); |
| |
| Context *contextPacked = PackParam<Context *>(context); |
| |
| ANGLE_CL_VALIDATE_POINTER(CreateBuffer, contextPacked, flags, size, host_ptr, errcode_ret); |
| |
| return CreateBuffer(contextPacked, flags, size, host_ptr, errcode_ret); |
| } |
| |
| cl_int CL_API_CALL clRetainMemObject(cl_mem memobj) |
| { |
| CL_EVENT(RetainMemObject, "memobj = 0x%016" PRIxPTR "", (uintptr_t)memobj); |
| |
| Memory *memobjPacked = PackParam<Memory *>(memobj); |
| |
| ANGLE_CL_VALIDATE_ERROR(RetainMemObject, memobjPacked); |
| |
| return RetainMemObject(memobjPacked); |
| } |
| |
| cl_int CL_API_CALL clReleaseMemObject(cl_mem memobj) |
| { |
| CL_EVENT(ReleaseMemObject, "memobj = 0x%016" PRIxPTR "", (uintptr_t)memobj); |
| |
| Memory *memobjPacked = PackParam<Memory *>(memobj); |
| |
| ANGLE_CL_VALIDATE_ERROR(ReleaseMemObject, memobjPacked); |
| |
| return ReleaseMemObject(memobjPacked); |
| } |
| |
| 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_EVENT(GetSupportedImageFormats, |
| "context = 0x%016" PRIxPTR |
| ", flags = %lu, image_type = %u, num_entries = %u, image_formats = 0x%016" PRIxPTR |
| ", num_image_formats = 0x%016" PRIxPTR "", |
| (uintptr_t)context, flags, image_type, num_entries, (uintptr_t)image_formats, |
| (uintptr_t)num_image_formats); |
| |
| Context *contextPacked = PackParam<Context *>(context); |
| MemObjectType image_typePacked = PackParam<MemObjectType>(image_type); |
| |
| ANGLE_CL_VALIDATE_ERROR(GetSupportedImageFormats, contextPacked, flags, image_typePacked, |
| num_entries, image_formats, num_image_formats); |
| |
| return GetSupportedImageFormats(contextPacked, flags, image_typePacked, num_entries, |
| image_formats, num_image_formats); |
| } |
| |
| 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_EVENT(GetMemObjectInfo, |
| "memobj = 0x%016" PRIxPTR |
| ", param_name = %u, param_value_size = %zu, param_value = 0x%016" PRIxPTR |
| ", param_value_size_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)memobj, param_name, param_value_size, (uintptr_t)param_value, |
| (uintptr_t)param_value_size_ret); |
| |
| Memory *memobjPacked = PackParam<Memory *>(memobj); |
| MemInfo param_namePacked = PackParam<MemInfo>(param_name); |
| |
| ANGLE_CL_VALIDATE_ERROR(GetMemObjectInfo, memobjPacked, param_namePacked, param_value_size, |
| param_value, param_value_size_ret); |
| |
| return GetMemObjectInfo(memobjPacked, param_namePacked, param_value_size, param_value, |
| param_value_size_ret); |
| } |
| |
| 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_EVENT(GetImageInfo, |
| "image = 0x%016" PRIxPTR |
| ", param_name = %u, param_value_size = %zu, param_value = 0x%016" PRIxPTR |
| ", param_value_size_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)image, param_name, param_value_size, (uintptr_t)param_value, |
| (uintptr_t)param_value_size_ret); |
| |
| Memory *imagePacked = PackParam<Memory *>(image); |
| ImageInfo param_namePacked = PackParam<ImageInfo>(param_name); |
| |
| ANGLE_CL_VALIDATE_ERROR(GetImageInfo, imagePacked, param_namePacked, param_value_size, |
| param_value, param_value_size_ret); |
| |
| return GetImageInfo(imagePacked, param_namePacked, param_value_size, param_value, |
| param_value_size_ret); |
| } |
| |
| cl_int CL_API_CALL clRetainSampler(cl_sampler sampler) |
| { |
| CL_EVENT(RetainSampler, "sampler = 0x%016" PRIxPTR "", (uintptr_t)sampler); |
| |
| Sampler *samplerPacked = PackParam<Sampler *>(sampler); |
| |
| ANGLE_CL_VALIDATE_ERROR(RetainSampler, samplerPacked); |
| |
| return RetainSampler(samplerPacked); |
| } |
| |
| cl_int CL_API_CALL clReleaseSampler(cl_sampler sampler) |
| { |
| CL_EVENT(ReleaseSampler, "sampler = 0x%016" PRIxPTR "", (uintptr_t)sampler); |
| |
| Sampler *samplerPacked = PackParam<Sampler *>(sampler); |
| |
| ANGLE_CL_VALIDATE_ERROR(ReleaseSampler, samplerPacked); |
| |
| return ReleaseSampler(samplerPacked); |
| } |
| |
| 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_EVENT(GetSamplerInfo, |
| "sampler = 0x%016" PRIxPTR |
| ", param_name = %u, param_value_size = %zu, param_value = 0x%016" PRIxPTR |
| ", param_value_size_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)sampler, param_name, param_value_size, (uintptr_t)param_value, |
| (uintptr_t)param_value_size_ret); |
| |
| Sampler *samplerPacked = PackParam<Sampler *>(sampler); |
| SamplerInfo param_namePacked = PackParam<SamplerInfo>(param_name); |
| |
| ANGLE_CL_VALIDATE_ERROR(GetSamplerInfo, samplerPacked, param_namePacked, param_value_size, |
| param_value, param_value_size_ret); |
| |
| return GetSamplerInfo(samplerPacked, param_namePacked, param_value_size, param_value, |
| param_value_size_ret); |
| } |
| |
| cl_program CL_API_CALL clCreateProgramWithSource(cl_context context, |
| cl_uint count, |
| const char **strings, |
| const size_t *lengths, |
| cl_int *errcode_ret) |
| { |
| CL_EVENT(CreateProgramWithSource, |
| "context = 0x%016" PRIxPTR ", count = %u, strings = 0x%016" PRIxPTR |
| ", lengths = 0x%016" PRIxPTR ", errcode_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)context, count, (uintptr_t)strings, (uintptr_t)lengths, |
| (uintptr_t)errcode_ret); |
| |
| Context *contextPacked = PackParam<Context *>(context); |
| |
| ANGLE_CL_VALIDATE_POINTER(CreateProgramWithSource, contextPacked, count, strings, lengths, |
| errcode_ret); |
| |
| return CreateProgramWithSource(contextPacked, count, strings, lengths, errcode_ret); |
| } |
| |
| 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_EVENT(CreateProgramWithBinary, |
| "context = 0x%016" PRIxPTR ", num_devices = %u, device_list = 0x%016" PRIxPTR |
| ", lengths = 0x%016" PRIxPTR ", binaries = 0x%016" PRIxPTR |
| ", binary_status = 0x%016" PRIxPTR ", errcode_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)context, num_devices, (uintptr_t)device_list, (uintptr_t)lengths, |
| (uintptr_t)binaries, (uintptr_t)binary_status, (uintptr_t)errcode_ret); |
| |
| Context *contextPacked = PackParam<Context *>(context); |
| Device *const *device_listPacked = PackParam<Device *const *>(device_list); |
| |
| ANGLE_CL_VALIDATE_POINTER(CreateProgramWithBinary, contextPacked, num_devices, |
| device_listPacked, lengths, binaries, binary_status, errcode_ret); |
| |
| return CreateProgramWithBinary(contextPacked, num_devices, device_listPacked, lengths, binaries, |
| binary_status, errcode_ret); |
| } |
| |
| cl_int CL_API_CALL clRetainProgram(cl_program program) |
| { |
| CL_EVENT(RetainProgram, "program = 0x%016" PRIxPTR "", (uintptr_t)program); |
| |
| Program *programPacked = PackParam<Program *>(program); |
| |
| ANGLE_CL_VALIDATE_ERROR(RetainProgram, programPacked); |
| |
| return RetainProgram(programPacked); |
| } |
| |
| cl_int CL_API_CALL clReleaseProgram(cl_program program) |
| { |
| CL_EVENT(ReleaseProgram, "program = 0x%016" PRIxPTR "", (uintptr_t)program); |
| |
| Program *programPacked = PackParam<Program *>(program); |
| |
| ANGLE_CL_VALIDATE_ERROR(ReleaseProgram, programPacked); |
| |
| return ReleaseProgram(programPacked); |
| } |
| |
| 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 program, |
| void *user_data), |
| void *user_data) |
| { |
| CL_EVENT(BuildProgram, |
| "program = 0x%016" PRIxPTR ", num_devices = %u, device_list = 0x%016" PRIxPTR |
| ", options = 0x%016" PRIxPTR ", pfn_notify = 0x%016" PRIxPTR |
| ", user_data = 0x%016" PRIxPTR "", |
| (uintptr_t)program, num_devices, (uintptr_t)device_list, (uintptr_t)options, |
| (uintptr_t)pfn_notify, (uintptr_t)user_data); |
| |
| Program *programPacked = PackParam<Program *>(program); |
| Device *const *device_listPacked = PackParam<Device *const *>(device_list); |
| |
| ANGLE_CL_VALIDATE_ERROR(BuildProgram, programPacked, num_devices, device_listPacked, options, |
| pfn_notify, user_data); |
| |
| return BuildProgram(programPacked, num_devices, device_listPacked, options, pfn_notify, |
| user_data); |
| } |
| |
| 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_EVENT(GetProgramInfo, |
| "program = 0x%016" PRIxPTR |
| ", param_name = %u, param_value_size = %zu, param_value = 0x%016" PRIxPTR |
| ", param_value_size_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)program, param_name, param_value_size, (uintptr_t)param_value, |
| (uintptr_t)param_value_size_ret); |
| |
| Program *programPacked = PackParam<Program *>(program); |
| ProgramInfo param_namePacked = PackParam<ProgramInfo>(param_name); |
| |
| ANGLE_CL_VALIDATE_ERROR(GetProgramInfo, programPacked, param_namePacked, param_value_size, |
| param_value, param_value_size_ret); |
| |
| return GetProgramInfo(programPacked, param_namePacked, param_value_size, param_value, |
| param_value_size_ret); |
| } |
| |
| 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_EVENT(GetProgramBuildInfo, |
| "program = 0x%016" PRIxPTR ", device = 0x%016" PRIxPTR |
| ", param_name = %u, param_value_size = %zu, param_value = 0x%016" PRIxPTR |
| ", param_value_size_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)program, (uintptr_t)device, param_name, param_value_size, |
| (uintptr_t)param_value, (uintptr_t)param_value_size_ret); |
| |
| Program *programPacked = PackParam<Program *>(program); |
| Device *devicePacked = PackParam<Device *>(device); |
| ProgramBuildInfo param_namePacked = PackParam<ProgramBuildInfo>(param_name); |
| |
| ANGLE_CL_VALIDATE_ERROR(GetProgramBuildInfo, programPacked, devicePacked, param_namePacked, |
| param_value_size, param_value, param_value_size_ret); |
| |
| return GetProgramBuildInfo(programPacked, devicePacked, param_namePacked, param_value_size, |
| param_value, param_value_size_ret); |
| } |
| |
| cl_kernel CL_API_CALL clCreateKernel(cl_program program, |
| const char *kernel_name, |
| cl_int *errcode_ret) |
| { |
| CL_EVENT(CreateKernel, |
| "program = 0x%016" PRIxPTR ", kernel_name = 0x%016" PRIxPTR |
| ", errcode_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)program, (uintptr_t)kernel_name, (uintptr_t)errcode_ret); |
| |
| Program *programPacked = PackParam<Program *>(program); |
| |
| ANGLE_CL_VALIDATE_POINTER(CreateKernel, programPacked, kernel_name, errcode_ret); |
| |
| return CreateKernel(programPacked, kernel_name, errcode_ret); |
| } |
| |
| cl_int CL_API_CALL clCreateKernelsInProgram(cl_program program, |
| cl_uint num_kernels, |
| cl_kernel *kernels, |
| cl_uint *num_kernels_ret) |
| { |
| CL_EVENT(CreateKernelsInProgram, |
| "program = 0x%016" PRIxPTR ", num_kernels = %u, kernels = 0x%016" PRIxPTR |
| ", num_kernels_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)program, num_kernels, (uintptr_t)kernels, (uintptr_t)num_kernels_ret); |
| |
| Program *programPacked = PackParam<Program *>(program); |
| Kernel **kernelsPacked = PackParam<Kernel **>(kernels); |
| |
| ANGLE_CL_VALIDATE_ERROR(CreateKernelsInProgram, programPacked, num_kernels, kernelsPacked, |
| num_kernels_ret); |
| |
| return CreateKernelsInProgram(programPacked, num_kernels, kernelsPacked, num_kernels_ret); |
| } |
| |
| cl_int CL_API_CALL clRetainKernel(cl_kernel kernel) |
| { |
| CL_EVENT(RetainKernel, "kernel = 0x%016" PRIxPTR "", (uintptr_t)kernel); |
| |
| Kernel *kernelPacked = PackParam<Kernel *>(kernel); |
| |
| ANGLE_CL_VALIDATE_ERROR(RetainKernel, kernelPacked); |
| |
| return RetainKernel(kernelPacked); |
| } |
| |
| cl_int CL_API_CALL clReleaseKernel(cl_kernel kernel) |
| { |
| CL_EVENT(ReleaseKernel, "kernel = 0x%016" PRIxPTR "", (uintptr_t)kernel); |
| |
| Kernel *kernelPacked = PackParam<Kernel *>(kernel); |
| |
| ANGLE_CL_VALIDATE_ERROR(ReleaseKernel, kernelPacked); |
| |
| return ReleaseKernel(kernelPacked); |
| } |
| |
| cl_int CL_API_CALL clSetKernelArg(cl_kernel kernel, |
| cl_uint arg_index, |
| size_t arg_size, |
| const void *arg_value) |
| { |
| CL_EVENT(SetKernelArg, |
| "kernel = 0x%016" PRIxPTR |
| ", arg_index = %u, arg_size = %zu, arg_value = 0x%016" PRIxPTR "", |
| (uintptr_t)kernel, arg_index, arg_size, (uintptr_t)arg_value); |
| |
| Kernel *kernelPacked = PackParam<Kernel *>(kernel); |
| |
| ANGLE_CL_VALIDATE_ERROR(SetKernelArg, kernelPacked, arg_index, arg_size, arg_value); |
| |
| return SetKernelArg(kernelPacked, arg_index, arg_size, arg_value); |
| } |
| |
| 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_EVENT(GetKernelInfo, |
| "kernel = 0x%016" PRIxPTR |
| ", param_name = %u, param_value_size = %zu, param_value = 0x%016" PRIxPTR |
| ", param_value_size_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)kernel, param_name, param_value_size, (uintptr_t)param_value, |
| (uintptr_t)param_value_size_ret); |
| |
| Kernel *kernelPacked = PackParam<Kernel *>(kernel); |
| KernelInfo param_namePacked = PackParam<KernelInfo>(param_name); |
| |
| ANGLE_CL_VALIDATE_ERROR(GetKernelInfo, kernelPacked, param_namePacked, param_value_size, |
| param_value, param_value_size_ret); |
| |
| return GetKernelInfo(kernelPacked, param_namePacked, param_value_size, param_value, |
| param_value_size_ret); |
| } |
| |
| 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_EVENT(GetKernelWorkGroupInfo, |
| "kernel = 0x%016" PRIxPTR ", device = 0x%016" PRIxPTR |
| ", param_name = %u, param_value_size = %zu, param_value = 0x%016" PRIxPTR |
| ", param_value_size_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)kernel, (uintptr_t)device, param_name, param_value_size, |
| (uintptr_t)param_value, (uintptr_t)param_value_size_ret); |
| |
| Kernel *kernelPacked = PackParam<Kernel *>(kernel); |
| Device *devicePacked = PackParam<Device *>(device); |
| KernelWorkGroupInfo param_namePacked = PackParam<KernelWorkGroupInfo>(param_name); |
| |
| ANGLE_CL_VALIDATE_ERROR(GetKernelWorkGroupInfo, kernelPacked, devicePacked, param_namePacked, |
| param_value_size, param_value, param_value_size_ret); |
| |
| return GetKernelWorkGroupInfo(kernelPacked, devicePacked, param_namePacked, param_value_size, |
| param_value, param_value_size_ret); |
| } |
| |
| cl_int CL_API_CALL clWaitForEvents(cl_uint num_events, const cl_event *event_list) |
| { |
| CL_EVENT(WaitForEvents, "num_events = %u, event_list = 0x%016" PRIxPTR "", num_events, |
| (uintptr_t)event_list); |
| |
| Event *const *event_listPacked = PackParam<Event *const *>(event_list); |
| |
| ANGLE_CL_VALIDATE_ERROR(WaitForEvents, num_events, event_listPacked); |
| |
| return WaitForEvents(num_events, event_listPacked); |
| } |
| |
| 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_EVENT(GetEventInfo, |
| "event = 0x%016" PRIxPTR |
| ", param_name = %u, param_value_size = %zu, param_value = 0x%016" PRIxPTR |
| ", param_value_size_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)event, param_name, param_value_size, (uintptr_t)param_value, |
| (uintptr_t)param_value_size_ret); |
| |
| Event *eventPacked = PackParam<Event *>(event); |
| EventInfo param_namePacked = PackParam<EventInfo>(param_name); |
| |
| ANGLE_CL_VALIDATE_ERROR(GetEventInfo, eventPacked, param_namePacked, param_value_size, |
| param_value, param_value_size_ret); |
| |
| return GetEventInfo(eventPacked, param_namePacked, param_value_size, param_value, |
| param_value_size_ret); |
| } |
| |
| cl_int CL_API_CALL clRetainEvent(cl_event event) |
| { |
| CL_EVENT(RetainEvent, "event = 0x%016" PRIxPTR "", (uintptr_t)event); |
| |
| Event *eventPacked = PackParam<Event *>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(RetainEvent, eventPacked); |
| |
| return RetainEvent(eventPacked); |
| } |
| |
| cl_int CL_API_CALL clReleaseEvent(cl_event event) |
| { |
| CL_EVENT(ReleaseEvent, "event = 0x%016" PRIxPTR "", (uintptr_t)event); |
| |
| Event *eventPacked = PackParam<Event *>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(ReleaseEvent, eventPacked); |
| |
| return ReleaseEvent(eventPacked); |
| } |
| |
| 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_EVENT(GetEventProfilingInfo, |
| "event = 0x%016" PRIxPTR |
| ", param_name = %u, param_value_size = %zu, param_value = 0x%016" PRIxPTR |
| ", param_value_size_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)event, param_name, param_value_size, (uintptr_t)param_value, |
| (uintptr_t)param_value_size_ret); |
| |
| Event *eventPacked = PackParam<Event *>(event); |
| ProfilingInfo param_namePacked = PackParam<ProfilingInfo>(param_name); |
| |
| ANGLE_CL_VALIDATE_ERROR(GetEventProfilingInfo, eventPacked, param_namePacked, param_value_size, |
| param_value, param_value_size_ret); |
| |
| return GetEventProfilingInfo(eventPacked, param_namePacked, param_value_size, param_value, |
| param_value_size_ret); |
| } |
| |
| cl_int CL_API_CALL clFlush(cl_command_queue command_queue) |
| { |
| CL_EVENT(Flush, "command_queue = 0x%016" PRIxPTR "", (uintptr_t)command_queue); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| |
| ANGLE_CL_VALIDATE_ERROR(Flush, command_queuePacked); |
| |
| return Flush(command_queuePacked); |
| } |
| |
| cl_int CL_API_CALL clFinish(cl_command_queue command_queue) |
| { |
| CL_EVENT(Finish, "command_queue = 0x%016" PRIxPTR "", (uintptr_t)command_queue); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| |
| ANGLE_CL_VALIDATE_ERROR(Finish, command_queuePacked); |
| |
| return Finish(command_queuePacked); |
| } |
| |
| cl_int CL_API_CALL clEnqueueReadBuffer(cl_command_queue command_queue, |
| cl_mem buffer, |
| cl_bool blocking_read, |
| size_t offset, |
| size_t size, |
| void *ptr, |
| cl_uint num_events_in_wait_list, |
| const cl_event *event_wait_list, |
| cl_event *event) |
| { |
| CL_EVENT(EnqueueReadBuffer, |
| "command_queue = 0x%016" PRIxPTR ", buffer = 0x%016" PRIxPTR |
| ", blocking_read = %u, offset = %zu, size = %zu, ptr = 0x%016" PRIxPTR |
| ", num_events_in_wait_list = %u, event_wait_list = 0x%016" PRIxPTR |
| ", event = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, (uintptr_t)buffer, blocking_read, offset, size, |
| (uintptr_t)ptr, num_events_in_wait_list, (uintptr_t)event_wait_list, (uintptr_t)event); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Memory *bufferPacked = PackParam<Memory *>(buffer); |
| Event *const *event_wait_listPacked = PackParam<Event *const *>(event_wait_list); |
| Event **eventPacked = PackParam<Event **>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(EnqueueReadBuffer, command_queuePacked, bufferPacked, blocking_read, |
| offset, size, ptr, num_events_in_wait_list, event_wait_listPacked, |
| eventPacked); |
| |
| return EnqueueReadBuffer(command_queuePacked, bufferPacked, blocking_read, offset, size, ptr, |
| num_events_in_wait_list, event_wait_listPacked, eventPacked); |
| } |
| |
| cl_int CL_API_CALL clEnqueueWriteBuffer(cl_command_queue command_queue, |
| cl_mem buffer, |
| cl_bool blocking_write, |
| size_t offset, |
| size_t size, |
| const void *ptr, |
| cl_uint num_events_in_wait_list, |
| const cl_event *event_wait_list, |
| cl_event *event) |
| { |
| CL_EVENT(EnqueueWriteBuffer, |
| "command_queue = 0x%016" PRIxPTR ", buffer = 0x%016" PRIxPTR |
| ", blocking_write = %u, offset = %zu, size = %zu, ptr = 0x%016" PRIxPTR |
| ", num_events_in_wait_list = %u, event_wait_list = 0x%016" PRIxPTR |
| ", event = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, (uintptr_t)buffer, blocking_write, offset, size, |
| (uintptr_t)ptr, num_events_in_wait_list, (uintptr_t)event_wait_list, (uintptr_t)event); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Memory *bufferPacked = PackParam<Memory *>(buffer); |
| Event *const *event_wait_listPacked = PackParam<Event *const *>(event_wait_list); |
| Event **eventPacked = PackParam<Event **>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(EnqueueWriteBuffer, command_queuePacked, bufferPacked, blocking_write, |
| offset, size, ptr, num_events_in_wait_list, event_wait_listPacked, |
| eventPacked); |
| |
| return EnqueueWriteBuffer(command_queuePacked, bufferPacked, blocking_write, offset, size, ptr, |
| num_events_in_wait_list, event_wait_listPacked, eventPacked); |
| } |
| |
| 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 size, |
| cl_uint num_events_in_wait_list, |
| const cl_event *event_wait_list, |
| cl_event *event) |
| { |
| CL_EVENT(EnqueueCopyBuffer, |
| "command_queue = 0x%016" PRIxPTR ", src_buffer = 0x%016" PRIxPTR |
| ", dst_buffer = 0x%016" PRIxPTR |
| ", src_offset = %zu, dst_offset = %zu, size = %zu, num_events_in_wait_list = %u, " |
| "event_wait_list = 0x%016" PRIxPTR ", event = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, (uintptr_t)src_buffer, (uintptr_t)dst_buffer, src_offset, |
| dst_offset, size, num_events_in_wait_list, (uintptr_t)event_wait_list, |
| (uintptr_t)event); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Memory *src_bufferPacked = PackParam<Memory *>(src_buffer); |
| Memory *dst_bufferPacked = PackParam<Memory *>(dst_buffer); |
| Event *const *event_wait_listPacked = PackParam<Event *const *>(event_wait_list); |
| Event **eventPacked = PackParam<Event **>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(EnqueueCopyBuffer, command_queuePacked, src_bufferPacked, |
| dst_bufferPacked, src_offset, dst_offset, size, num_events_in_wait_list, |
| event_wait_listPacked, eventPacked); |
| |
| return EnqueueCopyBuffer(command_queuePacked, src_bufferPacked, dst_bufferPacked, src_offset, |
| dst_offset, size, num_events_in_wait_list, event_wait_listPacked, |
| eventPacked); |
| } |
| |
| 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_EVENT(EnqueueReadImage, |
| "command_queue = 0x%016" PRIxPTR ", image = 0x%016" PRIxPTR |
| ", blocking_read = %u, origin = 0x%016" PRIxPTR ", region = 0x%016" PRIxPTR |
| ", row_pitch = %zu, slice_pitch = %zu, ptr = 0x%016" PRIxPTR |
| ", num_events_in_wait_list = %u, event_wait_list = 0x%016" PRIxPTR |
| ", event = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, (uintptr_t)image, blocking_read, (uintptr_t)origin, |
| (uintptr_t)region, row_pitch, slice_pitch, (uintptr_t)ptr, num_events_in_wait_list, |
| (uintptr_t)event_wait_list, (uintptr_t)event); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Memory *imagePacked = PackParam<Memory *>(image); |
| Event *const *event_wait_listPacked = PackParam<Event *const *>(event_wait_list); |
| Event **eventPacked = PackParam<Event **>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(EnqueueReadImage, command_queuePacked, imagePacked, blocking_read, |
| origin, region, row_pitch, slice_pitch, ptr, num_events_in_wait_list, |
| event_wait_listPacked, eventPacked); |
| |
| return EnqueueReadImage(command_queuePacked, imagePacked, blocking_read, origin, region, |
| row_pitch, slice_pitch, ptr, num_events_in_wait_list, |
| event_wait_listPacked, eventPacked); |
| } |
| |
| 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_EVENT(EnqueueWriteImage, |
| "command_queue = 0x%016" PRIxPTR ", image = 0x%016" PRIxPTR |
| ", blocking_write = %u, origin = 0x%016" PRIxPTR ", region = 0x%016" PRIxPTR |
| ", input_row_pitch = %zu, input_slice_pitch = %zu, ptr = 0x%016" PRIxPTR |
| ", num_events_in_wait_list = %u, event_wait_list = 0x%016" PRIxPTR |
| ", event = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, (uintptr_t)image, blocking_write, (uintptr_t)origin, |
| (uintptr_t)region, input_row_pitch, input_slice_pitch, (uintptr_t)ptr, |
| num_events_in_wait_list, (uintptr_t)event_wait_list, (uintptr_t)event); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Memory *imagePacked = PackParam<Memory *>(image); |
| Event *const *event_wait_listPacked = PackParam<Event *const *>(event_wait_list); |
| Event **eventPacked = PackParam<Event **>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(EnqueueWriteImage, command_queuePacked, imagePacked, blocking_write, |
| origin, region, input_row_pitch, input_slice_pitch, ptr, |
| num_events_in_wait_list, event_wait_listPacked, eventPacked); |
| |
| return EnqueueWriteImage(command_queuePacked, imagePacked, blocking_write, origin, region, |
| input_row_pitch, input_slice_pitch, ptr, num_events_in_wait_list, |
| event_wait_listPacked, eventPacked); |
| } |
| |
| 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_EVENT(EnqueueCopyImage, |
| "command_queue = 0x%016" PRIxPTR ", src_image = 0x%016" PRIxPTR |
| ", dst_image = 0x%016" PRIxPTR ", src_origin = 0x%016" PRIxPTR |
| ", dst_origin = 0x%016" PRIxPTR ", region = 0x%016" PRIxPTR |
| ", num_events_in_wait_list = %u, event_wait_list = 0x%016" PRIxPTR |
| ", event = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, (uintptr_t)src_image, (uintptr_t)dst_image, |
| (uintptr_t)src_origin, (uintptr_t)dst_origin, (uintptr_t)region, |
| num_events_in_wait_list, (uintptr_t)event_wait_list, (uintptr_t)event); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Memory *src_imagePacked = PackParam<Memory *>(src_image); |
| Memory *dst_imagePacked = PackParam<Memory *>(dst_image); |
| Event *const *event_wait_listPacked = PackParam<Event *const *>(event_wait_list); |
| Event **eventPacked = PackParam<Event **>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(EnqueueCopyImage, command_queuePacked, src_imagePacked, dst_imagePacked, |
| src_origin, dst_origin, region, num_events_in_wait_list, |
| event_wait_listPacked, eventPacked); |
| |
| return EnqueueCopyImage(command_queuePacked, src_imagePacked, dst_imagePacked, src_origin, |
| dst_origin, region, num_events_in_wait_list, event_wait_listPacked, |
| eventPacked); |
| } |
| |
| 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_EVENT(EnqueueCopyImageToBuffer, |
| "command_queue = 0x%016" PRIxPTR ", src_image = 0x%016" PRIxPTR |
| ", dst_buffer = 0x%016" PRIxPTR ", src_origin = 0x%016" PRIxPTR |
| ", region = 0x%016" PRIxPTR |
| ", dst_offset = %zu, num_events_in_wait_list = %u, event_wait_list = 0x%016" PRIxPTR |
| ", event = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, (uintptr_t)src_image, (uintptr_t)dst_buffer, |
| (uintptr_t)src_origin, (uintptr_t)region, dst_offset, num_events_in_wait_list, |
| (uintptr_t)event_wait_list, (uintptr_t)event); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Memory *src_imagePacked = PackParam<Memory *>(src_image); |
| Memory *dst_bufferPacked = PackParam<Memory *>(dst_buffer); |
| Event *const *event_wait_listPacked = PackParam<Event *const *>(event_wait_list); |
| Event **eventPacked = PackParam<Event **>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(EnqueueCopyImageToBuffer, command_queuePacked, src_imagePacked, |
| dst_bufferPacked, src_origin, region, dst_offset, |
| num_events_in_wait_list, event_wait_listPacked, eventPacked); |
| |
| return EnqueueCopyImageToBuffer(command_queuePacked, src_imagePacked, dst_bufferPacked, |
| src_origin, region, dst_offset, num_events_in_wait_list, |
| event_wait_listPacked, eventPacked); |
| } |
| |
| 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_EVENT(EnqueueCopyBufferToImage, |
| "command_queue = 0x%016" PRIxPTR ", src_buffer = 0x%016" PRIxPTR |
| ", dst_image = 0x%016" PRIxPTR ", src_offset = %zu, dst_origin = 0x%016" PRIxPTR |
| ", region = 0x%016" PRIxPTR |
| ", num_events_in_wait_list = %u, event_wait_list = 0x%016" PRIxPTR |
| ", event = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, (uintptr_t)src_buffer, (uintptr_t)dst_image, src_offset, |
| (uintptr_t)dst_origin, (uintptr_t)region, num_events_in_wait_list, |
| (uintptr_t)event_wait_list, (uintptr_t)event); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Memory *src_bufferPacked = PackParam<Memory *>(src_buffer); |
| Memory *dst_imagePacked = PackParam<Memory *>(dst_image); |
| Event *const *event_wait_listPacked = PackParam<Event *const *>(event_wait_list); |
| Event **eventPacked = PackParam<Event **>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(EnqueueCopyBufferToImage, command_queuePacked, src_bufferPacked, |
| dst_imagePacked, src_offset, dst_origin, region, |
| num_events_in_wait_list, event_wait_listPacked, eventPacked); |
| |
| return EnqueueCopyBufferToImage(command_queuePacked, src_bufferPacked, dst_imagePacked, |
| src_offset, dst_origin, region, num_events_in_wait_list, |
| event_wait_listPacked, eventPacked); |
| } |
| |
| 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 size, |
| cl_uint num_events_in_wait_list, |
| const cl_event *event_wait_list, |
| cl_event *event, |
| cl_int *errcode_ret) |
| { |
| CL_EVENT(EnqueueMapBuffer, |
| "command_queue = 0x%016" PRIxPTR ", buffer = 0x%016" PRIxPTR |
| ", blocking_map = %u, map_flags = %lu, offset = %zu, size = %zu, " |
| "num_events_in_wait_list = %u, event_wait_list = 0x%016" PRIxPTR |
| ", event = 0x%016" PRIxPTR ", errcode_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, (uintptr_t)buffer, blocking_map, map_flags, offset, size, |
| num_events_in_wait_list, (uintptr_t)event_wait_list, (uintptr_t)event, |
| (uintptr_t)errcode_ret); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Memory *bufferPacked = PackParam<Memory *>(buffer); |
| Event *const *event_wait_listPacked = PackParam<Event *const *>(event_wait_list); |
| Event **eventPacked = PackParam<Event **>(event); |
| |
| ANGLE_CL_VALIDATE_POINTER(EnqueueMapBuffer, command_queuePacked, bufferPacked, blocking_map, |
| map_flags, offset, size, num_events_in_wait_list, |
| event_wait_listPacked, eventPacked, errcode_ret); |
| |
| return EnqueueMapBuffer(command_queuePacked, bufferPacked, blocking_map, map_flags, offset, |
| size, num_events_in_wait_list, event_wait_listPacked, eventPacked, |
| errcode_ret); |
| } |
| |
| 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_EVENT(EnqueueMapImage, |
| "command_queue = 0x%016" PRIxPTR ", image = 0x%016" PRIxPTR |
| ", blocking_map = %u, map_flags = %lu, origin = 0x%016" PRIxPTR |
| ", region = 0x%016" PRIxPTR ", image_row_pitch = 0x%016" PRIxPTR |
| ", image_slice_pitch = 0x%016" PRIxPTR |
| ", num_events_in_wait_list = %u, event_wait_list = 0x%016" PRIxPTR |
| ", event = 0x%016" PRIxPTR ", errcode_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, (uintptr_t)image, blocking_map, map_flags, (uintptr_t)origin, |
| (uintptr_t)region, (uintptr_t)image_row_pitch, (uintptr_t)image_slice_pitch, |
| num_events_in_wait_list, (uintptr_t)event_wait_list, (uintptr_t)event, |
| (uintptr_t)errcode_ret); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Memory *imagePacked = PackParam<Memory *>(image); |
| Event *const *event_wait_listPacked = PackParam<Event *const *>(event_wait_list); |
| Event **eventPacked = PackParam<Event **>(event); |
| |
| ANGLE_CL_VALIDATE_POINTER(EnqueueMapImage, command_queuePacked, imagePacked, blocking_map, |
| map_flags, origin, region, image_row_pitch, image_slice_pitch, |
| num_events_in_wait_list, event_wait_listPacked, eventPacked, |
| errcode_ret); |
| |
| return EnqueueMapImage(command_queuePacked, imagePacked, blocking_map, map_flags, origin, |
| region, image_row_pitch, image_slice_pitch, num_events_in_wait_list, |
| event_wait_listPacked, eventPacked, errcode_ret); |
| } |
| |
| 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_EVENT(EnqueueUnmapMemObject, |
| "command_queue = 0x%016" PRIxPTR ", memobj = 0x%016" PRIxPTR |
| ", mapped_ptr = 0x%016" PRIxPTR |
| ", num_events_in_wait_list = %u, event_wait_list = 0x%016" PRIxPTR |
| ", event = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, (uintptr_t)memobj, (uintptr_t)mapped_ptr, |
| num_events_in_wait_list, (uintptr_t)event_wait_list, (uintptr_t)event); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Memory *memobjPacked = PackParam<Memory *>(memobj); |
| Event *const *event_wait_listPacked = PackParam<Event *const *>(event_wait_list); |
| Event **eventPacked = PackParam<Event **>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(EnqueueUnmapMemObject, command_queuePacked, memobjPacked, mapped_ptr, |
| num_events_in_wait_list, event_wait_listPacked, eventPacked); |
| |
| return EnqueueUnmapMemObject(command_queuePacked, memobjPacked, mapped_ptr, |
| num_events_in_wait_list, event_wait_listPacked, eventPacked); |
| } |
| |
| 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_EVENT(EnqueueNDRangeKernel, |
| "command_queue = 0x%016" PRIxPTR ", kernel = 0x%016" PRIxPTR |
| ", work_dim = %u, global_work_offset = 0x%016" PRIxPTR |
| ", global_work_size = 0x%016" PRIxPTR ", local_work_size = 0x%016" PRIxPTR |
| ", num_events_in_wait_list = %u, event_wait_list = 0x%016" PRIxPTR |
| ", event = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, (uintptr_t)kernel, work_dim, (uintptr_t)global_work_offset, |
| (uintptr_t)global_work_size, (uintptr_t)local_work_size, num_events_in_wait_list, |
| (uintptr_t)event_wait_list, (uintptr_t)event); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Kernel *kernelPacked = PackParam<Kernel *>(kernel); |
| Event *const *event_wait_listPacked = PackParam<Event *const *>(event_wait_list); |
| Event **eventPacked = PackParam<Event **>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(EnqueueNDRangeKernel, command_queuePacked, kernelPacked, work_dim, |
| global_work_offset, global_work_size, local_work_size, |
| num_events_in_wait_list, event_wait_listPacked, eventPacked); |
| |
| return EnqueueNDRangeKernel(command_queuePacked, kernelPacked, work_dim, global_work_offset, |
| global_work_size, local_work_size, num_events_in_wait_list, |
| event_wait_listPacked, eventPacked); |
| } |
| |
| 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_EVENT(EnqueueNativeKernel, |
| "command_queue = 0x%016" PRIxPTR ", user_func = 0x%016" PRIxPTR |
| ", args = 0x%016" PRIxPTR |
| ", cb_args = %zu, num_mem_objects = %u, mem_list = 0x%016" PRIxPTR |
| ", args_mem_loc = 0x%016" PRIxPTR |
| ", num_events_in_wait_list = %u, event_wait_list = 0x%016" PRIxPTR |
| ", event = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, (uintptr_t)user_func, (uintptr_t)args, cb_args, |
| num_mem_objects, (uintptr_t)mem_list, (uintptr_t)args_mem_loc, num_events_in_wait_list, |
| (uintptr_t)event_wait_list, (uintptr_t)event); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Memory *const *mem_listPacked = PackParam<Memory *const *>(mem_list); |
| Event *const *event_wait_listPacked = PackParam<Event *const *>(event_wait_list); |
| Event **eventPacked = PackParam<Event **>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(EnqueueNativeKernel, command_queuePacked, user_func, args, cb_args, |
| num_mem_objects, mem_listPacked, args_mem_loc, num_events_in_wait_list, |
| event_wait_listPacked, eventPacked); |
| |
| return EnqueueNativeKernel(command_queuePacked, user_func, args, cb_args, num_mem_objects, |
| mem_listPacked, args_mem_loc, num_events_in_wait_list, |
| event_wait_listPacked, eventPacked); |
| } |
| |
| 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_EVENT(SetCommandQueueProperty, |
| "command_queue = 0x%016" PRIxPTR |
| ", properties = %lu, enable = %u, old_properties = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, properties, enable, (uintptr_t)old_properties); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| |
| ANGLE_CL_VALIDATE_ERROR(SetCommandQueueProperty, command_queuePacked, properties, enable, |
| old_properties); |
| |
| return SetCommandQueueProperty(command_queuePacked, properties, enable, old_properties); |
| } |
| |
| 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_EVENT( |
| CreateImage2D, |
| "context = 0x%016" PRIxPTR ", flags = %lu, image_format = 0x%016" PRIxPTR |
| ", image_width = %zu, image_height = %zu, image_row_pitch = %zu, host_ptr = 0x%016" PRIxPTR |
| ", errcode_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)context, flags, (uintptr_t)image_format, image_width, image_height, |
| image_row_pitch, (uintptr_t)host_ptr, (uintptr_t)errcode_ret); |
| |
| Context *contextPacked = PackParam<Context *>(context); |
| |
| ANGLE_CL_VALIDATE_POINTER(CreateImage2D, contextPacked, flags, image_format, image_width, |
| image_height, image_row_pitch, host_ptr, errcode_ret); |
| |
| return CreateImage2D(contextPacked, flags, image_format, image_width, image_height, |
| image_row_pitch, host_ptr, errcode_ret); |
| } |
| |
| 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_EVENT( |
| CreateImage3D, |
| "context = 0x%016" PRIxPTR ", flags = %lu, image_format = 0x%016" PRIxPTR |
| ", image_width = %zu, image_height = %zu, image_depth = %zu, image_row_pitch = %zu, " |
| "image_slice_pitch = %zu, host_ptr = 0x%016" PRIxPTR ", errcode_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)context, flags, (uintptr_t)image_format, image_width, image_height, image_depth, |
| image_row_pitch, image_slice_pitch, (uintptr_t)host_ptr, (uintptr_t)errcode_ret); |
| |
| Context *contextPacked = PackParam<Context *>(context); |
| |
| ANGLE_CL_VALIDATE_POINTER(CreateImage3D, contextPacked, flags, image_format, image_width, |
| image_height, image_depth, image_row_pitch, image_slice_pitch, |
| host_ptr, errcode_ret); |
| |
| return CreateImage3D(contextPacked, flags, image_format, image_width, image_height, image_depth, |
| image_row_pitch, image_slice_pitch, host_ptr, errcode_ret); |
| } |
| |
| cl_int CL_API_CALL clEnqueueMarker(cl_command_queue command_queue, cl_event *event) |
| { |
| CL_EVENT(EnqueueMarker, "command_queue = 0x%016" PRIxPTR ", event = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, (uintptr_t)event); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Event **eventPacked = PackParam<Event **>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(EnqueueMarker, command_queuePacked, eventPacked); |
| |
| return EnqueueMarker(command_queuePacked, eventPacked); |
| } |
| |
| cl_int CL_API_CALL clEnqueueWaitForEvents(cl_command_queue command_queue, |
| cl_uint num_events, |
| const cl_event *event_list) |
| { |
| CL_EVENT(EnqueueWaitForEvents, |
| "command_queue = 0x%016" PRIxPTR ", num_events = %u, event_list = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, num_events, (uintptr_t)event_list); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Event *const *event_listPacked = PackParam<Event *const *>(event_list); |
| |
| ANGLE_CL_VALIDATE_ERROR(EnqueueWaitForEvents, command_queuePacked, num_events, |
| event_listPacked); |
| |
| return EnqueueWaitForEvents(command_queuePacked, num_events, event_listPacked); |
| } |
| |
| cl_int CL_API_CALL clEnqueueBarrier(cl_command_queue command_queue) |
| { |
| CL_EVENT(EnqueueBarrier, "command_queue = 0x%016" PRIxPTR "", (uintptr_t)command_queue); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| |
| ANGLE_CL_VALIDATE_ERROR(EnqueueBarrier, command_queuePacked); |
| |
| return EnqueueBarrier(command_queuePacked); |
| } |
| |
| cl_int CL_API_CALL clUnloadCompiler() |
| { |
| CL_EVENT(UnloadCompiler, ""); |
| |
| ANGLE_CL_VALIDATE_ERROR(UnloadCompiler); |
| |
| return UnloadCompiler(); |
| } |
| |
| void *CL_API_CALL clGetExtensionFunctionAddress(const char *func_name) |
| { |
| CL_EVENT(GetExtensionFunctionAddress, "func_name = 0x%016" PRIxPTR "", (uintptr_t)func_name); |
| |
| ANGLE_CL_VALIDATE_POINTER(GetExtensionFunctionAddress, func_name); |
| |
| return GetExtensionFunctionAddress(func_name); |
| } |
| |
| cl_command_queue CL_API_CALL clCreateCommandQueue(cl_context context, |
| cl_device_id device, |
| cl_command_queue_properties properties, |
| cl_int *errcode_ret) |
| { |
| CL_EVENT(CreateCommandQueue, |
| "context = 0x%016" PRIxPTR ", device = 0x%016" PRIxPTR |
| ", properties = %lu, errcode_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)context, (uintptr_t)device, properties, (uintptr_t)errcode_ret); |
| |
| Context *contextPacked = PackParam<Context *>(context); |
| Device *devicePacked = PackParam<Device *>(device); |
| |
| ANGLE_CL_VALIDATE_POINTER(CreateCommandQueue, contextPacked, devicePacked, properties, |
| errcode_ret); |
| |
| return CreateCommandQueue(contextPacked, devicePacked, properties, errcode_ret); |
| } |
| |
| 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_EVENT(CreateSampler, |
| "context = 0x%016" PRIxPTR |
| ", normalized_coords = %u, addressing_mode = %u, filter_mode = %u, errcode_ret = " |
| "0x%016" PRIxPTR "", |
| (uintptr_t)context, normalized_coords, addressing_mode, filter_mode, |
| (uintptr_t)errcode_ret); |
| |
| Context *contextPacked = PackParam<Context *>(context); |
| AddressingMode addressing_modePacked = PackParam<AddressingMode>(addressing_mode); |
| FilterMode filter_modePacked = PackParam<FilterMode>(filter_mode); |
| |
| ANGLE_CL_VALIDATE_POINTER(CreateSampler, contextPacked, normalized_coords, |
| addressing_modePacked, filter_modePacked, errcode_ret); |
| |
| return CreateSampler(contextPacked, normalized_coords, addressing_modePacked, filter_modePacked, |
| errcode_ret); |
| } |
| |
| 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_EVENT(EnqueueTask, |
| "command_queue = 0x%016" PRIxPTR ", kernel = 0x%016" PRIxPTR |
| ", num_events_in_wait_list = %u, event_wait_list = 0x%016" PRIxPTR |
| ", event = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, (uintptr_t)kernel, num_events_in_wait_list, |
| (uintptr_t)event_wait_list, (uintptr_t)event); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Kernel *kernelPacked = PackParam<Kernel *>(kernel); |
| Event *const *event_wait_listPacked = PackParam<Event *const *>(event_wait_list); |
| Event **eventPacked = PackParam<Event **>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(EnqueueTask, command_queuePacked, kernelPacked, num_events_in_wait_list, |
| event_wait_listPacked, eventPacked); |
| |
| return EnqueueTask(command_queuePacked, kernelPacked, num_events_in_wait_list, |
| event_wait_listPacked, eventPacked); |
| } |
| |
| // CL 1.1 |
| 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_EVENT(CreateSubBuffer, |
| "buffer = 0x%016" PRIxPTR |
| ", flags = %lu, buffer_create_type = %u, buffer_create_info = 0x%016" PRIxPTR |
| ", errcode_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)buffer, flags, buffer_create_type, (uintptr_t)buffer_create_info, |
| (uintptr_t)errcode_ret); |
| |
| Memory *bufferPacked = PackParam<Memory *>(buffer); |
| |
| ANGLE_CL_VALIDATE_POINTER(CreateSubBuffer, bufferPacked, flags, buffer_create_type, |
| buffer_create_info, errcode_ret); |
| |
| return CreateSubBuffer(bufferPacked, flags, buffer_create_type, buffer_create_info, |
| errcode_ret); |
| } |
| |
| cl_int CL_API_CALL clSetMemObjectDestructorCallback(cl_mem memobj, |
| void(CL_CALLBACK *pfn_notify)(cl_mem memobj, |
| void *user_data), |
| void *user_data) |
| { |
| CL_EVENT(SetMemObjectDestructorCallback, |
| "memobj = 0x%016" PRIxPTR ", pfn_notify = 0x%016" PRIxPTR |
| ", user_data = 0x%016" PRIxPTR "", |
| (uintptr_t)memobj, (uintptr_t)pfn_notify, (uintptr_t)user_data); |
| |
| Memory *memobjPacked = PackParam<Memory *>(memobj); |
| |
| ANGLE_CL_VALIDATE_ERROR(SetMemObjectDestructorCallback, memobjPacked, pfn_notify, user_data); |
| |
| return SetMemObjectDestructorCallback(memobjPacked, pfn_notify, user_data); |
| } |
| |
| cl_event CL_API_CALL clCreateUserEvent(cl_context context, cl_int *errcode_ret) |
| { |
| CL_EVENT(CreateUserEvent, "context = 0x%016" PRIxPTR ", errcode_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)context, (uintptr_t)errcode_ret); |
| |
| Context *contextPacked = PackParam<Context *>(context); |
| |
| ANGLE_CL_VALIDATE_POINTER(CreateUserEvent, contextPacked, errcode_ret); |
| |
| return CreateUserEvent(contextPacked, errcode_ret); |
| } |
| |
| cl_int CL_API_CALL clSetUserEventStatus(cl_event event, cl_int execution_status) |
| { |
| CL_EVENT(SetUserEventStatus, "event = 0x%016" PRIxPTR ", execution_status = %d", |
| (uintptr_t)event, execution_status); |
| |
| Event *eventPacked = PackParam<Event *>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(SetUserEventStatus, eventPacked, execution_status); |
| |
| return SetUserEventStatus(eventPacked, execution_status); |
| } |
| |
| cl_int CL_API_CALL clSetEventCallback(cl_event event, |
| cl_int command_exec_callback_type, |
| void(CL_CALLBACK *pfn_notify)(cl_event event, |
| cl_int event_command_status, |
| void *user_data), |
| void *user_data) |
| { |
| CL_EVENT( |
| SetEventCallback, |
| "event = 0x%016" PRIxPTR ", command_exec_callback_type = %d, pfn_notify = 0x%016" PRIxPTR |
| ", user_data = 0x%016" PRIxPTR "", |
| (uintptr_t)event, command_exec_callback_type, (uintptr_t)pfn_notify, (uintptr_t)user_data); |
| |
| Event *eventPacked = PackParam<Event *>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(SetEventCallback, eventPacked, command_exec_callback_type, pfn_notify, |
| user_data); |
| |
| return SetEventCallback(eventPacked, command_exec_callback_type, pfn_notify, user_data); |
| } |
| |
| 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_EVENT(EnqueueReadBufferRect, |
| "command_queue = 0x%016" PRIxPTR ", buffer = 0x%016" PRIxPTR |
| ", blocking_read = %u, buffer_origin = 0x%016" PRIxPTR ", host_origin = 0x%016" PRIxPTR |
| ", region = 0x%016" PRIxPTR |
| ", buffer_row_pitch = %zu, buffer_slice_pitch = %zu, host_row_pitch = %zu, " |
| "host_slice_pitch = %zu, ptr = 0x%016" PRIxPTR |
| ", num_events_in_wait_list = %u, event_wait_list = 0x%016" PRIxPTR |
| ", event = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, (uintptr_t)buffer, blocking_read, (uintptr_t)buffer_origin, |
| (uintptr_t)host_origin, (uintptr_t)region, buffer_row_pitch, buffer_slice_pitch, |
| host_row_pitch, host_slice_pitch, (uintptr_t)ptr, num_events_in_wait_list, |
| (uintptr_t)event_wait_list, (uintptr_t)event); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Memory *bufferPacked = PackParam<Memory *>(buffer); |
| Event *const *event_wait_listPacked = PackParam<Event *const *>(event_wait_list); |
| Event **eventPacked = PackParam<Event **>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(EnqueueReadBufferRect, command_queuePacked, bufferPacked, blocking_read, |
| buffer_origin, host_origin, region, buffer_row_pitch, |
| buffer_slice_pitch, host_row_pitch, host_slice_pitch, ptr, |
| num_events_in_wait_list, event_wait_listPacked, eventPacked); |
| |
| return EnqueueReadBufferRect(command_queuePacked, bufferPacked, blocking_read, buffer_origin, |
| host_origin, region, buffer_row_pitch, buffer_slice_pitch, |
| host_row_pitch, host_slice_pitch, ptr, num_events_in_wait_list, |
| event_wait_listPacked, eventPacked); |
| } |
| |
| cl_int CL_API_CALL clEnqueueWriteBufferRect(cl_command_queue command_queue, |
| cl_mem buffer, |
| cl_bool 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, |
| cl_uint num_events_in_wait_list, |
| const cl_event *event_wait_list, |
| cl_event *event) |
| { |
| CL_EVENT(EnqueueWriteBufferRect, |
| "command_queue = 0x%016" PRIxPTR ", buffer = 0x%016" PRIxPTR |
| ", blocking_write = %u, buffer_origin = 0x%016" PRIxPTR |
| ", host_origin = 0x%016" PRIxPTR ", region = 0x%016" PRIxPTR |
| ", buffer_row_pitch = %zu, buffer_slice_pitch = %zu, host_row_pitch = %zu, " |
| "host_slice_pitch = %zu, ptr = 0x%016" PRIxPTR |
| ", num_events_in_wait_list = %u, event_wait_list = 0x%016" PRIxPTR |
| ", event = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, (uintptr_t)buffer, blocking_write, (uintptr_t)buffer_origin, |
| (uintptr_t)host_origin, (uintptr_t)region, buffer_row_pitch, buffer_slice_pitch, |
| host_row_pitch, host_slice_pitch, (uintptr_t)ptr, num_events_in_wait_list, |
| (uintptr_t)event_wait_list, (uintptr_t)event); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Memory *bufferPacked = PackParam<Memory *>(buffer); |
| Event *const *event_wait_listPacked = PackParam<Event *const *>(event_wait_list); |
| Event **eventPacked = PackParam<Event **>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(EnqueueWriteBufferRect, command_queuePacked, bufferPacked, |
| blocking_write, buffer_origin, host_origin, region, buffer_row_pitch, |
| buffer_slice_pitch, host_row_pitch, host_slice_pitch, ptr, |
| num_events_in_wait_list, event_wait_listPacked, eventPacked); |
| |
| return EnqueueWriteBufferRect(command_queuePacked, bufferPacked, blocking_write, buffer_origin, |
| host_origin, region, buffer_row_pitch, buffer_slice_pitch, |
| host_row_pitch, host_slice_pitch, ptr, num_events_in_wait_list, |
| event_wait_listPacked, eventPacked); |
| } |
| |
| 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_EVENT(EnqueueCopyBufferRect, |
| "command_queue = 0x%016" PRIxPTR ", src_buffer = 0x%016" PRIxPTR |
| ", dst_buffer = 0x%016" PRIxPTR ", src_origin = 0x%016" PRIxPTR |
| ", dst_origin = 0x%016" PRIxPTR ", region = 0x%016" PRIxPTR |
| ", src_row_pitch = %zu, src_slice_pitch = %zu, dst_row_pitch = %zu, dst_slice_pitch = " |
| "%zu, num_events_in_wait_list = %u, event_wait_list = 0x%016" PRIxPTR |
| ", event = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, (uintptr_t)src_buffer, (uintptr_t)dst_buffer, |
| (uintptr_t)src_origin, (uintptr_t)dst_origin, (uintptr_t)region, src_row_pitch, |
| src_slice_pitch, dst_row_pitch, dst_slice_pitch, num_events_in_wait_list, |
| (uintptr_t)event_wait_list, (uintptr_t)event); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Memory *src_bufferPacked = PackParam<Memory *>(src_buffer); |
| Memory *dst_bufferPacked = PackParam<Memory *>(dst_buffer); |
| Event *const *event_wait_listPacked = PackParam<Event *const *>(event_wait_list); |
| Event **eventPacked = PackParam<Event **>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(EnqueueCopyBufferRect, command_queuePacked, src_bufferPacked, |
| dst_bufferPacked, src_origin, dst_origin, region, src_row_pitch, |
| src_slice_pitch, dst_row_pitch, dst_slice_pitch, |
| num_events_in_wait_list, event_wait_listPacked, eventPacked); |
| |
| return EnqueueCopyBufferRect(command_queuePacked, src_bufferPacked, dst_bufferPacked, |
| src_origin, dst_origin, region, src_row_pitch, src_slice_pitch, |
| dst_row_pitch, dst_slice_pitch, num_events_in_wait_list, |
| event_wait_listPacked, eventPacked); |
| } |
| |
| // CL 1.2 |
| cl_int CL_API_CALL clCreateSubDevices(cl_device_id in_device, |
| const cl_device_partition_property *properties, |
| cl_uint num_devices, |
| cl_device_id *out_devices, |
| cl_uint *num_devices_ret) |
| { |
| CL_EVENT(CreateSubDevices, |
| "in_device = 0x%016" PRIxPTR ", properties = 0x%016" PRIxPTR |
| ", num_devices = %u, out_devices = 0x%016" PRIxPTR ", num_devices_ret = 0x%016" PRIxPTR |
| "", |
| (uintptr_t)in_device, (uintptr_t)properties, num_devices, (uintptr_t)out_devices, |
| (uintptr_t)num_devices_ret); |
| |
| Device *in_devicePacked = PackParam<Device *>(in_device); |
| Device **out_devicesPacked = PackParam<Device **>(out_devices); |
| |
| ANGLE_CL_VALIDATE_ERROR(CreateSubDevices, in_devicePacked, properties, num_devices, |
| out_devicesPacked, num_devices_ret); |
| |
| return CreateSubDevices(in_devicePacked, properties, num_devices, out_devicesPacked, |
| num_devices_ret); |
| } |
| |
| cl_int CL_API_CALL clRetainDevice(cl_device_id device) |
| { |
| CL_EVENT(RetainDevice, "device = 0x%016" PRIxPTR "", (uintptr_t)device); |
| |
| Device *devicePacked = PackParam<Device *>(device); |
| |
| ANGLE_CL_VALIDATE_ERROR(RetainDevice, devicePacked); |
| |
| return RetainDevice(devicePacked); |
| } |
| |
| cl_int CL_API_CALL clReleaseDevice(cl_device_id device) |
| { |
| CL_EVENT(ReleaseDevice, "device = 0x%016" PRIxPTR "", (uintptr_t)device); |
| |
| Device *devicePacked = PackParam<Device *>(device); |
| |
| ANGLE_CL_VALIDATE_ERROR(ReleaseDevice, devicePacked); |
| |
| return ReleaseDevice(devicePacked); |
| } |
| |
| 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_EVENT(CreateImage, |
| "context = 0x%016" PRIxPTR ", flags = %lu, image_format = 0x%016" PRIxPTR |
| ", image_desc = 0x%016" PRIxPTR ", host_ptr = 0x%016" PRIxPTR |
| ", errcode_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)context, flags, (uintptr_t)image_format, (uintptr_t)image_desc, |
| (uintptr_t)host_ptr, (uintptr_t)errcode_ret); |
| |
| Context *contextPacked = PackParam<Context *>(context); |
| |
| ANGLE_CL_VALIDATE_POINTER(CreateImage, contextPacked, flags, image_format, image_desc, host_ptr, |
| errcode_ret); |
| |
| return CreateImage(contextPacked, flags, image_format, image_desc, host_ptr, errcode_ret); |
| } |
| |
| 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_EVENT(CreateProgramWithBuiltInKernels, |
| "context = 0x%016" PRIxPTR ", num_devices = %u, device_list = 0x%016" PRIxPTR |
| ", kernel_names = 0x%016" PRIxPTR ", errcode_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)context, num_devices, (uintptr_t)device_list, (uintptr_t)kernel_names, |
| (uintptr_t)errcode_ret); |
| |
| Context *contextPacked = PackParam<Context *>(context); |
| Device *const *device_listPacked = PackParam<Device *const *>(device_list); |
| |
| ANGLE_CL_VALIDATE_POINTER(CreateProgramWithBuiltInKernels, contextPacked, num_devices, |
| device_listPacked, kernel_names, errcode_ret); |
| |
| return CreateProgramWithBuiltInKernels(contextPacked, num_devices, device_listPacked, |
| kernel_names, errcode_ret); |
| } |
| |
| 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 program, |
| void *user_data), |
| void *user_data) |
| { |
| CL_EVENT(CompileProgram, |
| "program = 0x%016" PRIxPTR ", num_devices = %u, device_list = 0x%016" PRIxPTR |
| ", options = 0x%016" PRIxPTR ", num_input_headers = %u, input_headers = 0x%016" PRIxPTR |
| ", header_include_names = 0x%016" PRIxPTR ", pfn_notify = 0x%016" PRIxPTR |
| ", user_data = 0x%016" PRIxPTR "", |
| (uintptr_t)program, num_devices, (uintptr_t)device_list, (uintptr_t)options, |
| num_input_headers, (uintptr_t)input_headers, (uintptr_t)header_include_names, |
| (uintptr_t)pfn_notify, (uintptr_t)user_data); |
| |
| Program *programPacked = PackParam<Program *>(program); |
| Device *const *device_listPacked = PackParam<Device *const *>(device_list); |
| Program *const *input_headersPacked = PackParam<Program *const *>(input_headers); |
| |
| ANGLE_CL_VALIDATE_ERROR(CompileProgram, programPacked, num_devices, device_listPacked, options, |
| num_input_headers, input_headersPacked, header_include_names, |
| pfn_notify, user_data); |
| |
| return CompileProgram(programPacked, num_devices, device_listPacked, options, num_input_headers, |
| input_headersPacked, header_include_names, pfn_notify, user_data); |
| } |
| |
| 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 program, |
| void *user_data), |
| void *user_data, |
| cl_int *errcode_ret) |
| { |
| CL_EVENT(LinkProgram, |
| "context = 0x%016" PRIxPTR ", num_devices = %u, device_list = 0x%016" PRIxPTR |
| ", options = 0x%016" PRIxPTR |
| ", num_input_programs = %u, input_programs = 0x%016" PRIxPTR |
| ", pfn_notify = 0x%016" PRIxPTR ", user_data = 0x%016" PRIxPTR |
| ", errcode_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)context, num_devices, (uintptr_t)device_list, (uintptr_t)options, |
| num_input_programs, (uintptr_t)input_programs, (uintptr_t)pfn_notify, |
| (uintptr_t)user_data, (uintptr_t)errcode_ret); |
| |
| Context *contextPacked = PackParam<Context *>(context); |
| Device *const *device_listPacked = PackParam<Device *const *>(device_list); |
| Program *const *input_programsPacked = PackParam<Program *const *>(input_programs); |
| |
| ANGLE_CL_VALIDATE_POINTER(LinkProgram, contextPacked, num_devices, device_listPacked, options, |
| num_input_programs, input_programsPacked, pfn_notify, user_data, |
| errcode_ret); |
| |
| return LinkProgram(contextPacked, num_devices, device_listPacked, options, num_input_programs, |
| input_programsPacked, pfn_notify, user_data, errcode_ret); |
| } |
| |
| cl_int CL_API_CALL clUnloadPlatformCompiler(cl_platform_id platform) |
| { |
| CL_EVENT(UnloadPlatformCompiler, "platform = 0x%016" PRIxPTR "", (uintptr_t)platform); |
| |
| Platform *platformPacked = PackParam<Platform *>(platform); |
| |
| ANGLE_CL_VALIDATE_ERROR(UnloadPlatformCompiler, platformPacked); |
| |
| return UnloadPlatformCompiler(platformPacked); |
| } |
| |
| cl_int CL_API_CALL clGetKernelArgInfo(cl_kernel kernel, |
| cl_uint arg_index, |
| cl_kernel_arg_info param_name, |
| size_t param_value_size, |
| void *param_value, |
| size_t *param_value_size_ret) |
| { |
| CL_EVENT( |
| GetKernelArgInfo, |
| "kernel = 0x%016" PRIxPTR |
| ", arg_index = %u, param_name = %u, param_value_size = %zu, param_value = 0x%016" PRIxPTR |
| ", param_value_size_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)kernel, arg_index, param_name, param_value_size, (uintptr_t)param_value, |
| (uintptr_t)param_value_size_ret); |
| |
| Kernel *kernelPacked = PackParam<Kernel *>(kernel); |
| KernelArgInfo param_namePacked = PackParam<KernelArgInfo>(param_name); |
| |
| ANGLE_CL_VALIDATE_ERROR(GetKernelArgInfo, kernelPacked, arg_index, param_namePacked, |
| param_value_size, param_value, param_value_size_ret); |
| |
| return GetKernelArgInfo(kernelPacked, arg_index, param_namePacked, param_value_size, |
| param_value, param_value_size_ret); |
| } |
| |
| 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_EVENT(EnqueueFillBuffer, |
| "command_queue = 0x%016" PRIxPTR ", buffer = 0x%016" PRIxPTR |
| ", pattern = 0x%016" PRIxPTR |
| ", pattern_size = %zu, offset = %zu, size = %zu, num_events_in_wait_list = %u, " |
| "event_wait_list = 0x%016" PRIxPTR ", event = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, (uintptr_t)buffer, (uintptr_t)pattern, pattern_size, offset, |
| size, num_events_in_wait_list, (uintptr_t)event_wait_list, (uintptr_t)event); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Memory *bufferPacked = PackParam<Memory *>(buffer); |
| Event *const *event_wait_listPacked = PackParam<Event *const *>(event_wait_list); |
| Event **eventPacked = PackParam<Event **>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(EnqueueFillBuffer, command_queuePacked, bufferPacked, pattern, |
| pattern_size, offset, size, num_events_in_wait_list, |
| event_wait_listPacked, eventPacked); |
| |
| return EnqueueFillBuffer(command_queuePacked, bufferPacked, pattern, pattern_size, offset, size, |
| num_events_in_wait_list, event_wait_listPacked, eventPacked); |
| } |
| |
| 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_EVENT(EnqueueFillImage, |
| "command_queue = 0x%016" PRIxPTR ", image = 0x%016" PRIxPTR |
| ", fill_color = 0x%016" PRIxPTR ", origin = 0x%016" PRIxPTR ", region = 0x%016" PRIxPTR |
| ", num_events_in_wait_list = %u, event_wait_list = 0x%016" PRIxPTR |
| ", event = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, (uintptr_t)image, (uintptr_t)fill_color, (uintptr_t)origin, |
| (uintptr_t)region, num_events_in_wait_list, (uintptr_t)event_wait_list, |
| (uintptr_t)event); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Memory *imagePacked = PackParam<Memory *>(image); |
| Event *const *event_wait_listPacked = PackParam<Event *const *>(event_wait_list); |
| Event **eventPacked = PackParam<Event **>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(EnqueueFillImage, command_queuePacked, imagePacked, fill_color, origin, |
| region, num_events_in_wait_list, event_wait_listPacked, eventPacked); |
| |
| return EnqueueFillImage(command_queuePacked, imagePacked, fill_color, origin, region, |
| num_events_in_wait_list, event_wait_listPacked, eventPacked); |
| } |
| |
| 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_EVENT(EnqueueMigrateMemObjects, |
| "command_queue = 0x%016" PRIxPTR ", num_mem_objects = %u, mem_objects = 0x%016" PRIxPTR |
| ", flags = %lu, num_events_in_wait_list = %u, event_wait_list = 0x%016" PRIxPTR |
| ", event = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, num_mem_objects, (uintptr_t)mem_objects, flags, |
| num_events_in_wait_list, (uintptr_t)event_wait_list, (uintptr_t)event); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Memory *const *mem_objectsPacked = PackParam<Memory *const *>(mem_objects); |
| Event *const *event_wait_listPacked = PackParam<Event *const *>(event_wait_list); |
| Event **eventPacked = PackParam<Event **>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(EnqueueMigrateMemObjects, command_queuePacked, num_mem_objects, |
| mem_objectsPacked, flags, num_events_in_wait_list, |
| event_wait_listPacked, eventPacked); |
| |
| return EnqueueMigrateMemObjects(command_queuePacked, num_mem_objects, mem_objectsPacked, flags, |
| num_events_in_wait_list, event_wait_listPacked, eventPacked); |
| } |
| |
| 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_EVENT(EnqueueMarkerWithWaitList, |
| "command_queue = 0x%016" PRIxPTR |
| ", num_events_in_wait_list = %u, event_wait_list = 0x%016" PRIxPTR |
| ", event = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, num_events_in_wait_list, (uintptr_t)event_wait_list, |
| (uintptr_t)event); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Event *const *event_wait_listPacked = PackParam<Event *const *>(event_wait_list); |
| Event **eventPacked = PackParam<Event **>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(EnqueueMarkerWithWaitList, command_queuePacked, num_events_in_wait_list, |
| event_wait_listPacked, eventPacked); |
| |
| return EnqueueMarkerWithWaitList(command_queuePacked, num_events_in_wait_list, |
| event_wait_listPacked, eventPacked); |
| } |
| |
| 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_EVENT(EnqueueBarrierWithWaitList, |
| "command_queue = 0x%016" PRIxPTR |
| ", num_events_in_wait_list = %u, event_wait_list = 0x%016" PRIxPTR |
| ", event = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, num_events_in_wait_list, (uintptr_t)event_wait_list, |
| (uintptr_t)event); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Event *const *event_wait_listPacked = PackParam<Event *const *>(event_wait_list); |
| Event **eventPacked = PackParam<Event **>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(EnqueueBarrierWithWaitList, command_queuePacked, |
| num_events_in_wait_list, event_wait_listPacked, eventPacked); |
| |
| return EnqueueBarrierWithWaitList(command_queuePacked, num_events_in_wait_list, |
| event_wait_listPacked, eventPacked); |
| } |
| |
| void *CL_API_CALL clGetExtensionFunctionAddressForPlatform(cl_platform_id platform, |
| const char *func_name) |
| { |
| CL_EVENT(GetExtensionFunctionAddressForPlatform, |
| "platform = 0x%016" PRIxPTR ", func_name = 0x%016" PRIxPTR "", (uintptr_t)platform, |
| (uintptr_t)func_name); |
| |
| Platform *platformPacked = PackParam<Platform *>(platform); |
| |
| ANGLE_CL_VALIDATE_POINTER(GetExtensionFunctionAddressForPlatform, platformPacked, func_name); |
| |
| return GetExtensionFunctionAddressForPlatform(platformPacked, func_name); |
| } |
| |
| // CL 2.0 |
| cl_command_queue CL_API_CALL |
| clCreateCommandQueueWithProperties(cl_context context, |
| cl_device_id device, |
| const cl_queue_properties *properties, |
| cl_int *errcode_ret) |
| { |
| CL_EVENT(CreateCommandQueueWithProperties, |
| "context = 0x%016" PRIxPTR ", device = 0x%016" PRIxPTR ", properties = 0x%016" PRIxPTR |
| ", errcode_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)context, (uintptr_t)device, (uintptr_t)properties, (uintptr_t)errcode_ret); |
| |
| Context *contextPacked = PackParam<Context *>(context); |
| Device *devicePacked = PackParam<Device *>(device); |
| |
| ANGLE_CL_VALIDATE_POINTER(CreateCommandQueueWithProperties, contextPacked, devicePacked, |
| properties, errcode_ret); |
| |
| return CreateCommandQueueWithProperties(contextPacked, devicePacked, properties, errcode_ret); |
| } |
| |
| cl_mem 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_EVENT( |
| CreatePipe, |
| "context = 0x%016" PRIxPTR |
| ", flags = %lu, pipe_packet_size = %u, pipe_max_packets = %u, properties = 0x%016" PRIxPTR |
| ", errcode_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)context, flags, pipe_packet_size, pipe_max_packets, (uintptr_t)properties, |
| (uintptr_t)errcode_ret); |
| |
| Context *contextPacked = PackParam<Context *>(context); |
| |
| ANGLE_CL_VALIDATE_POINTER(CreatePipe, contextPacked, flags, pipe_packet_size, pipe_max_packets, |
| properties, errcode_ret); |
| |
| return CreatePipe(contextPacked, flags, pipe_packet_size, pipe_max_packets, properties, |
| errcode_ret); |
| } |
| |
| cl_int 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_EVENT(GetPipeInfo, |
| "pipe = 0x%016" PRIxPTR |
| ", param_name = %u, param_value_size = %zu, param_value = 0x%016" PRIxPTR |
| ", param_value_size_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)pipe, param_name, param_value_size, (uintptr_t)param_value, |
| (uintptr_t)param_value_size_ret); |
| |
| Memory *pipePacked = PackParam<Memory *>(pipe); |
| PipeInfo param_namePacked = PackParam<PipeInfo>(param_name); |
| |
| ANGLE_CL_VALIDATE_ERROR(GetPipeInfo, pipePacked, param_namePacked, param_value_size, |
| param_value, param_value_size_ret); |
| |
| return GetPipeInfo(pipePacked, param_namePacked, param_value_size, param_value, |
| param_value_size_ret); |
| } |
| |
| void *CL_API_CALL clSVMAlloc(cl_context context, |
| cl_svm_mem_flags flags, |
| size_t size, |
| cl_uint alignment) |
| { |
| CL_EVENT(SVMAlloc, "context = 0x%016" PRIxPTR ", flags = %lu, size = %zu, alignment = %u", |
| (uintptr_t)context, flags, size, alignment); |
| |
| Context *contextPacked = PackParam<Context *>(context); |
| |
| ANGLE_CL_VALIDATE_POINTER(SVMAlloc, contextPacked, flags, size, alignment); |
| |
| return SVMAlloc(contextPacked, flags, size, alignment); |
| } |
| |
| void CL_API_CALL clSVMFree(cl_context context, void *svm_pointer) |
| { |
| CL_EVENT(SVMFree, "context = 0x%016" PRIxPTR ", svm_pointer = 0x%016" PRIxPTR "", |
| (uintptr_t)context, (uintptr_t)svm_pointer); |
| |
| Context *contextPacked = PackParam<Context *>(context); |
| |
| ANGLE_CL_VALIDATE_VOID(SVMFree, contextPacked, svm_pointer); |
| |
| SVMFree(contextPacked, svm_pointer); |
| } |
| |
| cl_sampler CL_API_CALL |
| clCreateSamplerWithProperties(cl_context context, |
| const cl_sampler_properties *sampler_properties, |
| cl_int *errcode_ret) |
| { |
| CL_EVENT(CreateSamplerWithProperties, |
| "context = 0x%016" PRIxPTR ", sampler_properties = 0x%016" PRIxPTR |
| ", errcode_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)context, (uintptr_t)sampler_properties, (uintptr_t)errcode_ret); |
| |
| Context *contextPacked = PackParam<Context *>(context); |
| |
| ANGLE_CL_VALIDATE_POINTER(CreateSamplerWithProperties, contextPacked, sampler_properties, |
| errcode_ret); |
| |
| return CreateSamplerWithProperties(contextPacked, sampler_properties, errcode_ret); |
| } |
| |
| cl_int CL_API_CALL clSetKernelArgSVMPointer(cl_kernel kernel, |
| cl_uint arg_index, |
| const void *arg_value) |
| { |
| CL_EVENT(SetKernelArgSVMPointer, |
| "kernel = 0x%016" PRIxPTR ", arg_index = %u, arg_value = 0x%016" PRIxPTR "", |
| (uintptr_t)kernel, arg_index, (uintptr_t)arg_value); |
| |
| Kernel *kernelPacked = PackParam<Kernel *>(kernel); |
| |
| ANGLE_CL_VALIDATE_ERROR(SetKernelArgSVMPointer, kernelPacked, arg_index, arg_value); |
| |
| return SetKernelArgSVMPointer(kernelPacked, arg_index, arg_value); |
| } |
| |
| cl_int CL_API_CALL clSetKernelExecInfo(cl_kernel kernel, |
| cl_kernel_exec_info param_name, |
| size_t param_value_size, |
| const void *param_value) |
| { |
| CL_EVENT(SetKernelExecInfo, |
| "kernel = 0x%016" PRIxPTR |
| ", param_name = %u, param_value_size = %zu, param_value = 0x%016" PRIxPTR "", |
| (uintptr_t)kernel, param_name, param_value_size, (uintptr_t)param_value); |
| |
| Kernel *kernelPacked = PackParam<Kernel *>(kernel); |
| KernelExecInfo param_namePacked = PackParam<KernelExecInfo>(param_name); |
| |
| ANGLE_CL_VALIDATE_ERROR(SetKernelExecInfo, kernelPacked, param_namePacked, param_value_size, |
| param_value); |
| |
| return SetKernelExecInfo(kernelPacked, param_namePacked, param_value_size, param_value); |
| } |
| |
| 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 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_EVENT(EnqueueSVMFree, |
| "command_queue = 0x%016" PRIxPTR |
| ", num_svm_pointers = %u, svm_pointers = 0x%016" PRIxPTR |
| ", pfn_free_func = 0x%016" PRIxPTR ", user_data = 0x%016" PRIxPTR |
| ", num_events_in_wait_list = %u, event_wait_list = 0x%016" PRIxPTR |
| ", event = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, num_svm_pointers, (uintptr_t)svm_pointers, |
| (uintptr_t)pfn_free_func, (uintptr_t)user_data, num_events_in_wait_list, |
| (uintptr_t)event_wait_list, (uintptr_t)event); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Event *const *event_wait_listPacked = PackParam<Event *const *>(event_wait_list); |
| Event **eventPacked = PackParam<Event **>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(EnqueueSVMFree, command_queuePacked, num_svm_pointers, svm_pointers, |
| pfn_free_func, user_data, num_events_in_wait_list, |
| event_wait_listPacked, eventPacked); |
| |
| return EnqueueSVMFree(command_queuePacked, num_svm_pointers, svm_pointers, pfn_free_func, |
| user_data, num_events_in_wait_list, event_wait_listPacked, eventPacked); |
| } |
| |
| 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_EVENT(EnqueueSVMMemcpy, |
| "command_queue = 0x%016" PRIxPTR ", blocking_copy = %u, dst_ptr = 0x%016" PRIxPTR |
| ", src_ptr = 0x%016" PRIxPTR |
| ", size = %zu, num_events_in_wait_list = %u, event_wait_list = 0x%016" PRIxPTR |
| ", event = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, blocking_copy, (uintptr_t)dst_ptr, (uintptr_t)src_ptr, size, |
| num_events_in_wait_list, (uintptr_t)event_wait_list, (uintptr_t)event); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Event *const *event_wait_listPacked = PackParam<Event *const *>(event_wait_list); |
| Event **eventPacked = PackParam<Event **>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(EnqueueSVMMemcpy, command_queuePacked, blocking_copy, dst_ptr, src_ptr, |
| size, num_events_in_wait_list, event_wait_listPacked, eventPacked); |
| |
| return EnqueueSVMMemcpy(command_queuePacked, blocking_copy, dst_ptr, src_ptr, size, |
| num_events_in_wait_list, event_wait_listPacked, eventPacked); |
| } |
| |
| 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_EVENT(EnqueueSVMMemFill, |
| "command_queue = 0x%016" PRIxPTR ", svm_ptr = 0x%016" PRIxPTR |
| ", pattern = 0x%016" PRIxPTR |
| ", pattern_size = %zu, size = %zu, num_events_in_wait_list = %u, event_wait_list = " |
| "0x%016" PRIxPTR ", event = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, (uintptr_t)svm_ptr, (uintptr_t)pattern, pattern_size, size, |
| num_events_in_wait_list, (uintptr_t)event_wait_list, (uintptr_t)event); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Event *const *event_wait_listPacked = PackParam<Event *const *>(event_wait_list); |
| Event **eventPacked = PackParam<Event **>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(EnqueueSVMMemFill, command_queuePacked, svm_ptr, pattern, pattern_size, |
| size, num_events_in_wait_list, event_wait_listPacked, eventPacked); |
| |
| return EnqueueSVMMemFill(command_queuePacked, svm_ptr, pattern, pattern_size, size, |
| num_events_in_wait_list, event_wait_listPacked, eventPacked); |
| } |
| |
| cl_int CL_API_CALL clEnqueueSVMMap(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_EVENT(EnqueueSVMMap, |
| "command_queue = 0x%016" PRIxPTR |
| ", blocking_map = %u, flags = %lu, svm_ptr = 0x%016" PRIxPTR |
| ", size = %zu, num_events_in_wait_list = %u, event_wait_list = 0x%016" PRIxPTR |
| ", event = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, blocking_map, flags, (uintptr_t)svm_ptr, size, |
| num_events_in_wait_list, (uintptr_t)event_wait_list, (uintptr_t)event); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Event *const *event_wait_listPacked = PackParam<Event *const *>(event_wait_list); |
| Event **eventPacked = PackParam<Event **>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(EnqueueSVMMap, command_queuePacked, blocking_map, flags, svm_ptr, size, |
| num_events_in_wait_list, event_wait_listPacked, eventPacked); |
| |
| return EnqueueSVMMap(command_queuePacked, blocking_map, flags, svm_ptr, size, |
| num_events_in_wait_list, event_wait_listPacked, eventPacked); |
| } |
| |
| 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_EVENT(EnqueueSVMUnmap, |
| "command_queue = 0x%016" PRIxPTR ", svm_ptr = 0x%016" PRIxPTR |
| ", num_events_in_wait_list = %u, event_wait_list = 0x%016" PRIxPTR |
| ", event = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, (uintptr_t)svm_ptr, num_events_in_wait_list, |
| (uintptr_t)event_wait_list, (uintptr_t)event); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Event *const *event_wait_listPacked = PackParam<Event *const *>(event_wait_list); |
| Event **eventPacked = PackParam<Event **>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(EnqueueSVMUnmap, command_queuePacked, svm_ptr, num_events_in_wait_list, |
| event_wait_listPacked, eventPacked); |
| |
| return EnqueueSVMUnmap(command_queuePacked, svm_ptr, num_events_in_wait_list, |
| event_wait_listPacked, eventPacked); |
| } |
| |
| // CL 2.1 |
| cl_int CL_API_CALL clSetDefaultDeviceCommandQueue(cl_context context, |
| cl_device_id device, |
| cl_command_queue command_queue) |
| { |
| CL_EVENT(SetDefaultDeviceCommandQueue, |
| "context = 0x%016" PRIxPTR ", device = 0x%016" PRIxPTR |
| ", command_queue = 0x%016" PRIxPTR "", |
| (uintptr_t)context, (uintptr_t)device, (uintptr_t)command_queue); |
| |
| Context *contextPacked = PackParam<Context *>(context); |
| Device *devicePacked = PackParam<Device *>(device); |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| |
| ANGLE_CL_VALIDATE_ERROR(SetDefaultDeviceCommandQueue, contextPacked, devicePacked, |
| command_queuePacked); |
| |
| return SetDefaultDeviceCommandQueue(contextPacked, devicePacked, command_queuePacked); |
| } |
| |
| cl_int CL_API_CALL clGetDeviceAndHostTimer(cl_device_id device, |
| cl_ulong *device_timestamp, |
| cl_ulong *host_timestamp) |
| { |
| CL_EVENT(GetDeviceAndHostTimer, |
| "device = 0x%016" PRIxPTR ", device_timestamp = 0x%016" PRIxPTR |
| ", host_timestamp = 0x%016" PRIxPTR "", |
| (uintptr_t)device, (uintptr_t)device_timestamp, (uintptr_t)host_timestamp); |
| |
| Device *devicePacked = PackParam<Device *>(device); |
| |
| ANGLE_CL_VALIDATE_ERROR(GetDeviceAndHostTimer, devicePacked, device_timestamp, host_timestamp); |
| |
| return GetDeviceAndHostTimer(devicePacked, device_timestamp, host_timestamp); |
| } |
| |
| cl_int CL_API_CALL clGetHostTimer(cl_device_id device, cl_ulong *host_timestamp) |
| { |
| CL_EVENT(GetHostTimer, "device = 0x%016" PRIxPTR ", host_timestamp = 0x%016" PRIxPTR "", |
| (uintptr_t)device, (uintptr_t)host_timestamp); |
| |
| Device *devicePacked = PackParam<Device *>(device); |
| |
| ANGLE_CL_VALIDATE_ERROR(GetHostTimer, devicePacked, host_timestamp); |
| |
| return GetHostTimer(devicePacked, host_timestamp); |
| } |
| |
| cl_program CL_API_CALL clCreateProgramWithIL(cl_context context, |
| const void *il, |
| size_t length, |
| cl_int *errcode_ret) |
| { |
| CL_EVENT(CreateProgramWithIL, |
| "context = 0x%016" PRIxPTR ", il = 0x%016" PRIxPTR |
| ", length = %zu, errcode_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)context, (uintptr_t)il, length, (uintptr_t)errcode_ret); |
| |
| Context *contextPacked = PackParam<Context *>(context); |
| |
| ANGLE_CL_VALIDATE_POINTER(CreateProgramWithIL, contextPacked, il, length, errcode_ret); |
| |
| return CreateProgramWithIL(contextPacked, il, length, errcode_ret); |
| } |
| |
| cl_kernel CL_API_CALL clCloneKernel(cl_kernel source_kernel, cl_int *errcode_ret) |
| { |
| CL_EVENT(CloneKernel, "source_kernel = 0x%016" PRIxPTR ", errcode_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)source_kernel, (uintptr_t)errcode_ret); |
| |
| Kernel *source_kernelPacked = PackParam<Kernel *>(source_kernel); |
| |
| ANGLE_CL_VALIDATE_POINTER(CloneKernel, source_kernelPacked, errcode_ret); |
| |
| return CloneKernel(source_kernelPacked, errcode_ret); |
| } |
| |
| cl_int 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_EVENT(GetKernelSubGroupInfo, |
| "kernel = 0x%016" PRIxPTR ", device = 0x%016" PRIxPTR |
| ", param_name = %u, input_value_size = %zu, input_value = 0x%016" PRIxPTR |
| ", param_value_size = %zu, param_value = 0x%016" PRIxPTR |
| ", param_value_size_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)kernel, (uintptr_t)device, param_name, input_value_size, |
| (uintptr_t)input_value, param_value_size, (uintptr_t)param_value, |
| (uintptr_t)param_value_size_ret); |
| |
| Kernel *kernelPacked = PackParam<Kernel *>(kernel); |
| Device *devicePacked = PackParam<Device *>(device); |
| KernelSubGroupInfo param_namePacked = PackParam<KernelSubGroupInfo>(param_name); |
| |
| ANGLE_CL_VALIDATE_ERROR(GetKernelSubGroupInfo, kernelPacked, devicePacked, param_namePacked, |
| input_value_size, input_value, param_value_size, param_value, |
| param_value_size_ret); |
| |
| return GetKernelSubGroupInfo(kernelPacked, devicePacked, param_namePacked, input_value_size, |
| input_value, param_value_size, param_value, param_value_size_ret); |
| } |
| |
| 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_EVENT(EnqueueSVMMigrateMem, |
| "command_queue = 0x%016" PRIxPTR |
| ", num_svm_pointers = %u, svm_pointers = 0x%016" PRIxPTR ", sizes = 0x%016" PRIxPTR |
| ", flags = %lu, num_events_in_wait_list = %u, event_wait_list = 0x%016" PRIxPTR |
| ", event = 0x%016" PRIxPTR "", |
| (uintptr_t)command_queue, num_svm_pointers, (uintptr_t)svm_pointers, (uintptr_t)sizes, |
| flags, num_events_in_wait_list, (uintptr_t)event_wait_list, (uintptr_t)event); |
| |
| CommandQueue *command_queuePacked = PackParam<CommandQueue *>(command_queue); |
| Event *const *event_wait_listPacked = PackParam<Event *const *>(event_wait_list); |
| Event **eventPacked = PackParam<Event **>(event); |
| |
| ANGLE_CL_VALIDATE_ERROR(EnqueueSVMMigrateMem, command_queuePacked, num_svm_pointers, |
| svm_pointers, sizes, flags, num_events_in_wait_list, |
| event_wait_listPacked, eventPacked); |
| |
| return EnqueueSVMMigrateMem(command_queuePacked, num_svm_pointers, svm_pointers, sizes, flags, |
| num_events_in_wait_list, event_wait_listPacked, eventPacked); |
| } |
| |
| // CL 2.2 |
| cl_int CL_API_CALL clSetProgramReleaseCallback(cl_program program, |
| void(CL_CALLBACK *pfn_notify)(cl_program program, |
| void *user_data), |
| void *user_data) |
| { |
| CL_EVENT(SetProgramReleaseCallback, |
| "program = 0x%016" PRIxPTR ", pfn_notify = 0x%016" PRIxPTR |
| ", user_data = 0x%016" PRIxPTR "", |
| (uintptr_t)program, (uintptr_t)pfn_notify, (uintptr_t)user_data); |
| |
| Program *programPacked = PackParam<Program *>(program); |
| |
| ANGLE_CL_VALIDATE_ERROR(SetProgramReleaseCallback, programPacked, pfn_notify, user_data); |
| |
| return SetProgramReleaseCallback(programPacked, pfn_notify, user_data); |
| } |
| |
| cl_int CL_API_CALL clSetProgramSpecializationConstant(cl_program program, |
| cl_uint spec_id, |
| size_t spec_size, |
| const void *spec_value) |
| { |
| CL_EVENT(SetProgramSpecializationConstant, |
| "program = 0x%016" PRIxPTR |
| ", spec_id = %u, spec_size = %zu, spec_value = 0x%016" PRIxPTR "", |
| (uintptr_t)program, spec_id, spec_size, (uintptr_t)spec_value); |
| |
| Program *programPacked = PackParam<Program *>(program); |
| |
| ANGLE_CL_VALIDATE_ERROR(SetProgramSpecializationConstant, programPacked, spec_id, spec_size, |
| spec_value); |
| |
| return SetProgramSpecializationConstant(programPacked, spec_id, spec_size, spec_value); |
| } |
| |
| // CL 3.0 |
| cl_int CL_API_CALL clSetContextDestructorCallback(cl_context context, |
| void(CL_CALLBACK *pfn_notify)(cl_context context, |
| void *user_data), |
| void *user_data) |
| { |
| CL_EVENT(SetContextDestructorCallback, |
| "context = 0x%016" PRIxPTR ", pfn_notify = 0x%016" PRIxPTR |
| ", user_data = 0x%016" PRIxPTR "", |
| (uintptr_t)context, (uintptr_t)pfn_notify, (uintptr_t)user_data); |
| |
| Context *contextPacked = PackParam<Context *>(context); |
| |
| ANGLE_CL_VALIDATE_ERROR(SetContextDestructorCallback, contextPacked, pfn_notify, user_data); |
| |
| return SetContextDestructorCallback(contextPacked, pfn_notify, user_data); |
| } |
| |
| cl_mem CL_API_CALL clCreateBufferWithProperties(cl_context context, |
| const cl_mem_properties *properties, |
| cl_mem_flags flags, |
| size_t size, |
| void *host_ptr, |
| cl_int *errcode_ret) |
| { |
| CL_EVENT(CreateBufferWithProperties, |
| "context = 0x%016" PRIxPTR ", properties = 0x%016" PRIxPTR |
| ", flags = %lu, size = %zu, host_ptr = 0x%016" PRIxPTR ", errcode_ret = 0x%016" PRIxPTR |
| "", |
| (uintptr_t)context, (uintptr_t)properties, flags, size, (uintptr_t)host_ptr, |
| (uintptr_t)errcode_ret); |
| |
| Context *contextPacked = PackParam<Context *>(context); |
| |
| ANGLE_CL_VALIDATE_POINTER(CreateBufferWithProperties, contextPacked, properties, flags, size, |
| host_ptr, errcode_ret); |
| |
| return CreateBufferWithProperties(contextPacked, properties, flags, size, host_ptr, |
| errcode_ret); |
| } |
| |
| cl_mem CL_API_CALL clCreateImageWithProperties(cl_context context, |
| const cl_mem_properties *properties, |
| cl_mem_flags flags, |
| const cl_image_format *image_format, |
| const cl_image_desc *image_desc, |
| void *host_ptr, |
| cl_int *errcode_ret) |
| { |
| CL_EVENT(CreateImageWithProperties, |
| "context = 0x%016" PRIxPTR ", properties = 0x%016" PRIxPTR |
| ", flags = %lu, image_format = 0x%016" PRIxPTR ", image_desc = 0x%016" PRIxPTR |
| ", host_ptr = 0x%016" PRIxPTR ", errcode_ret = 0x%016" PRIxPTR "", |
| (uintptr_t)context, (uintptr_t)properties, flags, (uintptr_t)image_format, |
| (uintptr_t)image_desc, (uintptr_t)host_ptr, (uintptr_t)errcode_ret); |
| |
| Context *contextPacked = PackParam<Context *>(context); |
| |
| ANGLE_CL_VALIDATE_POINTER(CreateImageWithProperties, contextPacked, properties, flags, |
| image_format, image_desc, host_ptr, errcode_ret); |
| |
| return CreateImageWithProperties(contextPacked, properties, flags, image_format, image_desc, |
| host_ptr, errcode_ret); |
| } |
| |
| } // namespace cl |
