internal static extern ErrorCode clGetSupportedImageFormats(
cl_context context,
cl_mem_flags flags,
cl_mem_object_type image_type,
cl_uint num_entries,
[Out][MarshalAs(UnmanagedType.LPArray, SizeParamIndex = 3)] ImageFormat[] image_formats,
out cl_uint num_image_formats);
internal static extern ErrorCode clEnqueueUnmapMemObject(
cl_command_queue command_queue,
cl_mem memobj,
void *mapped_ptr,
cl_uint num_events_in_wait_list,
IntPtr *event_wait_list,
cl_event *_event);
internal static extern ErrorCode clEnqueueReleaseGLObjects(
cl_command_queue command_queue,
cl_uint num_objects,
[In] cl_mem[] mem_objects,
cl_uint num_events_in_wait_list,
[In] cl_event[] event_wait_list,
cl_event *_event);
internal static extern cl_int clBuildProgram(
cl_program program,
cl_uint num_devices,
[In] cl_device_id[] device_list,
String options,
ProgramNotify pfn_notify,
IntPtr user_data);
internal static extern ErrorCode clEnqueueUnmapMemObject(
cl_command_queue command_queue,
cl_mem memobj,
void *mapped_ptr,
cl_uint num_events_in_wait_list,
[In][MarshalAs(UnmanagedType.LPArray)] cl_event[] event_wait_list,
cl_event *_event);
internal static extern cl_program clCreateProgramWithBinary(
cl_context context,
cl_uint num_devices,
[In] cl_device_id[] device_list,
[In] IntPtr[] lengths,
[In] IntPtr[] pBinaries,
[Out][MarshalAs(UnmanagedType.LPArray, SizeParamIndex = 1)] cl_int[] binary_status,
[MarshalAs(UnmanagedType.I4)] out ErrorCode errcode_ret);
internal static extern ErrorCode clEnqueueNDRangeKernel(
cl_command_queue command_queue,
cl_kernel kernel,
cl_uint work_dim,
[In][MarshalAs(UnmanagedType.LPArray)] IntPtr[] global_work_offset,
[In][MarshalAs(UnmanagedType.LPArray)] IntPtr[] global_work_size,
[In][MarshalAs(UnmanagedType.LPArray)] IntPtr[] local_work_size,
cl_uint num_events_in_wait_list,
[In][MarshalAs(UnmanagedType.LPArray)] cl_event[] event_wait_list,
cl_event *_event);
internal static extern ErrorCode clEnqueueCopyBufferToImage(
cl_command_queue command_queue,
cl_mem src_buffer,
cl_mem dst_image,
IntPtr src_offset,
IntPtr *dst_origin,
IntPtr *region,
cl_uint num_events_in_wait_list,
IntPtr *event_wait_list,
cl_event *_event);
internal static extern ErrorCode clEnqueueCopyBufferToImage(
cl_command_queue command_queue,
cl_mem src_buffer,
cl_mem dst_image,
IntPtr src_offset,
[In][MarshalAs(UnmanagedType.LPArray, SizeConst = 3)] IntPtr[] dst_origin,
[In][MarshalAs(UnmanagedType.LPArray, SizeConst = 3)] IntPtr[] region,
cl_uint num_events_in_wait_list,
[In][MarshalAs(UnmanagedType.LPArray)] cl_event[] event_wait_list,
cl_event *_event);
internal static extern ErrorCode clEnqueueNDRangeKernel(
cl_command_queue command_queue,
cl_kernel kernel,
cl_uint work_dim,
IntPtr *global_work_offset,
IntPtr *global_work_size,
IntPtr *local_work_size,
cl_uint num_events_in_wait_list,
IntPtr *event_wait_list,
cl_event *_event);
internal static extern ErrorCode clEnqueueCopyBuffer(
cl_command_queue command_queue,
cl_mem src_buffer,
cl_mem dst_buffer,
IntPtr src_offset,
IntPtr dst_offset,
IntPtr cb,
cl_uint num_events_in_wait_list,
IntPtr *event_wait_list,
cl_event *_event);
internal static extern ErrorCode clEnqueueCopyBuffer(
cl_command_queue command_queue,
cl_mem src_buffer,
cl_mem dst_buffer,
IntPtr src_offset,
IntPtr dst_offset,
IntPtr cb,
cl_uint num_events_in_wait_list,
[In][MarshalAs(UnmanagedType.LPArray)] cl_event[] event_wait_list,
cl_event *_event);
internal static extern ErrorCode clEnqueueWriteBuffer(
cl_command_queue command_queue,
cl_mem buffer,
cl_bool blocking_write,
IntPtr offset,
IntPtr cb,
void *ptr,
cl_uint num_events_in_wait_list,
IntPtr *event_wait_list,
cl_event *_event);
internal static extern ErrorCode clEnqueueWriteBuffer(
cl_command_queue command_queue,
cl_mem buffer,
cl_bool blocking_write,
IntPtr offset,
IntPtr cb,
void *ptr,
cl_uint num_events_in_wait_list,
[In][MarshalAs(UnmanagedType.LPArray)] cl_event[] event_wait_list,
cl_event *_event);
internal static extern void *clEnqueueMapBuffer(
cl_command_queue command_queue,
cl_mem buffer,
cl_bool blocking_map,
cl_map_flags map_flags,
IntPtr offset,
IntPtr cb,
cl_uint num_events_in_wait_list,
IntPtr *event_wait_list,
cl_event *_event,
out ErrorCode errcode_ret);
internal static extern void *clEnqueueMapBuffer(
cl_command_queue command_queue,
cl_mem buffer,
cl_bool blocking_map,
cl_map_flags map_flags,
IntPtr offset,
IntPtr cb,
cl_uint num_events_in_wait_list,
[In][MarshalAs(UnmanagedType.LPArray)] cl_event[] event_wait_list,
cl_event *_event,
out ErrorCode errcode_ret);
internal static extern ErrorCode clEnqueueNativeKernel(
cl_command_queue command_queue,
NativeKernelInternal user_func,
void *args,
IntPtr cb_args,
cl_uint num_mem_objects,
[In] cl_mem[] mem_list,
[In][MarshalAs(UnmanagedType.LPArray, SizeParamIndex = 4)] IntPtr[] args_mem_loc,
cl_uint num_events_in_wait_list,
[In][MarshalAs(UnmanagedType.LPArray)] cl_event[] event_wait_list,
cl_event *_event);
internal static extern ErrorCode clEnqueueWriteImage(
cl_command_queue command_queue,
cl_mem image,
cl_bool blocking_write,
[In][MarshalAs(UnmanagedType.LPArray, SizeConst = 3)] IntPtr[] origin,
[In][MarshalAs(UnmanagedType.LPArray, SizeConst = 3)] IntPtr[] region,
IntPtr input_row_pitch,
IntPtr input_slice_pitch,
void *ptr,
cl_uint num_events_in_wait_list,
[In][MarshalAs(UnmanagedType.LPArray)] cl_event[] event_wait_list,
cl_event *_event);
internal static extern ErrorCode clEnqueueWriteImage(
cl_command_queue command_queue,
cl_mem image,
cl_bool blocking_write,
IntPtr *origin,
IntPtr *region,
IntPtr input_row_pitch,
IntPtr input_slice_pitch,
void *ptr,
cl_uint num_events_in_wait_list,
IntPtr *event_wait_list,
cl_event *_event);
internal static extern void *clEnqueueMapImage(
cl_command_queue command_queue,
cl_mem image,
cl_bool blocking_map,
cl_map_flags map_flags,
[In][MarshalAs(UnmanagedType.LPArray, SizeConst = 3)] IntPtr[] origin,
[In][MarshalAs(UnmanagedType.LPArray, SizeConst = 3)] IntPtr[] region,
out IntPtr image_row_pitch,
out IntPtr image_slice_pitch,
cl_uint num_events_in_wait_list,
[In][MarshalAs(UnmanagedType.LPArray)] cl_event[] event_wait_list,
cl_event *_event,
out ErrorCode errcode_ret);
internal static extern void *clEnqueueMapImage(
cl_command_queue command_queue,
cl_mem image,
cl_bool blocking_map,
cl_map_flags map_flags,
IntPtr *origin,
IntPtr *region,
out IntPtr image_row_pitch,
out IntPtr image_slice_pitch,
cl_uint num_events_in_wait_list,
IntPtr *event_wait_list,
cl_event *_event,
out ErrorCode errcode_ret);
internal static extern ErrorCode clEnqueueCopyBufferRect(
cl_command_queue command_queue,
cl_mem src_buffer,
cl_mem dst_buffer,
[In] IntPtr[] src_origin,
[In] IntPtr[] dst_origin,
[In] IntPtr[] region,
IntPtr src_row_pitch,
IntPtr src_slice_pitch,
IntPtr dst_row_pitch,
IntPtr dst_slice_pitch,
cl_uint num_events_in_wait_list,
[In][MarshalAs(UnmanagedType.LPArray)] cl_event[] _event_wait_list,
cl_event *_event);
internal static extern ErrorCode clEnqueueCopyBufferRect(
cl_command_queue command_queue,
cl_mem src_buffer,
cl_mem dst_buffer,
IntPtr *src_origin,
IntPtr *dst_origin,
IntPtr *region,
IntPtr src_row_pitch,
IntPtr src_slice_pitch,
IntPtr dst_row_pitch,
IntPtr dst_slice_pitch,
cl_uint num_events_in_wait_list,
cl_event *_event_wait_list,
cl_event *_event);
internal static extern ErrorCode clEnqueueWriteBufferRect(
cl_command_queue command_queue,
cl_mem buffer,
cl_bool blocking_write,
[In] IntPtr[] buffer_offset,
[In] IntPtr[] host_offset,
[In] IntPtr[] region,
IntPtr buffer_row_pitch,
IntPtr buffer_slice_pitch,
IntPtr host_row_pitch,
IntPtr host_slice_pitch,
void *ptr,
cl_uint num_events_in_wait_list,
[In][MarshalAs(UnmanagedType.LPArray)] cl_event[] _event_wait_list,
cl_event *_event);
internal static extern ErrorCode clEnqueueWriteBufferRect(
cl_command_queue command_queue,
cl_mem buffer,
cl_bool blocking_write,
IntPtr *buffer_offset,
IntPtr *host_offset,
IntPtr *region,
IntPtr buffer_row_pitch,
IntPtr buffer_slice_pitch,
IntPtr host_row_pitch,
IntPtr host_slice_pitch,
void *ptr,
cl_uint num_events_in_wait_list,
cl_event *_event_wait_list,
cl_event *_event);
public static ErrorCode EnqueueNativeKernel(cl_command_queue command_queue,
NativeKernelInternal user_func,
void *args,
IntPtr cb_args,
cl_uint num_mem_objects,
cl_mem[] mem_list,
IntPtr[] args_mem_loc,
cl_uint num_events_in_wait_list,
cl_event[] event_wait_list,
cl_event *_event)
{
return(OpenCLAPI.clEnqueueNativeKernel(command_queue,
user_func,
args,
cb_args,
num_mem_objects,
mem_list,
args_mem_loc,
num_events_in_wait_list,
event_wait_list,
_event));
}
private static extern ErrorCode clGetGLContextInfoKHR( [In] [MarshalAs(UnmanagedType.LPArray)] cl_uint[] properties, cl_gl_ContextInfo info, cl_uint size, [Out] [MarshalAs(UnmanagedType.LPArray)] Device[] devices, [Out] out cl_uint retSize);
private static extern IntPtr clCreateContext([In] [MarshalAs(UnmanagedType.LPArray)] cl_uint[] properties, cl_uint numDevices, [In] [MarshalAs(UnmanagedType.LPArray)] Device[] devices, ContextNotify pfnNotify, IntPtr userData, out ErrorCode errcodeRet);
internal static extern ErrorCode clEnqueueTask(
cl_command_queue command_queue,
cl_kernel kernel,
cl_uint num_events_in_wait_list,
[In][MarshalAs(UnmanagedType.LPArray)] cl_event[] event_wait_list,
cl_event *_event);
internal static extern ErrorCode clWaitForEvents(
cl_uint num_events,
[In][MarshalAs(UnmanagedType.LPArray)] cl_event[] _event_list);
internal static extern ErrorCode clEnqueueTask(
cl_command_queue command_queue,
cl_kernel kernel,
cl_uint num_events_in_wait_list,
IntPtr *event_wait_list,
cl_event *_event);
internal static extern ErrorCode clEnqueueWaitForEvents(
cl_command_queue command_queue,
cl_uint num_events,
IntPtr *_event_list);
