CL11 (LWJGL 3.2.4 SNAPSHOT

java.lang.Object
- org.lwjgl.opencl.CL10
- - org.lwjgl.opencl.CL11

Direct Known Subclasses:

CL12
```
public class CL11
extends CL10
```
The core OpenCL 1.1 functionality.

Field Summary

Fields
Modifier and Type	Field and Description
`static int`	`CL_ADDRESS_MIRRORED_REPEAT` cl_addressing_mode.
`static int`	`CL_BUFFER_CREATE_TYPE_REGION` cl_buffer_create_type.
`static int`	`CL_COMMAND_COPY_BUFFER_RECT` cl_command_type.
`static int`	`CL_COMMAND_READ_BUFFER_RECT` cl_command_type.
`static int`	`CL_COMMAND_USER` cl_command_type.
`static int`	`CL_COMMAND_WRITE_BUFFER_RECT` cl_command_type.
`static int`	`CL_CONTEXT_NUM_DEVICES` cl_context_info.
`static int`	`CL_DEVICE_HOST_UNIFIED_MEMORY` cl_device_info.
`static int`	`CL_DEVICE_NATIVE_VECTOR_WIDTH_CHAR` cl_device_info.
`static int`	`CL_DEVICE_NATIVE_VECTOR_WIDTH_DOUBLE` cl_device_info.
`static int`	`CL_DEVICE_NATIVE_VECTOR_WIDTH_FLOAT` cl_device_info.
`static int`	`CL_DEVICE_NATIVE_VECTOR_WIDTH_HALF` cl_device_info.
`static int`	`CL_DEVICE_NATIVE_VECTOR_WIDTH_INT` cl_device_info.
`static int`	`CL_DEVICE_NATIVE_VECTOR_WIDTH_LONG` cl_device_info.
`static int`	`CL_DEVICE_NATIVE_VECTOR_WIDTH_SHORT` cl_device_info.
`static int`	`CL_DEVICE_OPENCL_C_VERSION` cl_device_info.
`static int`	`CL_DEVICE_PREFERRED_VECTOR_WIDTH_HALF` cl_device_info.
`static int`	`CL_EVENT_CONTEXT` cl_event_info.
`static int`	`CL_EXEC_STATUS_ERROR_FOR_EVENTS_IN_WAIT_LIST` Error Codes.
`static int`	`CL_FP_SOFT_FLOAT` cl_device_fp_config - bitfield.
`static int`	`CL_INVALID_PROPERTY` Error Codes.
`static int`	`CL_KERNEL_PREFERRED_WORK_GROUP_SIZE_MULTIPLE` cl_kernel_work_group_info.
`static int`	`CL_KERNEL_PRIVATE_MEM_SIZE` cl_kernel_work_group_info.
`static int`	`CL_MEM_ASSOCIATED_MEMOBJECT` cl_mem_info.
`static int`	`CL_MEM_OFFSET` cl_mem_info.
`static int`	`CL_MISALIGNED_SUB_BUFFER_OFFSET` Error Codes.
`static int`	`CL_RGBx` cl_channel_order.
`static int`	`CL_RGx` cl_channel_order.
`static int`	`CL_Rx` cl_channel_order.
`static int`	`CL_VERSION_1_1` OpenCL Version.

Fields inherited from class org.lwjgl.opencl.CL10
CL_A, CL_ADDRESS_CLAMP, CL_ADDRESS_CLAMP_TO_EDGE, CL_ADDRESS_NONE, CL_ADDRESS_REPEAT, CL_ARGB, CL_BGRA, CL_BUILD_ERROR, CL_BUILD_IN_PROGRESS, CL_BUILD_NONE, CL_BUILD_PROGRAM_FAILURE, CL_BUILD_SUCCESS, CL_COMMAND_ACQUIRE_GL_OBJECTS, CL_COMMAND_COPY_BUFFER, CL_COMMAND_COPY_BUFFER_TO_IMAGE, CL_COMMAND_COPY_IMAGE, CL_COMMAND_COPY_IMAGE_TO_BUFFER, CL_COMMAND_MAP_BUFFER, CL_COMMAND_MAP_IMAGE, CL_COMMAND_MARKER, CL_COMMAND_NATIVE_KERNEL, CL_COMMAND_NDRANGE_KERNEL, CL_COMMAND_READ_BUFFER, CL_COMMAND_READ_IMAGE, CL_COMMAND_RELEASE_GL_OBJECTS, CL_COMMAND_TASK, CL_COMMAND_UNMAP_MEM_OBJECT, CL_COMMAND_WRITE_BUFFER, CL_COMMAND_WRITE_IMAGE, CL_COMPILER_NOT_AVAILABLE, CL_COMPLETE, CL_CONTEXT_DEVICES, CL_CONTEXT_PLATFORM, CL_CONTEXT_PROPERTIES, CL_CONTEXT_REFERENCE_COUNT, CL_DEVICE_ADDRESS_BITS, CL_DEVICE_AVAILABLE, CL_DEVICE_COMPILER_AVAILABLE, CL_DEVICE_ENDIAN_LITTLE, CL_DEVICE_ERROR_CORRECTION_SUPPORT, CL_DEVICE_EXECUTION_CAPABILITIES, CL_DEVICE_EXTENSIONS, CL_DEVICE_GLOBAL_MEM_CACHE_SIZE, CL_DEVICE_GLOBAL_MEM_CACHE_TYPE, CL_DEVICE_GLOBAL_MEM_CACHELINE_SIZE, CL_DEVICE_GLOBAL_MEM_SIZE, CL_DEVICE_IMAGE_SUPPORT, CL_DEVICE_IMAGE2D_MAX_HEIGHT, CL_DEVICE_IMAGE2D_MAX_WIDTH, CL_DEVICE_IMAGE3D_MAX_DEPTH, CL_DEVICE_IMAGE3D_MAX_HEIGHT, CL_DEVICE_IMAGE3D_MAX_WIDTH, CL_DEVICE_LOCAL_MEM_SIZE, CL_DEVICE_LOCAL_MEM_TYPE, CL_DEVICE_MAX_CLOCK_FREQUENCY, CL_DEVICE_MAX_COMPUTE_UNITS, CL_DEVICE_MAX_CONSTANT_ARGS, CL_DEVICE_MAX_CONSTANT_BUFFER_SIZE, CL_DEVICE_MAX_MEM_ALLOC_SIZE, CL_DEVICE_MAX_PARAMETER_SIZE, CL_DEVICE_MAX_READ_IMAGE_ARGS, CL_DEVICE_MAX_SAMPLERS, CL_DEVICE_MAX_WORK_GROUP_SIZE, CL_DEVICE_MAX_WORK_ITEM_DIMENSIONS, CL_DEVICE_MAX_WORK_ITEM_SIZES, CL_DEVICE_MAX_WRITE_IMAGE_ARGS, CL_DEVICE_MEM_BASE_ADDR_ALIGN, CL_DEVICE_MIN_DATA_TYPE_ALIGN_SIZE, CL_DEVICE_NAME, CL_DEVICE_NOT_AVAILABLE, CL_DEVICE_NOT_FOUND, CL_DEVICE_PLATFORM, CL_DEVICE_PREFERRED_VECTOR_WIDTH_CHAR, CL_DEVICE_PREFERRED_VECTOR_WIDTH_DOUBLE, CL_DEVICE_PREFERRED_VECTOR_WIDTH_FLOAT, CL_DEVICE_PREFERRED_VECTOR_WIDTH_INT, CL_DEVICE_PREFERRED_VECTOR_WIDTH_LONG, CL_DEVICE_PREFERRED_VECTOR_WIDTH_SHORT, CL_DEVICE_PROFILE, CL_DEVICE_PROFILING_TIMER_RESOLUTION, CL_DEVICE_QUEUE_PROPERTIES, CL_DEVICE_SINGLE_FP_CONFIG, CL_DEVICE_TYPE, CL_DEVICE_TYPE_ACCELERATOR, CL_DEVICE_TYPE_ALL, CL_DEVICE_TYPE_CPU, CL_DEVICE_TYPE_DEFAULT, CL_DEVICE_TYPE_GPU, CL_DEVICE_VENDOR, CL_DEVICE_VENDOR_ID, CL_DEVICE_VERSION, CL_DRIVER_VERSION, CL_EVENT_COMMAND_EXECUTION_STATUS, CL_EVENT_COMMAND_QUEUE, CL_EVENT_COMMAND_TYPE, CL_EVENT_REFERENCE_COUNT, CL_EXEC_KERNEL, CL_EXEC_NATIVE_KERNEL, CL_FALSE, CL_FILTER_LINEAR, CL_FILTER_NEAREST, CL_FLOAT, CL_FP_DENORM, CL_FP_FMA, CL_FP_INF_NAN, CL_FP_ROUND_TO_INF, CL_FP_ROUND_TO_NEAREST, CL_FP_ROUND_TO_ZERO, CL_GLOBAL, CL_HALF_FLOAT, CL_IMAGE_DEPTH, CL_IMAGE_ELEMENT_SIZE, CL_IMAGE_FORMAT, CL_IMAGE_FORMAT_MISMATCH, CL_IMAGE_FORMAT_NOT_SUPPORTED, CL_IMAGE_HEIGHT, CL_IMAGE_ROW_PITCH, CL_IMAGE_SLICE_PITCH, CL_IMAGE_WIDTH, CL_INTENSITY, CL_INVALID_ARG_INDEX, CL_INVALID_ARG_SIZE, CL_INVALID_ARG_VALUE, CL_INVALID_BINARY, CL_INVALID_BUFFER_SIZE, CL_INVALID_BUILD_OPTIONS, CL_INVALID_COMMAND_QUEUE, CL_INVALID_CONTEXT, CL_INVALID_DEVICE, CL_INVALID_DEVICE_TYPE, CL_INVALID_EVENT, CL_INVALID_EVENT_WAIT_LIST, CL_INVALID_GLOBAL_OFFSET, CL_INVALID_GLOBAL_WORK_SIZE, CL_INVALID_HOST_PTR, CL_INVALID_IMAGE_FORMAT_DESCRIPTOR, CL_INVALID_IMAGE_SIZE, CL_INVALID_KERNEL, CL_INVALID_KERNEL_ARGS, CL_INVALID_KERNEL_DEFINITION, CL_INVALID_KERNEL_NAME, CL_INVALID_MEM_OBJECT, CL_INVALID_OPERATION, CL_INVALID_PLATFORM, CL_INVALID_PROGRAM, CL_INVALID_PROGRAM_EXECUTABLE, CL_INVALID_QUEUE_PROPERTIES, CL_INVALID_SAMPLER, CL_INVALID_VALUE, CL_INVALID_WORK_DIMENSION, CL_INVALID_WORK_GROUP_SIZE, CL_INVALID_WORK_ITEM_SIZE, CL_KERNEL_COMPILE_WORK_GROUP_SIZE, CL_KERNEL_CONTEXT, CL_KERNEL_FUNCTION_NAME, CL_KERNEL_LOCAL_MEM_SIZE, CL_KERNEL_NUM_ARGS, CL_KERNEL_PROGRAM, CL_KERNEL_REFERENCE_COUNT, CL_KERNEL_WORK_GROUP_SIZE, CL_LOCAL, CL_LUMINANCE, CL_MAP_FAILURE, CL_MAP_READ, CL_MAP_WRITE, CL_MEM_ALLOC_HOST_PTR, CL_MEM_CONTEXT, CL_MEM_COPY_HOST_PTR, CL_MEM_COPY_OVERLAP, CL_MEM_FLAGS, CL_MEM_HOST_PTR, CL_MEM_MAP_COUNT, CL_MEM_OBJECT_ALLOCATION_FAILURE, CL_MEM_OBJECT_BUFFER, CL_MEM_OBJECT_IMAGE2D, CL_MEM_OBJECT_IMAGE3D, CL_MEM_READ_ONLY, CL_MEM_READ_WRITE, CL_MEM_REFERENCE_COUNT, CL_MEM_SIZE, CL_MEM_TYPE, CL_MEM_USE_HOST_PTR, CL_MEM_WRITE_ONLY, CL_NONE, CL_OUT_OF_HOST_MEMORY, CL_OUT_OF_RESOURCES, CL_PLATFORM_EXTENSIONS, CL_PLATFORM_NAME, CL_PLATFORM_PROFILE, CL_PLATFORM_VENDOR, CL_PLATFORM_VERSION, CL_PROFILING_COMMAND_END, CL_PROFILING_COMMAND_QUEUED, CL_PROFILING_COMMAND_START, CL_PROFILING_COMMAND_SUBMIT, CL_PROFILING_INFO_NOT_AVAILABLE, CL_PROGRAM_BINARIES, CL_PROGRAM_BINARY_SIZES, CL_PROGRAM_BUILD_LOG, CL_PROGRAM_BUILD_OPTIONS, CL_PROGRAM_BUILD_STATUS, CL_PROGRAM_CONTEXT, CL_PROGRAM_DEVICES, CL_PROGRAM_NUM_DEVICES, CL_PROGRAM_REFERENCE_COUNT, CL_PROGRAM_SOURCE, CL_QUEUE_CONTEXT, CL_QUEUE_DEVICE, CL_QUEUE_OUT_OF_ORDER_EXEC_MODE_ENABLE, CL_QUEUE_PROFILING_ENABLE, CL_QUEUE_PROPERTIES, CL_QUEUE_REFERENCE_COUNT, CL_QUEUED, CL_R, CL_RA, CL_READ_ONLY_CACHE, CL_READ_WRITE_CACHE, CL_RG, CL_RGB, CL_RGBA, CL_RUNNING, CL_SAMPLER_ADDRESSING_MODE, CL_SAMPLER_CONTEXT, CL_SAMPLER_FILTER_MODE, CL_SAMPLER_NORMALIZED_COORDS, CL_SAMPLER_REFERENCE_COUNT, CL_SIGNED_INT16, CL_SIGNED_INT32, CL_SIGNED_INT8, CL_SNORM_INT16, CL_SNORM_INT8, CL_SUBMITTED, CL_SUCCESS, CL_TRUE, CL_UNORM_INT_101010, CL_UNORM_INT16, CL_UNORM_INT8, CL_UNORM_SHORT_555, CL_UNORM_SHORT_565, CL_UNSIGNED_INT16, CL_UNSIGNED_INT32, CL_UNSIGNED_INT8, CL_VERSION_1_0

Method Summary

All Methods Static Methods Concrete Methods
Modifier and Type	Method and Description
`static long`	`clCreateSubBuffer(long buffer, long flags, int buffer_create_type, java.nio.ByteBuffer buffer_create_info, int[] errcode_ret)` Array version of: `CreateSubBuffer`
`static long`	`clCreateSubBuffer(long buffer, long flags, int buffer_create_type, java.nio.ByteBuffer buffer_create_info, java.nio.IntBuffer errcode_ret)` Creates a new buffer object (referred to as a sub-buffer object) from an existing buffer object.
`static long`	`clCreateUserEvent(long context, int[] errcode_ret)` Array version of: `CreateUserEvent`
`static long`	`clCreateUserEvent(long context, java.nio.IntBuffer errcode_ret)` Creates a user event object.
`static int`	`clEnqueueCopyBufferRect(long command_queue, long src_buffer, long dst_buffer, org.lwjgl.PointerBuffer src_origin, org.lwjgl.PointerBuffer dst_origin, org.lwjgl.PointerBuffer region, long src_row_pitch, long src_slice_pitch, long dst_row_pitch, long dst_slice_pitch, org.lwjgl.PointerBuffer event_wait_list, org.lwjgl.PointerBuffer event)` Enqueues a command to copy a 2D or 3D rectangular region from the buffer object identified by `src_buffer` to a 2D or 3D region in the buffer object identified by `dst_buffer`.
`static int`	`clEnqueueReadBufferRect(long command_queue, long buffer, boolean blocking_read, org.lwjgl.PointerBuffer buffer_offset, org.lwjgl.PointerBuffer host_offset, org.lwjgl.PointerBuffer region, long buffer_row_pitch, long buffer_slice_pitch, long host_row_pitch, long host_slice_pitch, java.nio.ByteBuffer ptr, org.lwjgl.PointerBuffer event_wait_list, org.lwjgl.PointerBuffer event)` Enqueues a command to read a 2D or 3D rectangular region from a buffer object to host memory.
`static int`	`clEnqueueReadBufferRect(long command_queue, long buffer, boolean blocking_read, org.lwjgl.PointerBuffer buffer_offset, org.lwjgl.PointerBuffer host_offset, org.lwjgl.PointerBuffer region, long buffer_row_pitch, long buffer_slice_pitch, long host_row_pitch, long host_slice_pitch, double[] ptr, org.lwjgl.PointerBuffer event_wait_list, org.lwjgl.PointerBuffer event)` Array version of: `EnqueueReadBufferRect`
`static int`	`clEnqueueReadBufferRect(long command_queue, long buffer, boolean blocking_read, org.lwjgl.PointerBuffer buffer_offset, org.lwjgl.PointerBuffer host_offset, org.lwjgl.PointerBuffer region, long buffer_row_pitch, long buffer_slice_pitch, long host_row_pitch, long host_slice_pitch, java.nio.DoubleBuffer ptr, org.lwjgl.PointerBuffer event_wait_list, org.lwjgl.PointerBuffer event)` Enqueues a command to read a 2D or 3D rectangular region from a buffer object to host memory.
`static int`	`clEnqueueReadBufferRect(long command_queue, long buffer, boolean blocking_read, org.lwjgl.PointerBuffer buffer_offset, org.lwjgl.PointerBuffer host_offset, org.lwjgl.PointerBuffer region, long buffer_row_pitch, long buffer_slice_pitch, long host_row_pitch, long host_slice_pitch, float[] ptr, org.lwjgl.PointerBuffer event_wait_list, org.lwjgl.PointerBuffer event)` Array version of: `EnqueueReadBufferRect`
`static int`	`clEnqueueReadBufferRect(long command_queue, long buffer, boolean blocking_read, org.lwjgl.PointerBuffer buffer_offset, org.lwjgl.PointerBuffer host_offset, org.lwjgl.PointerBuffer region, long buffer_row_pitch, long buffer_slice_pitch, long host_row_pitch, long host_slice_pitch, java.nio.FloatBuffer ptr, org.lwjgl.PointerBuffer event_wait_list, org.lwjgl.PointerBuffer event)` Enqueues a command to read a 2D or 3D rectangular region from a buffer object to host memory.
`static int`	`clEnqueueReadBufferRect(long command_queue, long buffer, boolean blocking_read, org.lwjgl.PointerBuffer buffer_offset, org.lwjgl.PointerBuffer host_offset, org.lwjgl.PointerBuffer region, long buffer_row_pitch, long buffer_slice_pitch, long host_row_pitch, long host_slice_pitch, int[] ptr, org.lwjgl.PointerBuffer event_wait_list, org.lwjgl.PointerBuffer event)` Array version of: `EnqueueReadBufferRect`
`static int`	`clEnqueueReadBufferRect(long command_queue, long buffer, boolean blocking_read, org.lwjgl.PointerBuffer buffer_offset, org.lwjgl.PointerBuffer host_offset, org.lwjgl.PointerBuffer region, long buffer_row_pitch, long buffer_slice_pitch, long host_row_pitch, long host_slice_pitch, java.nio.IntBuffer ptr, org.lwjgl.PointerBuffer event_wait_list, org.lwjgl.PointerBuffer event)` Enqueues a command to read a 2D or 3D rectangular region from a buffer object to host memory.
`static int`	`clEnqueueReadBufferRect(long command_queue, long buffer, boolean blocking_read, org.lwjgl.PointerBuffer buffer_offset, org.lwjgl.PointerBuffer host_offset, org.lwjgl.PointerBuffer region, long buffer_row_pitch, long buffer_slice_pitch, long host_row_pitch, long host_slice_pitch, short[] ptr, org.lwjgl.PointerBuffer event_wait_list, org.lwjgl.PointerBuffer event)` Array version of: `EnqueueReadBufferRect`
`static int`	`clEnqueueReadBufferRect(long command_queue, long buffer, boolean blocking_read, org.lwjgl.PointerBuffer buffer_offset, org.lwjgl.PointerBuffer host_offset, org.lwjgl.PointerBuffer region, long buffer_row_pitch, long buffer_slice_pitch, long host_row_pitch, long host_slice_pitch, java.nio.ShortBuffer ptr, org.lwjgl.PointerBuffer event_wait_list, org.lwjgl.PointerBuffer event)` Enqueues a command to read a 2D or 3D rectangular region from a buffer object to host memory.
`static int`	`clEnqueueWriteBufferRect(long command_queue, long buffer, boolean blocking_write, org.lwjgl.PointerBuffer buffer_offset, org.lwjgl.PointerBuffer host_offset, org.lwjgl.PointerBuffer region, long buffer_row_pitch, long buffer_slice_pitch, long host_row_pitch, long host_slice_pitch, java.nio.ByteBuffer ptr, org.lwjgl.PointerBuffer event_wait_list, org.lwjgl.PointerBuffer event)` Enqueues a command to write a 2D or 3D rectangular region to a buffer object from host memory.
`static int`	`clEnqueueWriteBufferRect(long command_queue, long buffer, boolean blocking_write, org.lwjgl.PointerBuffer buffer_offset, org.lwjgl.PointerBuffer host_offset, org.lwjgl.PointerBuffer region, long buffer_row_pitch, long buffer_slice_pitch, long host_row_pitch, long host_slice_pitch, double[] ptr, org.lwjgl.PointerBuffer event_wait_list, org.lwjgl.PointerBuffer event)` Array version of: `EnqueueWriteBufferRect`
`static int`	`clEnqueueWriteBufferRect(long command_queue, long buffer, boolean blocking_write, org.lwjgl.PointerBuffer buffer_offset, org.lwjgl.PointerBuffer host_offset, org.lwjgl.PointerBuffer region, long buffer_row_pitch, long buffer_slice_pitch, long host_row_pitch, long host_slice_pitch, java.nio.DoubleBuffer ptr, org.lwjgl.PointerBuffer event_wait_list, org.lwjgl.PointerBuffer event)` Enqueues a command to write a 2D or 3D rectangular region to a buffer object from host memory.
`static int`	`clEnqueueWriteBufferRect(long command_queue, long buffer, boolean blocking_write, org.lwjgl.PointerBuffer buffer_offset, org.lwjgl.PointerBuffer host_offset, org.lwjgl.PointerBuffer region, long buffer_row_pitch, long buffer_slice_pitch, long host_row_pitch, long host_slice_pitch, float[] ptr, org.lwjgl.PointerBuffer event_wait_list, org.lwjgl.PointerBuffer event)` Array version of: `EnqueueWriteBufferRect`
`static int`	`clEnqueueWriteBufferRect(long command_queue, long buffer, boolean blocking_write, org.lwjgl.PointerBuffer buffer_offset, org.lwjgl.PointerBuffer host_offset, org.lwjgl.PointerBuffer region, long buffer_row_pitch, long buffer_slice_pitch, long host_row_pitch, long host_slice_pitch, java.nio.FloatBuffer ptr, org.lwjgl.PointerBuffer event_wait_list, org.lwjgl.PointerBuffer event)` Enqueues a command to write a 2D or 3D rectangular region to a buffer object from host memory.
`static int`	`clEnqueueWriteBufferRect(long command_queue, long buffer, boolean blocking_write, org.lwjgl.PointerBuffer buffer_offset, org.lwjgl.PointerBuffer host_offset, org.lwjgl.PointerBuffer region, long buffer_row_pitch, long buffer_slice_pitch, long host_row_pitch, long host_slice_pitch, int[] ptr, org.lwjgl.PointerBuffer event_wait_list, org.lwjgl.PointerBuffer event)` Array version of: `EnqueueWriteBufferRect`
`static int`	`clEnqueueWriteBufferRect(long command_queue, long buffer, boolean blocking_write, org.lwjgl.PointerBuffer buffer_offset, org.lwjgl.PointerBuffer host_offset, org.lwjgl.PointerBuffer region, long buffer_row_pitch, long buffer_slice_pitch, long host_row_pitch, long host_slice_pitch, java.nio.IntBuffer ptr, org.lwjgl.PointerBuffer event_wait_list, org.lwjgl.PointerBuffer event)` Enqueues a command to write a 2D or 3D rectangular region to a buffer object from host memory.
`static int`	`clEnqueueWriteBufferRect(long command_queue, long buffer, boolean blocking_write, org.lwjgl.PointerBuffer buffer_offset, org.lwjgl.PointerBuffer host_offset, org.lwjgl.PointerBuffer region, long buffer_row_pitch, long buffer_slice_pitch, long host_row_pitch, long host_slice_pitch, short[] ptr, org.lwjgl.PointerBuffer event_wait_list, org.lwjgl.PointerBuffer event)` Array version of: `EnqueueWriteBufferRect`
`static int`	`clEnqueueWriteBufferRect(long command_queue, long buffer, boolean blocking_write, org.lwjgl.PointerBuffer buffer_offset, org.lwjgl.PointerBuffer host_offset, org.lwjgl.PointerBuffer region, long buffer_row_pitch, long buffer_slice_pitch, long host_row_pitch, long host_slice_pitch, java.nio.ShortBuffer ptr, org.lwjgl.PointerBuffer event_wait_list, org.lwjgl.PointerBuffer event)` Enqueues a command to write a 2D or 3D rectangular region to a buffer object from host memory.
`static int`	`clSetEventCallback(long event, int command_exec_callback_type, CLEventCallbackI pfn_notify, long user_data)` Registers a user callback function for a specific command execution status.
`static int`	`clSetMemObjectDestructorCallback(long memobj, CLMemObjectDestructorCallbackI pfn_notify, long user_data)` Registers a user callback function with a memory object.
`static int`	`clSetUserEventStatus(long event, int execution_status)` Sets the execution status of a user event object.
`static long`	`nclCreateSubBuffer(long buffer, long flags, int buffer_create_type, long buffer_create_info, long errcode_ret)` Unsafe version of: `CreateSubBuffer`
`static long`	`nclCreateUserEvent(long context, long errcode_ret)` Unsafe version of: `CreateUserEvent`
`static int`	`nclEnqueueCopyBufferRect(long command_queue, long src_buffer, long dst_buffer, long src_origin, long dst_origin, long region, long src_row_pitch, long src_slice_pitch, long dst_row_pitch, long dst_slice_pitch, int num_events_in_wait_list, long event_wait_list, long event)` Unsafe version of: `EnqueueCopyBufferRect`
`static int`	`nclEnqueueReadBufferRect(long command_queue, long buffer, int blocking_read, long buffer_offset, long host_offset, long region, long buffer_row_pitch, long buffer_slice_pitch, long host_row_pitch, long host_slice_pitch, long ptr, int num_events_in_wait_list, long event_wait_list, long event)` Unsafe version of: `EnqueueReadBufferRect`
`static int`	`nclEnqueueWriteBufferRect(long command_queue, long buffer, int blocking_write, long buffer_offset, long host_offset, long region, long buffer_row_pitch, long buffer_slice_pitch, long host_row_pitch, long host_slice_pitch, long ptr, int num_events_in_wait_list, long event_wait_list, long event)` Unsafe version of: `EnqueueWriteBufferRect`
`static int`	`nclSetEventCallback(long event, int command_exec_callback_type, long pfn_notify, long user_data)` Unsafe version of: `SetEventCallback`
`static int`	`nclSetMemObjectDestructorCallback(long memobj, long pfn_notify, long user_data)` Unsafe version of: `SetMemObjectDestructorCallback`

Methods inherited from class org.lwjgl.opencl.CL10
clBuildProgram, clBuildProgram, clBuildProgram, clCreateBuffer, clCreateBuffer, clCreateBuffer, clCreateBuffer, clCreateBuffer, clCreateBuffer, clCreateBuffer, clCreateBuffer, clCreateBuffer, clCreateBuffer, clCreateBuffer, clCreateCommandQueue, clCreateCommandQueue, clCreateContext, clCreateContext, clCreateContext, clCreateContextFromType, clCreateContextFromType, clCreateImage2D, clCreateImage2D, clCreateImage2D, clCreateImage2D, clCreateImage2D, clCreateImage2D, clCreateImage2D, clCreateImage2D, clCreateImage3D, clCreateImage3D, clCreateImage3D, clCreateImage3D, clCreateImage3D, clCreateImage3D, clCreateImage3D, clCreateImage3D, clCreateKernel, clCreateKernel, clCreateKernel, clCreateKernel, clCreateKernelsInProgram, clCreateKernelsInProgram, clCreateProgramWithBinary, clCreateProgramWithBinary, clCreateProgramWithBinary, clCreateProgramWithBinary, clCreateProgramWithSource, clCreateProgramWithSource, clCreateProgramWithSource, clCreateProgramWithSource, clCreateSampler, clCreateSampler, clEnqueueBarrier, clEnqueueCopyBuffer, clEnqueueCopyBufferToImage, clEnqueueCopyImage, clEnqueueCopyImageToBuffer, clEnqueueMapBuffer, clEnqueueMapBuffer, clEnqueueMapImage, clEnqueueMapImage, clEnqueueMapImage, clEnqueueMapImage, clEnqueueMarker, clEnqueueNativeKernel, clEnqueueNativeKernel, clEnqueueNDRangeKernel, clEnqueueReadBuffer, clEnqueueReadBuffer, clEnqueueReadBuffer, clEnqueueReadBuffer, clEnqueueReadBuffer, clEnqueueReadBuffer, clEnqueueReadBuffer, clEnqueueReadBuffer, clEnqueueReadBuffer, clEnqueueReadImage, clEnqueueReadImage, clEnqueueReadImage, clEnqueueReadImage, clEnqueueReadImage, clEnqueueReadImage, clEnqueueReadImage, clEnqueueReadImage, clEnqueueReadImage, clEnqueueTask, clEnqueueUnmapMemObject, clEnqueueWaitForEvents, clEnqueueWaitForEvents, clEnqueueWriteBuffer, clEnqueueWriteBuffer, clEnqueueWriteBuffer, clEnqueueWriteBuffer, clEnqueueWriteBuffer, clEnqueueWriteBuffer, clEnqueueWriteBuffer, clEnqueueWriteBuffer, clEnqueueWriteBuffer, clEnqueueWriteImage, clEnqueueWriteImage, clEnqueueWriteImage, clEnqueueWriteImage, clEnqueueWriteImage, clEnqueueWriteImage, clEnqueueWriteImage, clEnqueueWriteImage, clEnqueueWriteImage, clFinish, clFlush, clGetCommandQueueInfo, clGetCommandQueueInfo, clGetCommandQueueInfo, clGetCommandQueueInfo, clGetCommandQueueInfo, clGetCommandQueueInfo, clGetContextInfo, clGetContextInfo, clGetContextInfo, clGetContextInfo, clGetDeviceIDs, clGetDeviceIDs, clGetDeviceInfo, clGetDeviceInfo, clGetDeviceInfo, clGetDeviceInfo, clGetDeviceInfo, clGetDeviceInfo, clGetEventInfo, clGetEventInfo, clGetEventInfo, clGetEventInfo, clGetEventProfilingInfo, clGetEventProfilingInfo, clGetEventProfilingInfo, clGetExtensionFunctionAddress, clGetExtensionFunctionAddress, clGetImageInfo, clGetImageInfo, clGetImageInfo, clGetImageInfo, clGetKernelInfo, clGetKernelInfo, clGetKernelInfo, clGetKernelInfo, clGetKernelWorkGroupInfo, clGetKernelWorkGroupInfo, clGetKernelWorkGroupInfo, clGetKernelWorkGroupInfo, clGetKernelWorkGroupInfo, clGetKernelWorkGroupInfo, clGetMemObjectInfo, clGetMemObjectInfo, clGetMemObjectInfo, clGetMemObjectInfo, clGetMemObjectInfo, clGetMemObjectInfo, clGetPlatformIDs, clGetPlatformIDs, clGetPlatformInfo, clGetPlatformInfo, clGetPlatformInfo, clGetProgramBuildInfo, clGetProgramBuildInfo, clGetProgramBuildInfo, clGetProgramBuildInfo, clGetProgramInfo, clGetProgramInfo, clGetProgramInfo, clGetProgramInfo, clGetSamplerInfo, clGetSamplerInfo, clGetSamplerInfo, clGetSamplerInfo, clGetSupportedImageFormats, clGetSupportedImageFormats, clReleaseCommandQueue, clReleaseContext, clReleaseEvent, clReleaseKernel, clReleaseMemObject, clReleaseProgram, clReleaseSampler, clRetainCommandQueue, clRetainContext, clRetainEvent, clRetainKernel, clRetainMemObject, clRetainProgram, clRetainSampler, clSetKernelArg, clSetKernelArg, clSetKernelArg, clSetKernelArg, clSetKernelArg, clSetKernelArg, clSetKernelArg, clSetKernelArg, clSetKernelArg, clSetKernelArg, clSetKernelArg, clSetKernelArg, clSetKernelArg, clSetKernelArg1b, clSetKernelArg1d, clSetKernelArg1f, clSetKernelArg1i, clSetKernelArg1l, clSetKernelArg1p, clSetKernelArg1s, clSetKernelArg2b, clSetKernelArg2d, clSetKernelArg2f, clSetKernelArg2i, clSetKernelArg2l, clSetKernelArg2p, clSetKernelArg2s, clSetKernelArg4b, clSetKernelArg4d, clSetKernelArg4f, clSetKernelArg4i, clSetKernelArg4l, clSetKernelArg4p, clSetKernelArg4s, clUnloadCompiler, clWaitForEvents, clWaitForEvents, nclBuildProgram, nclCreateBuffer, nclCreateCommandQueue, nclCreateContext, nclCreateContextFromType, nclCreateImage2D, nclCreateImage3D, nclCreateKernel, nclCreateKernelsInProgram, nclCreateProgramWithBinary, nclCreateProgramWithSource, nclCreateSampler, nclEnqueueCopyBuffer, nclEnqueueCopyBufferToImage, nclEnqueueCopyImage, nclEnqueueCopyImageToBuffer, nclEnqueueMapBuffer, nclEnqueueMapImage, nclEnqueueMarker, nclEnqueueNativeKernel, nclEnqueueNDRangeKernel, nclEnqueueReadBuffer, nclEnqueueReadImage, nclEnqueueTask, nclEnqueueUnmapMemObject, nclEnqueueWaitForEvents, nclEnqueueWriteBuffer, nclEnqueueWriteImage, nclGetCommandQueueInfo, nclGetContextInfo, nclGetDeviceIDs, nclGetDeviceInfo, nclGetEventInfo, nclGetEventProfilingInfo, nclGetExtensionFunctionAddress, nclGetImageInfo, nclGetKernelInfo, nclGetKernelWorkGroupInfo, nclGetMemObjectInfo, nclGetPlatformIDs, nclGetPlatformInfo, nclGetProgramBuildInfo, nclGetProgramInfo, nclGetSamplerInfo, nclGetSupportedImageFormats, nclSetKernelArg, nclWaitForEvents

Methods inherited from class java.lang.Object
equals, getClass, hashCode, notify, notifyAll, toString, wait, wait, wait

- Field Detail
  - CL_MISALIGNED_SUB_BUFFER_OFFSET
```
public static final int CL_MISALIGNED_SUB_BUFFER_OFFSET
```
    Error Codes.
    
    See Also:
    
    Constant Field Values
  - CL_EXEC_STATUS_ERROR_FOR_EVENTS_IN_WAIT_LIST
```
public static final int CL_EXEC_STATUS_ERROR_FOR_EVENTS_IN_WAIT_LIST
```
    Error Codes.
    
    See Also:
    
    Constant Field Values
  - CL_INVALID_PROPERTY
```
public static final int CL_INVALID_PROPERTY
```
    Error Codes.
    
    See Also:
    
    Constant Field Values
  - CL_VERSION_1_1
```
public static final int CL_VERSION_1_1
```
    OpenCL Version.
    
    See Also:
    
    Constant Field Values
  - CL_DEVICE_PREFERRED_VECTOR_WIDTH_HALF
```
public static final int CL_DEVICE_PREFERRED_VECTOR_WIDTH_HALF
```
    cl_device_info.
    
    See Also:
    
    Constant Field Values
  - CL_DEVICE_HOST_UNIFIED_MEMORY
```
public static final int CL_DEVICE_HOST_UNIFIED_MEMORY
```
    cl_device_info.
    
    See Also:
    
    Constant Field Values
  - CL_DEVICE_NATIVE_VECTOR_WIDTH_CHAR
```
public static final int CL_DEVICE_NATIVE_VECTOR_WIDTH_CHAR
```
    cl_device_info.
    
    See Also:
    
    Constant Field Values
  - CL_DEVICE_NATIVE_VECTOR_WIDTH_SHORT
```
public static final int CL_DEVICE_NATIVE_VECTOR_WIDTH_SHORT
```
    cl_device_info.
    
    See Also:
    
    Constant Field Values
  - CL_DEVICE_NATIVE_VECTOR_WIDTH_INT
```
public static final int CL_DEVICE_NATIVE_VECTOR_WIDTH_INT
```
    cl_device_info.
    
    See Also:
    
    Constant Field Values
  - CL_DEVICE_NATIVE_VECTOR_WIDTH_LONG
```
public static final int CL_DEVICE_NATIVE_VECTOR_WIDTH_LONG
```
    cl_device_info.
    
    See Also:
    
    Constant Field Values
  - CL_DEVICE_NATIVE_VECTOR_WIDTH_FLOAT
```
public static final int CL_DEVICE_NATIVE_VECTOR_WIDTH_FLOAT
```
    cl_device_info.
    
    See Also:
    
    Constant Field Values
  - CL_DEVICE_NATIVE_VECTOR_WIDTH_DOUBLE
```
public static final int CL_DEVICE_NATIVE_VECTOR_WIDTH_DOUBLE
```
    cl_device_info.
    
    See Also:
    
    Constant Field Values
  - CL_DEVICE_NATIVE_VECTOR_WIDTH_HALF
```
public static final int CL_DEVICE_NATIVE_VECTOR_WIDTH_HALF
```
    cl_device_info.
    
    See Also:
    
    Constant Field Values
  - CL_DEVICE_OPENCL_C_VERSION
```
public static final int CL_DEVICE_OPENCL_C_VERSION
```
    cl_device_info.
    
    See Also:
    
    Constant Field Values
  - CL_FP_SOFT_FLOAT
```
public static final int CL_FP_SOFT_FLOAT
```
    cl_device_fp_config - bitfield.
    
    See Also:
    
    Constant Field Values
  - CL_CONTEXT_NUM_DEVICES
```
public static final int CL_CONTEXT_NUM_DEVICES
```
    cl_context_info.
    
    See Also:
    
    Constant Field Values
  - CL_Rx
```
public static final int CL_Rx
```
    cl_channel_order.
    
    See Also:
    
    Constant Field Values
  - CL_RGx
```
public static final int CL_RGx
```
    cl_channel_order.
    
    See Also:
    
    Constant Field Values
  - CL_RGBx
```
public static final int CL_RGBx
```
    cl_channel_order.
    
    See Also:
    
    Constant Field Values
  - CL_MEM_ASSOCIATED_MEMOBJECT
```
public static final int CL_MEM_ASSOCIATED_MEMOBJECT
```
    cl_mem_info.
    
    See Also:
    
    Constant Field Values
  - CL_MEM_OFFSET
```
public static final int CL_MEM_OFFSET
```
    cl_mem_info.
    
    See Also:
    
    Constant Field Values
  - CL_ADDRESS_MIRRORED_REPEAT
```
public static final int CL_ADDRESS_MIRRORED_REPEAT
```
    cl_addressing_mode.
    
    See Also:
    
    Constant Field Values
  - CL_KERNEL_PREFERRED_WORK_GROUP_SIZE_MULTIPLE
```
public static final int CL_KERNEL_PREFERRED_WORK_GROUP_SIZE_MULTIPLE
```
    cl_kernel_work_group_info.
    
    See Also:
    
    Constant Field Values
  - CL_KERNEL_PRIVATE_MEM_SIZE
```
public static final int CL_KERNEL_PRIVATE_MEM_SIZE
```
    cl_kernel_work_group_info.
    
    See Also:
    
    Constant Field Values
  - CL_EVENT_CONTEXT
```
public static final int CL_EVENT_CONTEXT
```
    cl_event_info.
    
    See Also:
    
    Constant Field Values
  - CL_COMMAND_READ_BUFFER_RECT
```
public static final int CL_COMMAND_READ_BUFFER_RECT
```
    cl_command_type.
    
    See Also:
    
    Constant Field Values
  - CL_COMMAND_WRITE_BUFFER_RECT
```
public static final int CL_COMMAND_WRITE_BUFFER_RECT
```
    cl_command_type.
    
    See Also:
    
    Constant Field Values
  - CL_COMMAND_COPY_BUFFER_RECT
```
public static final int CL_COMMAND_COPY_BUFFER_RECT
```
    cl_command_type.
    
    See Also:
    
    Constant Field Values
  - CL_COMMAND_USER
```
public static final int CL_COMMAND_USER
```
    cl_command_type.
    
    See Also:
    
    Constant Field Values
  - CL_BUFFER_CREATE_TYPE_REGION
```
public static final int CL_BUFFER_CREATE_TYPE_REGION
```
    cl_buffer_create_type.
    
    See Also:
    
    Constant Field Values
- Method Detail
  - nclCreateSubBuffer
```
public static long nclCreateSubBuffer(long buffer,
                                      long flags,
                                      int buffer_create_type,
                                      long buffer_create_info,
                                      long errcode_ret)
```
    Unsafe version of: CreateSubBuffer
  - clCreateSubBuffer
```
public static long clCreateSubBuffer(long buffer,
                                     long flags,
                                     int buffer_create_type,
                                     java.nio.ByteBuffer buffer_create_info,
                                     @Nullable
                                     java.nio.IntBuffer errcode_ret)
```
    Creates a new buffer object (referred to as a sub-buffer object) from an existing buffer object.
    NOTE: Concurrent reading from, writing to and copying between both a buffer object and its sub-buffer object(s) is undefined. Concurrent reading from, writing to and copying between overlapping sub-buffer objects created with the same buffer object is undefined. Only reading from both a buffer object and its sub-buffer objects or reading from multiple overlapping sub-buffer objects is defined.
    Parameters:
    
    buffer - a valid buffer object and cannot be a sub-buffer object
    
    flags - a bit-field that is used to specify allocation and usage information about the sub-buffer memory object being created.
    If the MEM_READ_WRITE, MEM_READ_ONLY or MEM_WRITE_ONLY values are not specified in flags, they are inherited from the corresponding memory access qualifers associated with buffer. The MEM_USE_HOST_PTR, MEM_ALLOC_HOST_PTR and MEM_COPY_HOST_PTR values cannot be specified in flags but are inherited from the corresponding memory access qualifiers associated with buffer. If MEM_COPY_HOST_PTR is specified in the memory access qualifier values associated with buffer it does not imply any additional copies when the sub-buffer is created from buffer. If the MEM_HOST_WRITE_ONLY, MEM_HOST_READ_ONLY or MEM_HOST_NO_ACCESS values are not specified in flags, they are inherited from the corresponding memory access qualifiers associated with buffer.
    
    buffer_create_type - the type of buffer object to be created. Must be:
    BUFFER_CREATE_TYPE_REGION
    
    buffer_create_info - details about the buffer object to be created.
    When buffer_create_type is BUFFER_CREATE_TYPE_REGION, then buffer_create_info is a pointer to a CLBufferRegion structure. (origin, size) defines the offset and size in bytes in buffer.
    
    errcode_ret - will return an appropriate error code. If errcode_ret is NULL, no error code is returned.
    
    Returns:
    SUCCESS if the function is executed successfully. Otherwise, it returns one of the following errors in errcode_ret:
    
    INVALID_MEM_OBJECT if buffer is not a valid buffer object or is a sub-buffer object.
    
    INVALID_VALUE if buffer was created with MEM_WRITE_ONLY and flags specifies MEM_READ_WRITE or MEM_READ_ONLY, or if buffer was created with MEM_READ_ONLY and flags specifies MEM_READ_WRITE or MEM_WRITE_ONLY, or if flags specifies MEM_USE_HOST_PTR or MEM_ALLOC_HOST_PTR or MEM_COPY_HOST_PTR.
    
    INVALID_VALUE if buffer was created with MEM_HOST_WRITE_ONLY and flags specify MEM_HOST_READ_ONLY, or if buffer was created with MEM_HOST_READ_ONLY and flags specify MEM_HOST_WRITE_ONLY, or if buffer was created with MEM_HOST_NO_ACCESS and flags specify MEM_HOST_READ_ONLY or MEM_HOST_WRITE_ONLY.
    
    INVALID_VALUE if value specified in buffer_create_type is not valid.
    
    INVALID_VALUE if value(s) specified in buffer_create_info (for a given buffer_create_type) is not valid or if buffer_create_info is NULL.
    
    INVALID_BUFFER_SIZE if size is 0.
    
    MEM_OBJECT_ALLOCATION_FAILURE if there is a failure to allocate memory for sub-buffer object.
    
    OUT_OF_RESOURCES if there is a failure to allocate resources required by the OpenCL implementation on the device.
    
    OUT_OF_HOST_MEMORY if there is a failure to allocate resources required by the OpenCL implementation on the host.
    See Also:
    
    Reference Page
  - nclSetMemObjectDestructorCallback
```
public static int nclSetMemObjectDestructorCallback(long memobj,
                                                    long pfn_notify,
                                                    long user_data)
```
    Unsafe version of: SetMemObjectDestructorCallback
  - clSetMemObjectDestructorCallback
```
public static int clSetMemObjectDestructorCallback(long memobj,
                                                   CLMemObjectDestructorCallbackI pfn_notify,
                                                   long user_data)
```
    Registers a user callback function with a memory object. Each call to clSetMemObjectDestructorCallback registers the specified user callback function on a callback stack associated with memobj. The registered user callback functions are called in the reverse order in which they were registered. The user callback functions are called and then the memory object's resources are freed and the memory object is deleted. This provides a mechanism for the application (and libraries) using memobj to be notified when the memory referenced by host_ptr, specified when the memory object is created and used as the storage bits for the memory object, can be reused or freed.
    Parameters:
    
    memobj - a valid memory object
    
    pfn_notify - the callback function that can be registered by the application. This callback function may be called asynchronously by the OpenCL implementation. It is the application's responsibility to ensure that the callback function is thread-safe.
    
    user_data - will be passed as the user_data argument when pfn_notify is called. user_data can be NULL.
    
    Returns:
    SUCCESS if the function is executed successfully. Otherwise, it returns one of the following errors:
    
    INVALID_MEM_OBJECT if memobj is not a valid memory object.
    
    INVALID_VALUE if pfn_notify is NULL.
    
    OUT_OF_RESOURCES if there is a failure to allocate resources required by the OpenCL implementation on the device.
    
    OUT_OF_HOST_MEMORY if there is a failure to allocate resources required by the OpenCL implementation on the host.
    See Also:
    
    Reference Page
  - nclEnqueueReadBufferRect
```
public static int nclEnqueueReadBufferRect(long command_queue,
                                           long buffer,
                                           int blocking_read,
                                           long buffer_offset,
                                           long host_offset,
                                           long region,
                                           long buffer_row_pitch,
                                           long buffer_slice_pitch,
                                           long host_row_pitch,
                                           long host_slice_pitch,
                                           long ptr,
                                           int num_events_in_wait_list,
                                           long event_wait_list,
                                           long event)
```
    Unsafe version of: EnqueueReadBufferRect
    
    Parameters:
    
    num_events_in_wait_list - the number of events in event_wait_list
  - clEnqueueReadBufferRect
```
public static int clEnqueueReadBufferRect(long command_queue,
                                          long buffer,
                                          boolean blocking_read,
                                          org.lwjgl.PointerBuffer buffer_offset,
                                          org.lwjgl.PointerBuffer host_offset,
                                          org.lwjgl.PointerBuffer region,
                                          long buffer_row_pitch,
                                          long buffer_slice_pitch,
                                          long host_row_pitch,
                                          long host_slice_pitch,
                                          java.nio.ByteBuffer ptr,
                                          @Nullable
                                          org.lwjgl.PointerBuffer event_wait_list,
                                          @Nullable
                                          org.lwjgl.PointerBuffer event)
```
    Enqueues a command to read a 2D or 3D rectangular region from a buffer object to host memory.
    Calling clEnqueueReadBufferRect to read a region of the buffer object with the ptr argument value set to host_ptr and host_origin, buffer_origin values are the same, where host_ptr is a pointer to the memory region specified when the buffer object being read is created with MEM_USE_HOST_PTR, must meet the following requirements in order to avoid undefined behavior:
    - All commands that use this buffer object or a memory object (buffer or image) created from this buffer object have finished execution before the read command begins execution.
    - The buffer object or memory objects created from this buffer object are not mapped.
    - The buffer object or memory objects created from this buffer object are not used by any command-queue until the read command has finished execution.
    Parameters:
    
    command_queue - the command-queue in which the read command will be queued. command_queue and buffer must be created with the same OpenCL context.
    
    buffer - a valid buffer object
    
    blocking_read - indicates if the read operation is blocking or nonblocking.
    If blocking_read is TRUE i.e. the read command is blocking, clEnqueueReadBufferRect does not return until the buffer data has been read and copied into memory pointed to by ptr.
    
    If blocking_read is FALSE i.e. the read command is non-blocking, clEnqueueReadBufferRect queues a non-blocking read command and returns. The contents of the buffer that ptr points to cannot be used until the read command has completed. The event argument returns an event object which can be used to query the execution status of the read command. When the read command has completed, the contents of the buffer that ptr points to can be used by the application.
    
    buffer_offset - the (x, y, z) offset in the memory region associated with buffer. For a 2D rectangle region, the z value given by buffer_origin[2] should be 0. The offset in bytes is computed as buffer_origin[2] * buffer_slice_pitch + buffer_origin[1] * buffer_row_pitch + buffer_origin[0].
    
    host_offset - the (x, y, z) offset in the memory region pointed to by ptr. For a 2D rectangle region, the z value given by host_origin[2] should be 0. The offset in bytes is computed as host_origin[2] * host_slice_pitch + host_origin[1] * host_row_pitch + host_origin[0].
    
    region - the (width in bytes, height in rows, depth in slices) of the 2D or 3D rectangle being read or written. For a 2D rectangle copy, the depth value given by region[2] should be 1. The values in region cannot be 0.
    
    buffer_row_pitch - the length of each row in bytes to be used for the memory region associated with buffer. If buffer_row_pitch is 0, buffer_row_pitch is computed as region[0].
    
    buffer_slice_pitch - the length of each 2D slice in bytes to be used for the memory region associated with buffer. If buffer_slice_pitch is 0, buffer_slice_pitch is computed as region[1] * buffer_row_pitch.
    
    host_row_pitch - the length of each row in bytes to be used for the memory region pointed to by ptr. If host_row_pitch is 0, host_row_pitch is computed as region[0].
    
    host_slice_pitch - the length of each 2D slice in bytes to be used for the memory region pointed to by ptr. If host_slice_pitch is 0, host_slice_pitch is computed as region[1] * host_row_pitch.
    
    ptr - the pointer to buffer in host memory where data is to be read into
    
    event_wait_list - a list of events that need to complete before this particular command can be executed. If event_wait_list is NULL, then this particular command does not wait on any event to complete. The events specified in event_wait_list act as synchronization points. The context associated with events in event_wait_list and command_queue must be the same.
    
    event - Returns an event object that identifies this particular command and can be used to query or queue a wait for this particular command to complete. event can be NULL in which case it will not be possible for the application to query the status of this command or queue a wait for this command to complete. If the event_wait_list and the event arguments are not NULL, the event argument should not refer to an element of the event_wait_list array.
    
    Returns:
    SUCCESS if the function is executed successfully. Otherwise, it returns one of the following errors:
    
    INVALID_COMMAND_QUEUE if command_queue is not a valid command-queue.
    
    INVALID_CONTEXT if the context associated with command_queue and buffer are not the same or if the context associated with command_queue and events in event_wait_list are not the same.
    
    INVALID_MEM_OBJECT if buffer is not a valid buffer object.
    
    INVALID_VALUE if the region being read specified by (buffer_origin, region, buffer_row_pitch, buffer_slice_pitch) is out of bounds.
    
    INVALID_VALUE if ptr is a NULL value.
    
    INVALID_VALUE if any region array element is 0.
    
    INVALID_VALUE if buffer_row_pitch is not 0 and is less than region[0].
    
    INVALID_VALUE if host_row_pitch is not 0 and is less than region[0].
    
    INVALID_VALUE if buffer_slice_pitch is not 0 and is less than region[1] * buffer_row_pitch and not a multiple of buffer_row_pitch.
    
    INVALID_VALUE if host_slice_pitch is not 0 and is less than region[1] * host_row_pitch and not a multiple of host_row_pitch.
    
    INVALID_EVENT_WAIT_LIST if event_wait_list is NULL and num_events_in_wait_list > 0, or event_wait_list is not NULL and num_events_in_wait_list is 0, or if event objects in event_wait_list are not valid events.
    
    MISALIGNED_SUB_BUFFER_OFFSET if buffer is a sub-buffer object and offset specified when the sub-buffer object is created is not aligned to DEVICE_MEM_BASE_ADDR_ALIGN value for device associated with queue.
    
    EXEC_STATUS_ERROR_FOR_EVENTS_IN_WAIT_LIST if the read operation is blocking and the execution status of any of the events in event_wait_list is a negative integer value.
    
    MEM_OBJECT_ALLOCATION_FAILURE if there is a failure to allocate memory for data store associated with buffer.
    
    INVALID_OPERATION if clEnqueueReadBufferRect is called on buffer which has been created with MEM_HOST_WRITE_ONLY or MEM_HOST_NO_ACCESS.
    
    OUT_OF_RESOURCES if there is a failure to allocate resources required by the OpenCL implementation on the device.
    
    OUT_OF_HOST_MEMORY if there is a failure to allocate resources required by the OpenCL implementation on the host.
    See Also:
    
    Reference Page
  - clEnqueueReadBufferRect
```
public static int clEnqueueReadBufferRect(long command_queue,
                                          long buffer,
                                          boolean blocking_read,
                                          org.lwjgl.PointerBuffer buffer_offset,
                                          org.lwjgl.PointerBuffer host_offset,
                                          org.lwjgl.PointerBuffer region,
                                          long buffer_row_pitch,
                                          long buffer_slice_pitch,
                                          long host_row_pitch,
                                          long host_slice_pitch,
                                          java.nio.ShortBuffer ptr,
                                          @Nullable
                                          org.lwjgl.PointerBuffer event_wait_list,
                                          @Nullable
                                          org.lwjgl.PointerBuffer event)
```
    Enqueues a command to read a 2D or 3D rectangular region from a buffer object to host memory.
    Calling clEnqueueReadBufferRect to read a region of the buffer object with the ptr argument value set to host_ptr and host_origin, buffer_origin values are the same, where host_ptr is a pointer to the memory region specified when the buffer object being read is created with MEM_USE_HOST_PTR, must meet the following requirements in order to avoid undefined behavior:
    - All commands that use this buffer object or a memory object (buffer or image) created from this buffer object have finished execution before the read command begins execution.
    - The buffer object or memory objects created from this buffer object are not mapped.
    - The buffer object or memory objects created from this buffer object are not used by any command-queue until the read command has finished execution.
    Parameters:
    
    command_queue - the command-queue in which the read command will be queued. command_queue and buffer must be created with the same OpenCL context.
    
    buffer - a valid buffer object
    
    blocking_read - indicates if the read operation is blocking or nonblocking.
    If blocking_read is TRUE i.e. the read command is blocking, clEnqueueReadBufferRect does not return until the buffer data has been read and copied into memory pointed to by ptr.
    
    If blocking_read is FALSE i.e. the read command is non-blocking, clEnqueueReadBufferRect queues a non-blocking read command and returns. The contents of the buffer that ptr points to cannot be used until the read command has completed. The event argument returns an event object which can be used to query the execution status of the read command. When the read command has completed, the contents of the buffer that ptr points to can be used by the application.
    
    buffer_offset - the (x, y, z) offset in the memory region associated with buffer. For a 2D rectangle region, the z value given by buffer_origin[2] should be 0. The offset in bytes is computed as buffer_origin[2] * buffer_slice_pitch + buffer_origin[1] * buffer_row_pitch + buffer_origin[0].
    
    host_offset - the (x, y, z) offset in the memory region pointed to by ptr. For a 2D rectangle region, the z value given by host_origin[2] should be 0. The offset in bytes is computed as host_origin[2] * host_slice_pitch + host_origin[1] * host_row_pitch + host_origin[0].
    
    region - the (width in bytes, height in rows, depth in slices) of the 2D or 3D rectangle being read or written. For a 2D rectangle copy, the depth value given by region[2] should be 1. The values in region cannot be 0.
    
    buffer_row_pitch - the length of each row in bytes to be used for the memory region associated with buffer. If buffer_row_pitch is 0, buffer_row_pitch is computed as region[0].
    
    buffer_slice_pitch - the length of each 2D slice in bytes to be used for the memory region associated with buffer. If buffer_slice_pitch is 0, buffer_slice_pitch is computed as region[1] * buffer_row_pitch.
    
    host_row_pitch - the length of each row in bytes to be used for the memory region pointed to by ptr. If host_row_pitch is 0, host_row_pitch is computed as region[0].
    
    host_slice_pitch - the length of each 2D slice in bytes to be used for the memory region pointed to by ptr. If host_slice_pitch is 0, host_slice_pitch is computed as region[1] * host_row_pitch.
    
    ptr - the pointer to buffer in host memory where data is to be read into
    
    event_wait_list - a list of events that need to complete before this particular command can be executed. If event_wait_list is NULL, then this particular command does not wait on any event to complete. The events specified in event_wait_list act as synchronization points. The context associated with events in event_wait_list and command_queue must be the same.
    
    event - Returns an event object that identifies this particular command and can be used to query or queue a wait for this particular command to complete. event can be NULL in which case it will not be possible for the application to query the status of this command or queue a wait for this command to complete. If the event_wait_list and the event arguments are not NULL, the event argument should not refer to an element of the event_wait_list array.
    
    Returns:
    SUCCESS if the function is executed successfully. Otherwise, it returns one of the following errors:
    
    INVALID_COMMAND_QUEUE if command_queue is not a valid command-queue.
    
    INVALID_CONTEXT if the context associated with command_queue and buffer are not the same or if the context associated with command_queue and events in event_wait_list are not the same.
    
    INVALID_MEM_OBJECT if buffer is not a valid buffer object.
    
    INVALID_VALUE if the region being read specified by (buffer_origin, region, buffer_row_pitch, buffer_slice_pitch) is out of bounds.
    
    INVALID_VALUE if ptr is a NULL value.
    
    INVALID_VALUE if any region array element is 0.
    
    INVALID_VALUE if buffer_row_pitch is not 0 and is less than region[0].
    
    INVALID_VALUE if host_row_pitch is not 0 and is less than region[0].
    
    INVALID_VALUE if buffer_slice_pitch is not 0 and is less than region[1] * buffer_row_pitch and not a multiple of buffer_row_pitch.
    
    INVALID_VALUE if host_slice_pitch is not 0 and is less than region[1] * host_row_pitch and not a multiple of host_row_pitch.
    
    INVALID_EVENT_WAIT_LIST if event_wait_list is NULL and num_events_in_wait_list > 0, or event_wait_list is not NULL and num_events_in_wait_list is 0, or if event objects in event_wait_list are not valid events.
    
    MISALIGNED_SUB_BUFFER_OFFSET if buffer is a sub-buffer object and offset specified when the sub-buffer object is created is not aligned to DEVICE_MEM_BASE_ADDR_ALIGN value for device associated with queue.
    
    EXEC_STATUS_ERROR_FOR_EVENTS_IN_WAIT_LIST if the read operation is blocking and the execution status of any of the events in event_wait_list is a negative integer value.
    
    MEM_OBJECT_ALLOCATION_FAILURE if there is a failure to allocate memory for data store associated with buffer.
    
    INVALID_OPERATION if clEnqueueReadBufferRect is called on buffer which has been created with MEM_HOST_WRITE_ONLY or MEM_HOST_NO_ACCESS.
    
    OUT_OF_RESOURCES if there is a failure to allocate resources required by the OpenCL implementation on the device.
    
    OUT_OF_HOST_MEMORY if there is a failure to allocate resources required by the OpenCL implementation on the host.
    See Also:
    
    Reference Page
  - clEnqueueReadBufferRect
```
public static int clEnqueueReadBufferRect(long command_queue,
                                          long buffer,
                                          boolean blocking_read,
                                          org.lwjgl.PointerBuffer buffer_offset,
                                          org.lwjgl.PointerBuffer host_offset,
                                          org.lwjgl.PointerBuffer region,
                                          long buffer_row_pitch,
                                          long buffer_slice_pitch,
                                          long host_row_pitch,
                                          long host_slice_pitch,
                                          java.nio.IntBuffer ptr,
                                          @Nullable
                                          org.lwjgl.PointerBuffer event_wait_list,
                                          @Nullable
                                          org.lwjgl.PointerBuffer event)
```
    Enqueues a command to read a 2D or 3D rectangular region from a buffer object to host memory.
    Calling clEnqueueReadBufferRect to read a region of the buffer object with the ptr argument value set to host_ptr and host_origin, buffer_origin values are the same, where host_ptr is a pointer to the memory region specified when the buffer object being read is created with MEM_USE_HOST_PTR, must meet the following requirements in order to avoid undefined behavior:
    - All commands that use this buffer object or a memory object (buffer or image) created from this buffer object have finished execution before the read command begins execution.
    - The buffer object or memory objects created from this buffer object are not mapped.
    - The buffer object or memory objects created from this buffer object are not used by any command-queue until the read command has finished execution.
    Parameters:
    
    command_queue - the command-queue in which the read command will be queued. command_queue and buffer must be created with the same OpenCL context.
    
    buffer - a valid buffer object
    
    blocking_read - indicates if the read operation is blocking or nonblocking.
    If blocking_read is TRUE i.e. the read command is blocking, clEnqueueReadBufferRect does not return until the buffer data has been read and copied into memory pointed to by ptr.
    
    If blocking_read is FALSE i.e. the read command is non-blocking, clEnqueueReadBufferRect queues a non-blocking read command and returns. The contents of the buffer that ptr points to cannot be used until the read command has completed. The event argument returns an event object which can be used to query the execution status of the read command. When the read command has completed, the contents of the buffer that ptr points to can be used by the application.
    
    buffer_offset - the (x, y, z) offset in the memory region associated with buffer. For a 2D rectangle region, the z value given by buffer_origin[2] should be 0. The offset in bytes is computed as buffer_origin[2] * buffer_slice_pitch + buffer_origin[1] * buffer_row_pitch + buffer_origin[0].
    
    host_offset - the (x, y, z) offset in the memory region pointed to by ptr. For a 2D rectangle region, the z value given by host_origin[2] should be 0. The offset in bytes is computed as host_origin[2] * host_slice_pitch + host_origin[1] * host_row_pitch + host_origin[0].
    
    region - the (width in bytes, height in rows, depth in slices) of the 2D or 3D rectangle being read or written. For a 2D rectangle copy, the depth value given by region[2] should be 1. The values in region cannot be 0.
    
    buffer_row_pitch - the length of each row in bytes to be used for the memory region associated with buffer. If buffer_row_pitch is 0, buffer_row_pitch is computed as region[0].
    
    buffer_slice_pitch - the length of each 2D slice in bytes to be used for the memory region associated with buffer. If buffer_slice_pitch is 0, buffer_slice_pitch is computed as region[1] * buffer_row_pitch.
    
    host_row_pitch - the length of each row in bytes to be used for the memory region pointed to by ptr. If host_row_pitch is 0, host_row_pitch is computed as region[0].
    
    host_slice_pitch - the length of each 2D slice in bytes to be used for the memory region pointed to by ptr. If host_slice_pitch is 0, host_slice_pitch is computed as region[1] * host_row_pitch.
    
    ptr - the pointer to buffer in host memory where data is to be read into
    
    event_wait_list - a list of events that need to complete before this particular command can be executed. If event_wait_list is NULL, then this particular command does not wait on any event to complete. The events specified in event_wait_list act as synchronization points. The context associated with events in event_wait_list and command_queue must be the same.
    
    event - Returns an event object that identifies this particular command and can be used to query or queue a wait for this particular command to complete. event can be NULL in which case it will not be possible for the application to query the status of this command or queue a wait for this command to complete. If the event_wait_list and the event arguments are not NULL, the event argument should not refer to an element of the event_wait_list array.
    
    Returns:
    SUCCESS if the function is executed successfully. Otherwise, it returns one of the following errors:
    
    INVALID_COMMAND_QUEUE if command_queue is not a valid command-queue.
    
    INVALID_CONTEXT if the context associated with command_queue and buffer are not the same or if the context associated with command_queue and events in event_wait_list are not the same.
    
    INVALID_MEM_OBJECT if buffer is not a valid buffer object.
    
    INVALID_VALUE if the region being read specified by (buffer_origin, region, buffer_row_pitch, buffer_slice_pitch) is out of bounds.
    
    INVALID_VALUE if ptr is a NULL value.
    
    INVALID_VALUE if any region array element is 0.
    
    INVALID_VALUE if buffer_row_pitch is not 0 and is less than region[0].
    
    INVALID_VALUE if host_row_pitch is not 0 and is less than region[0].
    
    INVALID_VALUE if buffer_slice_pitch is not 0 and is less than region[1] * buffer_row_pitch and not a multiple of buffer_row_pitch.
    
    INVALID_VALUE if host_slice_pitch is not 0 and is less than region[1] * host_row_pitch and not a multiple of host_row_pitch.
    
    INVALID_EVENT_WAIT_LIST if event_wait_list is NULL and num_events_in_wait_list > 0, or event_wait_list is not NULL and num_events_in_wait_list is 0, or if event objects in event_wait_list are not valid events.
    
    MISALIGNED_SUB_BUFFER_OFFSET if buffer is a sub-buffer object and offset specified when the sub-buffer object is created is not aligned to DEVICE_MEM_BASE_ADDR_ALIGN value for device associated with queue.
    
    EXEC_STATUS_ERROR_FOR_EVENTS_IN_WAIT_LIST if the read operation is blocking and the execution status of any of the events in event_wait_list is a negative integer value.
    
    MEM_OBJECT_ALLOCATION_FAILURE if there is a failure to allocate memory for data store associated with buffer.
    
    INVALID_OPERATION if clEnqueueReadBufferRect is called on buffer which has been created with MEM_HOST_WRITE_ONLY or MEM_HOST_NO_ACCESS.
    
    OUT_OF_RESOURCES if there is a failure to allocate resources required by the OpenCL implementation on the device.
    
    OUT_OF_HOST_MEMORY if there is a failure to allocate resources required by the OpenCL implementation on the host.
    See Also:
    
    Reference Page
  - clEnqueueReadBufferRect
```
public static int clEnqueueReadBufferRect(long command_queue,
                                          long buffer,
                                          boolean blocking_read,
                                          org.lwjgl.PointerBuffer buffer_offset,
                                          org.lwjgl.PointerBuffer host_offset,
                                          org.lwjgl.PointerBuffer region,
                                          long buffer_row_pitch,
                                          long buffer_slice_pitch,
                                          long host_row_pitch,
                                          long host_slice_pitch,
                                          java.nio.FloatBuffer ptr,
                                          @Nullable
                                          org.lwjgl.PointerBuffer event_wait_list,
                                          @Nullable
                                          org.lwjgl.PointerBuffer event)
```
    Enqueues a command to read a 2D or 3D rectangular region from a buffer object to host memory.
    Calling clEnqueueReadBufferRect to read a region of the buffer object with the ptr argument value set to host_ptr and host_origin, buffer_origin values are the same, where host_ptr is a pointer to the memory region specified when the buffer object being read is created with MEM_USE_HOST_PTR, must meet the following requirements in order to avoid undefined behavior:
    - All commands that use this buffer object or a memory object (buffer or image) created from this buffer object have finished execution before the read command begins execution.
    - The buffer object or memory objects created from this buffer object are not mapped.
    - The buffer object or memory objects created from this buffer object are not used by any command-queue until the read command has finished execution.
    Parameters:
    
    command_queue - the command-queue in which the read command will be queued. command_queue and buffer must be created with the same OpenCL context.
    
    buffer - a valid buffer object
    
    blocking_read - indicates if the read operation is blocking or nonblocking.
    If blocking_read is TRUE i.e. the read command is blocking, clEnqueueReadBufferRect does not return until the buffer data has been read and copied into memory pointed to by ptr.
    
    If blocking_read is FALSE i.e. the read command is non-blocking, clEnqueueReadBufferRect queues a non-blocking read command and returns. The contents of the buffer that ptr points to cannot be used until the read command has completed. The event argument returns an event object which can be used to query the execution status of the read command. When the read command has completed, the contents of the buffer that ptr points to can be used by the application.
    
    buffer_offset - the (x, y, z) offset in the memory region associated with buffer. For a 2D rectangle region, the z value given by buffer_origin[2] should be 0. The offset in bytes is computed as buffer_origin[2] * buffer_slice_pitch + buffer_origin[1] * buffer_row_pitch + buffer_origin[0].
    
    host_offset - the (x, y, z) offset in the memory region pointed to by ptr. For a 2D rectangle region, the z value given by host_origin[2] should be 0. The offset in bytes is computed as host_origin[2] * host_slice_pitch + host_origin[1] * host_row_pitch + host_origin[0].
    
    region - the (width in bytes, height in rows, depth in slices) of the 2D or 3D rectangle being read or written. For a 2D rectangle copy, the depth value given by region[2] should be 1. The values in region cannot be 0.
    
    buffer_row_pitch - the length of each row in bytes to be used for the memory region associated with buffer. If buffer_row_pitch is 0, buffer_row_pitch is computed as region[0].
    
    buffer_slice_pitch - the length of each 2D slice in bytes to be used for the memory region associated with buffer. If buffer_slice_pitch is 0, buffer_slice_pitch is computed as region[1] * buffer_row_pitch.
    
    host_row_pitch - the length of each row in bytes to be used for the memory region pointed to by ptr. If host_row_pitch is 0, host_row_pitch is computed as region[0].
    
    host_slice_pitch - the length of each 2D slice in bytes to be used for the memory region pointed to by ptr. If host_slice_pitch is 0, host_slice_pitch is computed as region[1] * host_row_pitch.
    
    ptr - the pointer to buffer in host memory where data is to be read into
    
    event_wait_list - a list of events that need to complete before this particular command can be executed. If event_wait_list is NULL, then this particular command does not wait on any event to complete. The events specified in event_wait_list act as synchronization points. The context associated with events in event_wait_list and command_queue must be the same.
    
    event - Returns an event object that identifies this particular command and can be used to query or queue a wait for this particular command to complete. event can be NULL in which case it will not be possible for the application to query the status of this command or queue a wait for this command to complete. If the event_wait_list and the event arguments are not NULL, the event argument should not refer to an element of the event_wait_list array.
    
    Returns:
    SUCCESS if the function is executed successfully. Otherwise, it returns one of the following errors:
    
    INVALID_COMMAND_QUEUE if command_queue is not a valid command-queue.
    
    INVALID_CONTEXT if the context associated with command_queue and buffer are not the same or if the context associated with command_queue and events in event_wait_list are not the same.
    
    INVALID_MEM_OBJECT if buffer is not a valid buffer object.
    
    INVALID_VALUE if the region being read specified by (buffer_origin, region, buffer_row_pitch, buffer_slice_pitch) is out of bounds.
    
    INVALID_VALUE if ptr is a NULL value.
    
    INVALID_VALUE if any region array element is 0.
    
    INVALID_VALUE if buffer_row_pitch is not 0 and is less than region[0].
    
    INVALID_VALUE if host_row_pitch is not 0 and is less than region[0].
    
    INVALID_VALUE if buffer_slice_pitch is not 0 and is less than region[1] * buffer_row_pitch and not a multiple of buffer_row_pitch.
    
    INVALID_VALUE if host_slice_pitch is not 0 and is less than region[1] * host_row_pitch and not a multiple of host_row_pitch.
    
    INVALID_EVENT_WAIT_LIST if event_wait_list is NULL and num_events_in_wait_list > 0, or event_wait_list is not NULL and num_events_in_wait_list is 0, or if event objects in event_wait_list are not valid events.
    
    MISALIGNED_SUB_BUFFER_OFFSET if buffer is a sub-buffer object and offset specified when the sub-buffer object is created is not aligned to DEVICE_MEM_BASE_ADDR_ALIGN value for device associated with queue.
    
    EXEC_STATUS_ERROR_FOR_EVENTS_IN_WAIT_LIST if the read operation is blocking and the execution status of any of the events in event_wait_list is a negative integer value.
    
    MEM_OBJECT_ALLOCATION_FAILURE if there is a failure to allocate memory for data store associated with buffer.
    
    INVALID_OPERATION if clEnqueueReadBufferRect is called on buffer which has been created with MEM_HOST_WRITE_ONLY or MEM_HOST_NO_ACCESS.
    
    OUT_OF_RESOURCES if there is a failure to allocate resources required by the OpenCL implementation on the device.
    
    OUT_OF_HOST_MEMORY if there is a failure to allocate resources required by the OpenCL implementation on the host.
    See Also:
    
    Reference Page
  - clEnqueueReadBufferRect
```
public static int clEnqueueReadBufferRect(long command_queue,
                                          long buffer,
                                          boolean blocking_read,
                                          org.lwjgl.PointerBuffer buffer_offset,
                                          org.lwjgl.PointerBuffer host_offset,
                                          org.lwjgl.PointerBuffer region,
                                          long buffer_row_pitch,
                                          long buffer_slice_pitch,
                                          long host_row_pitch,
                                          long host_slice_pitch,
                                          java.nio.DoubleBuffer ptr,
                                          @Nullable
                                          org.lwjgl.PointerBuffer event_wait_list,
                                          @Nullable
                                          org.lwjgl.PointerBuffer event)
```
    Enqueues a command to read a 2D or 3D rectangular region from a buffer object to host memory.
    Calling clEnqueueReadBufferRect to read a region of the buffer object with the ptr argument value set to host_ptr and host_origin, buffer_origin values are the same, where host_ptr is a pointer to the memory region specified when the buffer object being read is created with MEM_USE_HOST_PTR, must meet the following requirements in order to avoid undefined behavior:
    - All commands that use this buffer object or a memory object (buffer or image) created from this buffer object have finished execution before the read command begins execution.
    - The buffer object or memory objects created from this buffer object are not mapped.
    - The buffer object or memory objects created from this buffer object are not used by any command-queue until the read command has finished execution.
    Parameters:
    
    command_queue - the command-queue in which the read command will be queued. command_queue and buffer must be created with the same OpenCL context.
    
    buffer - a valid buffer object
    
    blocking_read - indicates if the read operation is blocking or nonblocking.
    If blocking_read is TRUE i.e. the read command is blocking, clEnqueueReadBufferRect does not return until the buffer data has been read and copied into memory pointed to by ptr.
    
    If blocking_read is FALSE i.e. the read command is non-blocking, clEnqueueReadBufferRect queues a non-blocking read command and returns. The contents of the buffer that ptr points to cannot be used until the read command has completed. The event argument returns an event object which can be used to query the execution status of the read command. When the read command has completed, the contents of the buffer that ptr points to can be used by the application.
    
    buffer_offset - the (x, y, z) offset in the memory region associated with buffer. For a 2D rectangle region, the z value given by buffer_origin[2] should be 0. The offset in bytes is computed as buffer_origin[2] * buffer_slice_pitch + buffer_origin[1] * buffer_row_pitch + buffer_origin[0].
    
    host_offset - the (x, y, z) offset in the memory region pointed to by ptr. For a 2D rectangle region, the z value given by host_origin[2] should be 0. The offset in bytes is computed as host_origin[2] * host_slice_pitch + host_origin[1] * host_row_pitch + host_origin[0].
    
    region - the (width in bytes, height in rows, depth in slices) of the 2D or 3D rectangle being read or written. For a 2D rectangle copy, the depth value given by region[2] should be 1. The values in region cannot be 0.
    
    buffer_row_pitch - the length of each row in bytes to be used for the memory region associated with buffer. If buffer_row_pitch is 0, buffer_row_pitch is computed as region[0].
    
    buffer_slice_pitch - the length of each 2D slice in bytes to be used for the memory region associated with buffer. If buffer_slice_pitch is 0, buffer_slice_pitch is computed as region[1] * buffer_row_pitch.
    
    host_row_pitch - the length of each row in bytes to be used for the memory region pointed to by ptr. If host_row_pitch is 0, host_row_pitch is computed as region[0].
    
    host_slice_pitch - the length of each 2D slice in bytes to be used for the memory region pointed to by ptr. If host_slice_pitch is 0, host_slice_pitch is computed as region[1] * host_row_pitch.
    
    ptr - the pointer to buffer in host memory where data is to be read into
    
    event_wait_list - a list of events that need to complete before this particular command can be executed. If event_wait_list is NULL, then this particular command does not wait on any event to complete. The events specified in event_wait_list act as synchronization points. The context associated with events in event_wait_list and command_queue must be the same.
    
    event - Returns an event object that identifies this particular command and can be used to query or queue a wait for this particular command to complete. event can be NULL in which case it will not be possible for the application to query the status of this command or queue a wait for this command to complete. If the event_wait_list and the event arguments are not NULL, the event argument should not refer to an element of the event_wait_list array.
    
    Returns:
    SUCCESS if the function is executed successfully. Otherwise, it returns one of the following errors:
    
    INVALID_COMMAND_QUEUE if command_queue is not a valid command-queue.
    
    INVALID_CONTEXT if the context associated with command_queue and buffer are not the same or if the context associated with command_queue and events in event_wait_list are not the same.
    
    INVALID_MEM_OBJECT if buffer is not a valid buffer object.
    
    INVALID_VALUE if the region being read specified by (buffer_origin, region, buffer_row_pitch, buffer_slice_pitch) is out of bounds.
    
    INVALID_VALUE if ptr is a NULL value.
    
    INVALID_VALUE if any region array element is 0.
    
    INVALID_VALUE if buffer_row_pitch is not 0 and is less than region[0].
    
    INVALID_VALUE if host_row_pitch is not 0 and is less than region[0].
    
    INVALID_VALUE if buffer_slice_pitch is not 0 and is less than region[1] * buffer_row_pitch and not a multiple of buffer_row_pitch.
    
    INVALID_VALUE if host_slice_pitch is not 0 and is less than region[1] * host_row_pitch and not a multiple of host_row_pitch.
    
    INVALID_EVENT_WAIT_LIST if event_wait_list is NULL and num_events_in_wait_list > 0, or event_wait_list is not NULL and num_events_in_wait_list is 0, or if event objects in event_wait_list are not valid events.
    
    MISALIGNED_SUB_BUFFER_OFFSET if buffer is a sub-buffer object and offset specified when the sub-buffer object is created is not aligned to DEVICE_MEM_BASE_ADDR_ALIGN value for device associated with queue.
    
    EXEC_STATUS_ERROR_FOR_EVENTS_IN_WAIT_LIST if the read operation is blocking and the execution status of any of the events in event_wait_list is a negative integer value.
    
    MEM_OBJECT_ALLOCATION_FAILURE if there is a failure to allocate memory for data store associated with buffer.
    
    INVALID_OPERATION if clEnqueueReadBufferRect is called on buffer which has been created with MEM_HOST_WRITE_ONLY or MEM_HOST_NO_ACCESS.
    
    OUT_OF_RESOURCES if there is a failure to allocate resources required by the OpenCL implementation on the device.
    
    OUT_OF_HOST_MEMORY if there is a failure to allocate resources required by the OpenCL implementation on the host.
    See Also:
    
    Reference Page
  - nclEnqueueWriteBufferRect
```
public static int nclEnqueueWriteBufferRect(long command_queue,
                                            long buffer,
                                            int blocking_write,
                                            long buffer_offset,
                                            long host_offset,
                                            long region,
                                            long buffer_row_pitch,
                                            long buffer_slice_pitch,
                                            long host_row_pitch,
                                            long host_slice_pitch,
                                            long ptr,
                                            int num_events_in_wait_list,
                                            long event_wait_list,
                                            long event)
```
    Unsafe version of: EnqueueWriteBufferRect
    
    Parameters:
    
    num_events_in_wait_list - the number of events in event_wait_list
  - clEnqueueWriteBufferRect
```
public static int clEnqueueWriteBufferRect(long command_queue,
                                           long buffer,
                                           boolean blocking_write,
                                           org.lwjgl.PointerBuffer buffer_offset,
                                           org.lwjgl.PointerBuffer host_offset,
                                           org.lwjgl.PointerBuffer region,
                                           long buffer_row_pitch,
                                           long buffer_slice_pitch,
                                           long host_row_pitch,
                                           long host_slice_pitch,
                                           java.nio.ByteBuffer ptr,
                                           @Nullable
                                           org.lwjgl.PointerBuffer event_wait_list,
                                           @Nullable
                                           org.lwjgl.PointerBuffer event)
```
    Enqueues a command to write a 2D or 3D rectangular region to a buffer object from host memory.
    Calling clEnqueueWriteBufferRect to update the latest bits in a region of the buffer object with the ptr argument value set to host_ptr and host_origin, buffer_origin values are the same, where host_ptr is a pointer to the memory region specified when the buffer object being written is created with MEM_USE_HOST_PTR, must meet the following requirements in order to avoid undefined behavior:
    - The host memory region given by (buffer_origin region) contains the latest bits when the enqueued write command begins execution.
    - The buffer object or memory objects created from this buffer object are not mapped.
    - The buffer object or memory objects created from this buffer object are not used by any command-queue until the write command has finished execution.
    Parameters:
    
    command_queue - the command-queue in which the write command will be queued. command_queue and buffer must be created with the same OpenCL context.
    
    buffer - a valid buffer object
    
    blocking_write - indicates if the write operation is blocking or nonblocking.
    If blocking_write is TRUE, the OpenCL implementation copies the data referred to by ptr and enqueues the write operation in the command-queue. The memory pointed to by ptr can be reused by the application after the clEnqueueWriteBufferRect call returns.
    
    If blocking_write is FALSE, the OpenCL implementation will use ptr to perform a non-blocking write. As the write is non-blocking the implementation can return immediately. The memory pointed to by ptr cannot be reused by the application after the call returns. The event argument returns an event object which can be used to query the execution status of the write command. When the write command has completed, the memory pointed to by ptr can then be reused by the application.
    
    buffer_offset - the (x, y, z) offset in the memory region associated with buffer. For a 2D rectangle region, the z value given by buffer_origin[2] should be 0. The offset in bytes is computed as buffer_origin[2] * buffer_slice_pitch + buffer_origin[1] * buffer_row_pitch + buffer_origin[0].
    
    host_offset - the (x, y, z) offset in the memory region pointed to by ptr. For a 2D rectangle region, the z value given by host_origin[2] should be 0. The offset in bytes is computed as host_origin[2] * host_slice_pitch + host_origin[1] * host_row_pitch + host_origin[0].
    
    region - the (width in bytes, height in rows, depth in slices) of the 2D or 3D rectangle being read or written. For a 2D rectangle copy, the depth value given by region[2] should be 1. The values in region cannot be 0.
    
    buffer_row_pitch - the length of each row in bytes to be used for the memory region associated with buffer. If buffer_row_pitch is 0, buffer_row_pitch is computed as region[0].
    
    buffer_slice_pitch - the length of each 2D slice in bytes to be used for the memory region associated with buffer. If buffer_slice_pitch is 0, buffer_slice_pitch is computed as region[1] * buffer_row_pitch.
    
    host_row_pitch - the length of each row in bytes to be used for the memory region pointed to by ptr. If host_row_pitch is 0, host_row_pitch is computed as region[0].
    
    host_slice_pitch - the length of each 2D slice in bytes to be used for the memory region pointed to by ptr. If host_slice_pitch is 0, host_slice_pitch is computed as region[1] * host_row_pitch.
    
    ptr - the pointer to buffer in host memory where data is to be written from
    
    event_wait_list - a list of events that need to complete before this particular command can be executed. If event_wait_list is NULL, then this particular command does not wait on any event to complete. The events specified in event_wait_list act as synchronization points. The context associated with events in event_wait_list and command_queue must be the same.
    
    event - Returns an event object that identifies this particular command and can be used to query or queue a wait for this particular command to complete. event can be NULL in which case it will not be possible for the application to query the status of this command or queue a wait for this command to complete. If the event_wait_list and the event arguments are not NULL, the event argument should not refer to an element of the event_wait_list array.
    
    Returns:
    SUCCESS if the function is executed successfully. Otherwise, it returns one of the following errors:
    
    INVALID_COMMAND_QUEUE if command_queue is not a valid command-queue.
    
    INVALID_CONTEXT if the context associated with command_queue and buffer are not the same or if the context associated with command_queue and events in event_wait_list are not the same.
    
    INVALID_MEM_OBJECT if buffer is not a valid buffer object.
    
    INVALID_VALUE if the region being written specified by (buffer_origin, region, buffer_row_pitch, buffer_slice_pitch) is out of bounds.
    
    INVALID_VALUE if ptr is a NULL value.
    
    INVALID_VALUE if any region array element is 0.
    
    INVALID_VALUE if buffer_row_pitch is not 0 and is less than region[0].
    
    INVALID_VALUE if host_row_pitch is not 0 and is less than region[0].
    
    INVALID_VALUE if buffer_slice_pitch is not 0 and is less than region[1] * buffer_row_pitch and not a multiple of buffer_row_pitch.
    
    INVALID_VALUE if host_slice_pitch is not 0 and is less than region[1] * host_row_pitch and not a multiple of host_row_pitch.
    
    INVALID_EVENT_WAIT_LIST if event_wait_list is NULL and num_events_in_wait_list > 0, or event_wait_list is not NULL and num_events_in_wait_list is 0, or if event objects in event_wait_list are not valid events.
    
    MISALIGNED_SUB_BUFFER_OFFSET if buffer is a sub-buffer object and offset specified when the sub-buffer object is created is not aligned to DEVICE_MEM_BASE_ADDR_ALIGN value for device associated with queue.
    
    EXEC_STATUS_ERROR_FOR_EVENTS_IN_WAIT_LIST if the write operation is blocking and the execution status of any of the events in event_wait_list is a negative integer value.
    
    MEM_OBJECT_ALLOCATION_FAILURE if there is a failure to allocate memory for data store associated with buffer.
    
    INVALID_OPERATION if clEnqueueWriteBufferRect is called on buffer which has been created with MEM_HOST_READ_ONLY or MEM_HOST_NO_ACCESS.
    
    OUT_OF_RESOURCES if there is a failure to allocate resources required by the OpenCL implementation on the device.
    
    OUT_OF_HOST_MEMORY if there is a failure to allocate resources required by the OpenCL implementation on the host.
    See Also:
    
    Reference Page
  - clEnqueueWriteBufferRect
```
public static int clEnqueueWriteBufferRect(long command_queue,
                                           long buffer,
                                           boolean blocking_write,
                                           org.lwjgl.PointerBuffer buffer_offset,
                                           org.lwjgl.PointerBuffer host_offset,
                                           org.lwjgl.PointerBuffer region,
                                           long buffer_row_pitch,
                                           long buffer_slice_pitch,
                                           long host_row_pitch,
                                           long host_slice_pitch,
                                           java.nio.ShortBuffer ptr,
                                           @Nullable
                                           org.lwjgl.PointerBuffer event_wait_list,
                                           @Nullable
                                           org.lwjgl.PointerBuffer event)
```
    Enqueues a command to write a 2D or 3D rectangular region to a buffer object from host memory.
    Calling clEnqueueWriteBufferRect to update the latest bits in a region of the buffer object with the ptr argument value set to host_ptr and host_origin, buffer_origin values are the same, where host_ptr is a pointer to the memory region specified when the buffer object being written is created with MEM_USE_HOST_PTR, must meet the following requirements in order to avoid undefined behavior:
    - The host memory region given by (buffer_origin region) contains the latest bits when the enqueued write command begins execution.
    - The buffer object or memory objects created from this buffer object are not mapped.
    - The buffer object or memory objects created from this buffer object are not used by any command-queue until the write command has finished execution.
    Parameters:
    
    command_queue - the command-queue in which the write command will be queued. command_queue and buffer must be created with the same OpenCL context.
    
    buffer - a valid buffer object
    
    blocking_write - indicates if the write operation is blocking or nonblocking.
    If blocking_write is TRUE, the OpenCL implementation copies the data referred to by ptr and enqueues the write operation in the command-queue. The memory pointed to by ptr can be reused by the application after the clEnqueueWriteBufferRect call returns.
    
    If blocking_write is FALSE, the OpenCL implementation will use ptr to perform a non-blocking write. As the write is non-blocking the implementation can return immediately. The memory pointed to by ptr cannot be reused by the application after the call returns. The event argument returns an event object which can be used to query the execution status of the write command. When the write command has completed, the memory pointed to by ptr can then be reused by the application.
    
    buffer_offset - the (x, y, z) offset in the memory region associated with buffer. For a 2D rectangle region, the z value given by buffer_origin[2] should be 0. The offset in bytes is computed as buffer_origin[2] * buffer_slice_pitch + buffer_origin[1] * buffer_row_pitch + buffer_origin[0].
    
    host_offset - the (x, y, z) offset in the memory region pointed to by ptr. For a 2D rectangle region, the z value given by host_origin[2] should be 0. The offset in bytes is computed as host_origin[2] * host_slice_pitch + host_origin[1] * host_row_pitch + host_origin[0].
    
    region - the (width in bytes, height in rows, depth in slices) of the 2D or 3D rectangle being read or written. For a 2D rectangle copy, the depth value given by region[2] should be 1. The values in region cannot be 0.
    
    buffer_row_pitch - the length of each row in bytes to be used for the memory region associated with buffer. If buffer_row_pitch is 0, buffer_row_pitch is computed as region[0].
    
    buffer_slice_pitch - the length of each 2D slice in bytes to be used for the memory region associated with buffer. If buffer_slice_pitch is 0, buffer_slice_pitch is computed as region[1] * buffer_row_pitch.
    
    host_row_pitch - the length of each row in bytes to be used for the memory region pointed to by ptr. If host_row_pitch is 0, host_row_pitch is computed as region[0].
    
    host_slice_pitch - the length of each 2D slice in bytes to be used for the memory region pointed to by ptr. If host_slice_pitch is 0, host_slice_pitch is computed as region[1] * host_row_pitch.
    
    ptr - the pointer to buffer in host memory where data is to be written from
    
    event_wait_list - a list of events that need to complete before this particular command can be executed. If event_wait_list is NULL, then this particular command does not wait on any event to complete. The events specified in event_wait_list act as synchronization points. The context associated with events in event_wait_list and command_queue must be the same.
    
    event - Returns an event object that identifies this particular command and can be used to query or queue a wait for this particular command to complete. event can be NULL in which case it will not be possible for the application to query the status of this command or queue a wait for this command to complete. If the event_wait_list and the event arguments are not NULL, the event argument should not refer to an element of the event_wait_list array.
    
    Returns:
    SUCCESS if the function is executed successfully. Otherwise, it returns one of the following errors:
    
    INVALID_COMMAND_QUEUE if command_queue is not a valid command-queue.
    
    INVALID_CONTEXT if the context associated with command_queue and buffer are not the same or if the context associated with command_queue and events in event_wait_list are not the same.
    
    INVALID_MEM_OBJECT if buffer is not a valid buffer object.
    
    INVALID_VALUE if the region being written specified by (buffer_origin, region, buffer_row_pitch, buffer_slice_pitch) is out of bounds.
    
    INVALID_VALUE if ptr is a NULL value.
    
    INVALID_VALUE if any region array element is 0.
    
    INVALID_VALUE if buffer_row_pitch is not 0 and is less than region[0].
    
    INVALID_VALUE if host_row_pitch is not 0 and is less than region[0].
    
    INVALID_VALUE if buffer_slice_pitch is not 0 and is less than region[1] * buffer_row_pitch and not a multiple of buffer_row_pitch.
    
    INVALID_VALUE if host_slice_pitch is not 0 and is less than region[1] * host_row_pitch and not a multiple of host_row_pitch.
    
    INVALID_EVENT_WAIT_LIST if event_wait_list is NULL and num_events_in_wait_list > 0, or event_wait_list is not NULL and num_events_in_wait_list is 0, or if event objects in event_wait_list are not valid events.
    
    MISALIGNED_SUB_BUFFER_OFFSET if buffer is a sub-buffer object and offset specified when the sub-buffer object is created is not aligned to DEVICE_MEM_BASE_ADDR_ALIGN value for device associated with queue.
    
    EXEC_STATUS_ERROR_FOR_EVENTS_IN_WAIT_LIST if the write operation is blocking and the execution status of any of the events in event_wait_list is a negative integer value.
    
    MEM_OBJECT_ALLOCATION_FAILURE if there is a failure to allocate memory for data store associated with buffer.
    
    INVALID_OPERATION if clEnqueueWriteBufferRect is called on buffer which has been created with MEM_HOST_READ_ONLY or MEM_HOST_NO_ACCESS.
    
    OUT_OF_RESOURCES if there is a failure to allocate resources required by the OpenCL implementation on the device.
    
    OUT_OF_HOST_MEMORY if there is a failure to allocate resources required by the OpenCL implementation on the host.
    See Also:
    
    Reference Page
  - clEnqueueWriteBufferRect
```
public static int clEnqueueWriteBufferRect(long command_queue,
                                           long buffer,
                                           boolean blocking_write,
                                           org.lwjgl.PointerBuffer buffer_offset,
                                           org.lwjgl.PointerBuffer host_offset,
                                           org.lwjgl.PointerBuffer region,
                                           long buffer_row_pitch,
                                           long buffer_slice_pitch,
                                           long host_row_pitch,
                                           long host_slice_pitch,
                                           java.nio.IntBuffer ptr,
                                           @Nullable
                                           org.lwjgl.PointerBuffer event_wait_list,
                                           @Nullable
                                           org.lwjgl.PointerBuffer event)
```
    Enqueues a command to write a 2D or 3D rectangular region to a buffer object from host memory.
    Calling clEnqueueWriteBufferRect to update the latest bits in a region of the buffer object with the ptr argument value set to host_ptr and host_origin, buffer_origin values are the same, where host_ptr is a pointer to the memory region specified when the buffer object being written is created with MEM_USE_HOST_PTR, must meet the following requirements in order to avoid undefined behavior:
    - The host memory region given by (buffer_origin region) contains the latest bits when the enqueued write command begins execution.
    - The buffer object or memory objects created from this buffer object are not mapped.
    - The buffer object or memory objects created from this buffer object are not used by any command-queue until the write command has finished execution.
    Parameters:
    
    command_queue - the command-queue in which the write command will be queued. command_queue and buffer must be created with the same OpenCL context.
    
    buffer - a valid buffer object
    
    blocking_write - indicates if the write operation is blocking or nonblocking.
    If blocking_write is TRUE, the OpenCL implementation copies the data referred to by ptr and enqueues the write operation in the command-queue. The memory pointed to by ptr can be reused by the application after the clEnqueueWriteBufferRect call returns.
    
    If blocking_write is FALSE, the OpenCL implementation will use ptr to perform a non-blocking write. As the write is non-blocking the implementation can return immediately. The memory pointed to by ptr cannot be reused by the application after the call returns. The event argument returns an event object which can be used to query the execution status of the write command. When the write command has completed, the memory pointed to by ptr can then be reused by the application.
    
    buffer_offset - the (x, y, z) offset in the memory region associated with buffer. For a 2D rectangle region, the z value given by buffer_origin[2] should be 0. The offset in bytes is computed as buffer_origin[2] * buffer_slice_pitch + buffer_origin[1] * buffer_row_pitch + buffer_origin[0].
    
    host_offset - the (x, y, z) offset in the memory region pointed to by ptr. For a 2D rectangle region, the z value given by host_origin[2] should be 0. The offset in bytes is computed as host_origin[2] * host_slice_pitch + host_origin[1] * host_row_pitch + host_origin[0].
    
    region - the (width in bytes, height in rows, depth in slices) of the 2D or 3D rectangle being read or written. For a 2D rectangle copy, the depth value given by region[2] should be 1. The values in region cannot be 0.
    
    buffer_row_pitch - the length of each row in bytes to be used for the memory region associated with buffer. If buffer_row_pitch is 0, buffer_row_pitch is computed as region[0].
    
    buffer_slice_pitch - the length of each 2D slice in bytes to be used for the memory region associated with buffer. If buffer_slice_pitch is 0, buffer_slice_pitch is computed as region[1] * buffer_row_pitch.
    
    host_row_pitch - the length of each row in bytes to be used for the memory region pointed to by ptr. If host_row_pitch is 0, host_row_pitch is computed as region[0].
    
    host_slice_pitch - the length of each 2D slice in bytes to be used for the memory region pointed to by ptr. If host_slice_pitch is 0, host_slice_pitch is computed as region[1] * host_row_pitch.
    
    ptr - the pointer to buffer in host memory where data is to be written from
    
    event_wait_list - a list of events that need to complete before this particular command can be executed. If event_wait_list is NULL, then this particular command does not wait on any event to complete. The events specified in event_wait_list act as synchronization points. The context associated with events in event_wait_list and command_queue must be the same.
    
    event - Returns an event object that identifies this particular command and can be used to query or queue a wait for this particular command to complete. event can be NULL in which case it will not be possible for the application to query the status of this command or queue a wait for this command to complete. If the event_wait_list and the event arguments are not NULL, the event argument should not refer to an element of the event_wait_list array.
    
    Returns:
    SUCCESS if the function is executed successfully. Otherwise, it returns one of the following errors:
    
    INVALID_COMMAND_QUEUE if command_queue is not a valid command-queue.
    
    INVALID_CONTEXT if the context associated with command_queue and buffer are not the same or if the context associated with command_queue and events in event_wait_list are not the same.
    
    INVALID_MEM_OBJECT if buffer is not a valid buffer object.
    
    INVALID_VALUE if the region being written specified by (buffer_origin, region, buffer_row_pitch, buffer_slice_pitch) is out of bounds.
    
    INVALID_VALUE if ptr is a NULL value.
    
    INVALID_VALUE if any region array element is 0.
    
    INVALID_VALUE if buffer_row_pitch is not 0 and is less than region[0].
    
    INVALID_VALUE if host_row_pitch is not 0 and is less than region[0].
    
    INVALID_VALUE if buffer_slice_pitch is not 0 and is less than region[1] * buffer_row_pitch and not a multiple of buffer_row_pitch.
    
    INVALID_VALUE if host_slice_pitch is not 0 and is less than region[1] * host_row_pitch and not a multiple of host_row_pitch.
    
    INVALID_EVENT_WAIT_LIST if event_wait_list is NULL and num_events_in_wait_list > 0, or event_wait_list is not NULL and num_events_in_wait_list is 0, or if event objects in event_wait_list are not valid events.
    
    MISALIGNED_SUB_BUFFER_OFFSET if buffer is a sub-buffer object and offset specified when the sub-buffer object is created is not aligned to DEVICE_MEM_BASE_ADDR_ALIGN value for device associated with queue.
    
    EXEC_STATUS_ERROR_FOR_EVENTS_IN_WAIT_LIST if the write operation is blocking and the execution status of any of the events in event_wait_list is a negative integer value.
    
    MEM_OBJECT_ALLOCATION_FAILURE if there is a failure to allocate memory for data store associated with buffer.
    
    INVALID_OPERATION if clEnqueueWriteBufferRect is called on buffer which has been created with MEM_HOST_READ_ONLY or MEM_HOST_NO_ACCESS.
    
    OUT_OF_RESOURCES if there is a failure to allocate resources required by the OpenCL implementation on the device.
    
    OUT_OF_HOST_MEMORY if there is a failure to allocate resources required by the OpenCL implementation on the host.
    See Also:
    
    Reference Page
  - clEnqueueWriteBufferRect
```
public static int clEnqueueWriteBufferRect(long command_queue,
                                           long buffer,
                                           boolean blocking_write,
                                           org.lwjgl.PointerBuffer buffer_offset,
                                           org.lwjgl.PointerBuffer host_offset,
                                           org.lwjgl.PointerBuffer region,
                                           long buffer_row_pitch,
                                           long buffer_slice_pitch,
                                           long host_row_pitch,
                                           long host_slice_pitch,
                                           java.nio.FloatBuffer ptr,
                                           @Nullable
                                           org.lwjgl.PointerBuffer event_wait_list,
                                           @Nullable
                                           org.lwjgl.PointerBuffer event)
```
    Enqueues a command to write a 2D or 3D rectangular region to a buffer object from host memory.
    Calling clEnqueueWriteBufferRect to update the latest bits in a region of the buffer object with the ptr argument value set to host_ptr and host_origin, buffer_origin values are the same, where host_ptr is a pointer to the memory region specified when the buffer object being written is created with MEM_USE_HOST_PTR, must meet the following requirements in order to avoid undefined behavior:
    - The host memory region given by (buffer_origin region) contains the latest bits when the enqueued write command begins execution.
    - The buffer object or memory objects created from this buffer object are not mapped.
    - The buffer object or memory objects created from this buffer object are not used by any command-queue until the write command has finished execution.
    Parameters:
    
    command_queue - the command-queue in which the write command will be queued. command_queue and buffer must be created with the same OpenCL context.
    
    buffer - a valid buffer object
    
    blocking_write - indicates if the write operation is blocking or nonblocking.
    If blocking_write is TRUE, the OpenCL implementation copies the data referred to by ptr and enqueues the write operation in the command-queue. The memory pointed to by ptr can be reused by the application after the clEnqueueWriteBufferRect call returns.
    
    If blocking_write is FALSE, the OpenCL implementation will use ptr to perform a non-blocking write. As the write is non-blocking the implementation can return immediately. The memory pointed to by ptr cannot be reused by the application after the call returns. The event argument returns an event object which can be used to query the execution status of the write command. When the write command has completed, the memory pointed to by ptr can then be reused by the application.
    
    buffer_offset - the (x, y, z) offset in the memory region associated with buffer. For a 2D rectangle region, the z value given by buffer_origin[2] should be 0. The offset in bytes is computed as buffer_origin[2] * buffer_slice_pitch + buffer_origin[1] * buffer_row_pitch + buffer_origin[0].
    
    host_offset - the (x, y, z) offset in the memory region pointed to by ptr. For a 2D rectangle region, the z value given by host_origin[2] should be 0. The offset in bytes is computed as host_origin[2] * host_slice_pitch + host_origin[1] * host_row_pitch + host_origin[0].
    
    region - the (width in bytes, height in rows, depth in slices) of the 2D or 3D rectangle being read or written. For a 2D rectangle copy, the depth value given by region[2] should be 1. The values in region cannot be 0.
    
    buffer_row_pitch - the length of each row in bytes to be used for the memory region associated with buffer. If buffer_row_pitch is 0, buffer_row_pitch is computed as region[0].
    
    buffer_slice_pitch - the length of each 2D slice in bytes to be used for the memory region associated with buffer. If buffer_slice_pitch is 0, buffer_slice_pitch is computed as region[1] * buffer_row_pitch.
    
    host_row_pitch - the length of each row in bytes to be used for the memory region pointed to by ptr. If host_row_pitch is 0, host_row_pitch is computed as region[0].
    
    host_slice_pitch - the length of each 2D slice in bytes to be used for the memory region pointed to by ptr. If host_slice_pitch is 0, host_slice_pitch is computed as region[1] * host_row_pitch.
    
    ptr - the pointer to buffer in host memory where data is to be written from
    
    event_wait_list - a list of events that need to complete before this particular command can be executed. If event_wait_list is NULL, then this particular command does not wait on any event to complete. The events specified in event_wait_list act as synchronization points. The context associated with events in event_wait_list and command_queue must be the same.
    
    event - Returns an event object that identifies this particular command and can be used to query or queue a wait for this particular command to complete. event can be NULL in which case it will not be possible for the application to query the status of this command or queue a wait for this command to complete. If the event_wait_list and the event arguments are not NULL, the event argument should not refer to an element of the event_wait_list array.
    
    Returns:
    SUCCESS if the function is executed successfully. Otherwise, it returns one of the following errors:
    
    INVALID_COMMAND_QUEUE if command_queue is not a valid command-queue.
    
    INVALID_CONTEXT if the context associated with command_queue and buffer are not the same or if the context associated with command_queue and events in event_wait_list are not the same.
    
    INVALID_MEM_OBJECT if buffer is not a valid buffer object.
    
    INVALID_VALUE if the region being written specified by (buffer_origin, region, buffer_row_pitch, buffer_slice_pitch) is out of bounds.
    
    INVALID_VALUE if ptr is a NULL value.
    
    INVALID_VALUE if any region array element is 0.
    
    INVALID_VALUE if buffer_row_pitch is not 0 and is less than region[0].
    
    INVALID_VALUE if host_row_pitch is not 0 and is less than region[0].
    
    INVALID_VALUE if buffer_slice_pitch is not 0 and is less than region[1] * buffer_row_pitch and not a multiple of buffer_row_pitch.
    
    INVALID_VALUE if host_slice_pitch is not 0 and is less than region[1] * host_row_pitch and not a multiple of host_row_pitch.
    
    INVALID_EVENT_WAIT_LIST if event_wait_list is NULL and num_events_in_wait_list > 0, or event_wait_list is not NULL and num_events_in_wait_list is 0, or if event objects in event_wait_list are not valid events.
    
    MISALIGNED_SUB_BUFFER_OFFSET if buffer is a sub-buffer object and offset specified when the sub-buffer object is created is not aligned to DEVICE_MEM_BASE_ADDR_ALIGN value for device associated with queue.
    
    EXEC_STATUS_ERROR_FOR_EVENTS_IN_WAIT_LIST if the write operation is blocking and the execution status of any of the events in event_wait_list is a negative integer value.
    
    MEM_OBJECT_ALLOCATION_FAILURE if there is a failure to allocate memory for data store associated with buffer.
    
    INVALID_OPERATION if clEnqueueWriteBufferRect is called on buffer which has been created with MEM_HOST_READ_ONLY or MEM_HOST_NO_ACCESS.
    
    OUT_OF_RESOURCES if there is a failure to allocate resources required by the OpenCL implementation on the device.
    
    OUT_OF_HOST_MEMORY if there is a failure to allocate resources required by the OpenCL implementation on the host.
    See Also:
    
    Reference Page
  - clEnqueueWriteBufferRect
```
public static int clEnqueueWriteBufferRect(long command_queue,
                                           long buffer,
                                           boolean blocking_write,
                                           org.lwjgl.PointerBuffer buffer_offset,
                                           org.lwjgl.PointerBuffer host_offset,
                                           org.lwjgl.PointerBuffer region,
                                           long buffer_row_pitch,
                                           long buffer_slice_pitch,
                                           long host_row_pitch,
                                           long host_slice_pitch,
                                           java.nio.DoubleBuffer ptr,
                                           @Nullable
                                           org.lwjgl.PointerBuffer event_wait_list,
                                           @Nullable
                                           org.lwjgl.PointerBuffer event)
```
    Enqueues a command to write a 2D or 3D rectangular region to a buffer object from host memory.
    Calling clEnqueueWriteBufferRect to update the latest bits in a region of the buffer object with the ptr argument value set to host_ptr and host_origin, buffer_origin values are the same, where host_ptr is a pointer to the memory region specified when the buffer object being written is created with MEM_USE_HOST_PTR, must meet the following requirements in order to avoid undefined behavior:
    - The host memory region given by (buffer_origin region) contains the latest bits when the enqueued write command begins execution.
    - The buffer object or memory objects created from this buffer object are not mapped.
    - The buffer object or memory objects created from this buffer object are not used by any command-queue until the write command has finished execution.
    Parameters:
    
    command_queue - the command-queue in which the write command will be queued. command_queue and buffer must be created with the same OpenCL context.
    
    buffer - a valid buffer object
    
    blocking_write - indicates if the write operation is blocking or nonblocking.
    If blocking_write is TRUE, the OpenCL implementation copies the data referred to by ptr and enqueues the write operation in the command-queue. The memory pointed to by ptr can be reused by the application after the clEnqueueWriteBufferRect call returns.
    
    If blocking_write is FALSE, the OpenCL implementation will use ptr to perform a non-blocking write. As the write is non-blocking the implementation can return immediately. The memory pointed to by ptr cannot be reused by the application after the call returns. The event argument returns an event object which can be used to query the execution status of the write command. When the write command has completed, the memory pointed to by ptr can then be reused by the application.
    
    buffer_offset - the (x, y, z) offset in the memory region associated with buffer. For a 2D rectangle region, the z value given by buffer_origin[2] should be 0. The offset in bytes is computed as buffer_origin[2] * buffer_slice_pitch + buffer_origin[1] * buffer_row_pitch + buffer_origin[0].
    
    host_offset - the (x, y, z) offset in the memory region pointed to by ptr. For a 2D rectangle region, the z value given by host_origin[2] should be 0. The offset in bytes is computed as host_origin[2] * host_slice_pitch + host_origin[1] * host_row_pitch + host_origin[0].
    
    region - the (width in bytes, height in rows, depth in slices) of the 2D or 3D rectangle being read or written. For a 2D rectangle copy, the depth value given by region[2] should be 1. The values in region cannot be 0.
    
    buffer_row_pitch - the length of each row in bytes to be used for the memory region associated with buffer. If buffer_row_pitch is 0, buffer_row_pitch is computed as region[0].
    
    buffer_slice_pitch - the length of each 2D slice in bytes to be used for the memory region associated with buffer. If buffer_slice_pitch is 0, buffer_slice_pitch is computed as region[1] * buffer_row_pitch.
    
    host_row_pitch - the length of each row in bytes to be used for the memory region pointed to by ptr. If host_row_pitch is 0, host_row_pitch is computed as region[0].
    
    host_slice_pitch - the length of each 2D slice in bytes to be used for the memory region pointed to by ptr. If host_slice_pitch is 0, host_slice_pitch is computed as region[1] * host_row_pitch.
    
    ptr - the pointer to buffer in host memory where data is to be written from
    
    event_wait_list - a list of events that need to complete before this particular command can be executed. If event_wait_list is NULL, then this particular command does not wait on any event to complete. The events specified in event_wait_list act as synchronization points. The context associated with events in event_wait_list and command_queue must be the same.
    
    event - Returns an event object that identifies this particular command and can be used to query or queue a wait for this particular command to complete. event can be NULL in which case it will not be possible for the application to query the status of this command or queue a wait for this command to complete. If the event_wait_list and the event arguments are not NULL, the event argument should not refer to an element of the event_wait_list array.
    
    Returns:
    SUCCESS if the function is executed successfully. Otherwise, it returns one of the following errors:
    
    INVALID_COMMAND_QUEUE if command_queue is not a valid command-queue.
    
    INVALID_CONTEXT if the context associated with command_queue and buffer are not the same or if the context associated with command_queue and events in event_wait_list are not the same.
    
    INVALID_MEM_OBJECT if buffer is not a valid buffer object.
    
    INVALID_VALUE if the region being written specified by (buffer_origin, region, buffer_row_pitch, buffer_slice_pitch) is out of bounds.
    
    INVALID_VALUE if ptr is a NULL value.
    
    INVALID_VALUE if any region array element is 0.
    
    INVALID_VALUE if buffer_row_pitch is not 0 and is less than region[0].
    
    INVALID_VALUE if host_row_pitch is not 0 and is less than region[0].
    
    INVALID_VALUE if buffer_slice_pitch is not 0 and is less than region[1] * buffer_row_pitch and not a multiple of buffer_row_pitch.
    
    INVALID_VALUE if host_slice_pitch is not 0 and is less than region[1] * host_row_pitch and not a multiple of host_row_pitch.
    
    INVALID_EVENT_WAIT_LIST if event_wait_list is NULL and num_events_in_wait_list > 0, or event_wait_list is not NULL and num_events_in_wait_list is 0, or if event objects in event_wait_list are not valid events.
    
    MISALIGNED_SUB_BUFFER_OFFSET if buffer is a sub-buffer object and offset specified when the sub-buffer object is created is not aligned to DEVICE_MEM_BASE_ADDR_ALIGN value for device associated with queue.
    
    EXEC_STATUS_ERROR_FOR_EVENTS_IN_WAIT_LIST if the write operation is blocking and the execution status of any of the events in event_wait_list is a negative integer value.
    
    MEM_OBJECT_ALLOCATION_FAILURE if there is a failure to allocate memory for data store associated with buffer.
    
    INVALID_OPERATION if clEnqueueWriteBufferRect is called on buffer which has been created with MEM_HOST_READ_ONLY or MEM_HOST_NO_ACCESS.
    
    OUT_OF_RESOURCES if there is a failure to allocate resources required by the OpenCL implementation on the device.
    
    OUT_OF_HOST_MEMORY if there is a failure to allocate resources required by the OpenCL implementation on the host.
    See Also:
    
    Reference Page
  - nclEnqueueCopyBufferRect
```
public static int nclEnqueueCopyBufferRect(long command_queue,
                                           long src_buffer,
                                           long dst_buffer,
                                           long src_origin,
                                           long dst_origin,
                                           long region,
                                           long src_row_pitch,
                                           long src_slice_pitch,
                                           long dst_row_pitch,
                                           long dst_slice_pitch,
                                           int num_events_in_wait_list,
                                           long event_wait_list,
                                           long event)
```
    Unsafe version of: EnqueueCopyBufferRect
    
    Parameters:
    
    num_events_in_wait_list - the number of events in event_wait_list
  - clEnqueueCopyBufferRect
```
public static int clEnqueueCopyBufferRect(long command_queue,
                                          long src_buffer,
                                          long dst_buffer,
                                          org.lwjgl.PointerBuffer src_origin,
                                          org.lwjgl.PointerBuffer dst_origin,
                                          org.lwjgl.PointerBuffer region,
                                          long src_row_pitch,
                                          long src_slice_pitch,
                                          long dst_row_pitch,
                                          long dst_slice_pitch,
                                          @Nullable
                                          org.lwjgl.PointerBuffer event_wait_list,
                                          @Nullable
                                          org.lwjgl.PointerBuffer event)
```
    Enqueues a command to copy a 2D or 3D rectangular region from the buffer object identified by src_buffer to a 2D or 3D region in the buffer object identified by dst_buffer. Copying begins at the source offset and destination offset which are computed as described below in the description for src_origin and dst_origin. Each byte of the region's width is copied from the source offset to the destination offset. After copying each width, the source and destination offsets are incremented by their respective source and destination row pitches. After copying each 2D rectangle, the source and destination offsets are incremented by their respective source and destination slice pitches.
    NOTE: If src_buffer and dst_buffer are the same buffer object, src_row_pitch must equal dst_row_pitch and src_slice_pitch must equal dst_slice_pitch.
    Parameters:
    
    command_queue - the command-queue in which the copy command will be queued. The OpenCL context associated with command_queue, src_buffer and dst_buffer must be the same.
    
    src_buffer - the source buffer
    
    dst_buffer - the destination buffer
    
    src_origin - the (x, y, z) offset in the memory region associated with src_buffer. For a 2D rectangle region, the z value given by src_origin[2] should be 0. The offset in bytes is computed as src_origin[2] * src_slice_pitch + src_origin[1] * src_row_pitch + src_origin[0].
    
    dst_origin - the (x, y, z) offset in the memory region associated with dst_buffer. For a 2D rectangle region, the z value given by dst_origin[2] should be 0. The offset in bytes is computed as dst_origin[2] * dst_slice_pitch + dst_origin[1] * dst_row_pitch + dst_origin[0].
    
    region - the (width in bytes, height in rows, depth in slices) of the 2D or 3D rectangle being copied. For a 2D rectangle, the depth value given by region[2] should be 1. The values in region cannot be 0.
    
    src_row_pitch - the length of each row in bytes to be used for the memory region associated with src_buffer. If src_row_pitch is 0, src_row_pitch is computed as region[0].
    
    src_slice_pitch - the length of each 2D slice in bytes to be used for the memory region associated with src_buffer. If src_slice_pitch is 0, src_slice_pitch is computed as region[1] * src_row_pitch.
    
    dst_row_pitch - the length of each row in bytes to be used for the memory region associated with dst_buffer. If dst_row_pitch is 0, dst_row_pitch is computed as region[0].
    
    dst_slice_pitch - the length of each 2D slice in bytes to be used for the memory region associated with dst_buffer. If dst_slice_pitch is 0, dst_slice_pitch is computed as region[1] * dst_row_pitch.
    
    event_wait_list - a list of events that need to complete before this particular command can be executed. If event_wait_list is NULL, then this particular command does not wait on any event to complete. The events specified in event_wait_list act as synchronization points. The context associated with events in event_wait_list and command_queue must be the same.
    
    event - Returns an event object that identifies this particular command and can be used to query or queue a wait for this particular command to complete. event can be NULL in which case it will not be possible for the application to query the status of this command or queue a wait for this command to complete. If the event_wait_list and the event arguments are not NULL, the event argument should not refer to an element of the event_wait_list array.
    
    Returns:
    SUCCESS if the function is executed successfully. Otherwise, it returns one of the following errors:
    
    INVALID_COMMAND_QUEUE if command_queue is not a valid command-queue.
    
    INVALID_CONTEXT if the context associated with command_queue, src_buffer and dst_buffer are not the same or if the context associated with command_queue and events in event_wait_list are not the same.
    
    INVALID_MEM_OBJECT if src_buffer and dst_buffer are not valid buffer objects.
    
    INVALID_VALUE if (src_origin, region, src_row_pitch, src_slice_pitch) or (dst_origin, region, dst_row_pitch, dst_slice_pitch) require accessing elements outside the src_buffer and dst_buffer buffer objects respectively.
    
    INVALID_VALUE if any region array element is 0.
    
    INVALID_VALUE if src_row_pitch is not 0 and is less than region[0].
    
    INVALID_VALUE if dst_row_pitch is not 0 and is less than region[0].
    
    INVALID_VALUE if src_slice_pitch is not 0 and is less than region[1] * src_row_pitch or if src_slice_pitch is not 0 and is not a multiple of src_row_pitch.
    
    INVALID_VALUE if dst_slice_pitch is not 0 and is less than region[1] * dst_row_pitch or if dst_slice_pitch is not 0 and is not a multiple of dst_row_pitch.
    
    INVALID_VALUE if src_buffer and dst_buffer are the same buffer object and src_slice_pitch is not equal to dst_slice_pitch and src_row_pitch is not equal to dst_row_pitch.
    
    INVALID_EVENT_WAIT_LIST if event_wait_list is NULL and num_events_in_wait_list > 0, or event_wait_list is not NULL and num_events_in_wait_list is 0, or if event objects in event_wait_list are not valid events.
    
    MEM_COPY_OVERLAP if src_buffer and dst_buffer are the same buffer or subbuffer object and the source and destination regions overlap or if src_buffer and dst_buffer are different sub-buffers of the same associated buffer object and they overlap.
    
    MISALIGNED_SUB_BUFFER_OFFSET if src_buffer is a sub-buffer object and offset specified when the sub-buffer object is created is not aligned to DEVICE_MEM_BASE_ADDR_ALIGN value for device associated with queue.
    
    MISALIGNED_SUB_BUFFER_OFFSET if dst_buffer is a sub-buffer object and offset specified when the sub-buffer object is created is not aligned to DEVICE_MEM_BASE_ADDR_ALIGN value for device associated with queue.
    
    MEM_OBJECT_ALLOCATION_FAILURE if there is a failure to allocate memory for data store associated with src_buffer or dst_buffer.
    
    OUT_OF_RESOURCES if there is a failure to allocate resources required by the OpenCL implementation on the device.
    
    OUT_OF_HOST_MEMORY if there is a failure to allocate resources required by the OpenCL implementation on the host.
    See Also:
    
    Reference Page
  - nclCreateUserEvent
```
public static long nclCreateUserEvent(long context,
                                      long errcode_ret)
```
    Unsafe version of: CreateUserEvent
  - clCreateUserEvent
```
public static long clCreateUserEvent(long context,
                                     @Nullable
                                     java.nio.IntBuffer errcode_ret)
```
    Creates a user event object. User events allow applications to enqueue commands that wait on a user event to finish before the command is executed by the device.
    The execution status of the user event object created is set to SUBMITTED.
    Parameters:
    
    context - a valid OpenCL context
    
    errcode_ret - will return an appropriate error code. If errcode_ret is NULL, no error code is returned.
    
    Returns:
    a valid non-zero event object and errcode_ret is set to SUCCESS if the user event object is created successfully. Otherwise, it returns a NULL value with one of the following error values returned in errcode_ret:
    
    INVALID_CONTEXT if context is not a valid context.
    
    OUT_OF_RESOURCES if there is a failure to allocate resources required by the OpenCL implementation on the device.
    
    OUT_OF_HOST_MEMORY if there is a failure to allocate resources required by the OpenCL implementation on the host.
    See Also:
    
    Reference Page
  - clSetUserEventStatus
```
public static int clSetUserEventStatus(long event,
                                       int execution_status)
```
    Sets the execution status of a user event object.
    NOTE: Enqueued commands that specify user events in the event_wait_list argument of clEnqueue*** commands must ensure that the status of these user events being waited on are set using clSetUserEventStatus before any OpenCL APIs that release OpenCL objects except for event objects are called; otherwise the behavior is undefined.
    
    For example, the following code sequence will result in undefined behavior of ReleaseMemObject.
```
 ev1 = clCreateUserEvent(ctx, NULL);
 clEnqueueWriteBuffer(cq, buf1, CL_FALSE, ..., 1, &ev1, NULL);
 clEnqueueWriteBuffer(cq, buf2, CL_FALSE, ...);
 clReleaseMemObject(buf2);
 clSetUserEventStatus(ev1, CL_COMPLETE);
```
    The following code sequence, however, works correctly.
```
 ev1 = clCreateUserEvent(ctx, NULL);
 clEnqueueWriteBuffer(cq, buf1, CL_FALSE, ..., 1, &ev1, NULL);
 clEnqueueWriteBuffer(cq, buf2, CL_FALSE, ...);
 clSetUserEventStatus(ev1, CL_COMPLETE);
 clReleaseMemObject(buf2);
```
    Parameters:
    
    event - a user event object created using CreateUserEvent
    
    execution_status - the new execution status to be set and can be COMPLETE or a negative integer value to indicate an error. A negative integer value causes all enqueued commands that wait on this user event to be terminated. clSetUserEventStatus can only be called once to change the execution status of event.
    
    Returns:
    SUCCESS if the function was executed successfully. Otherwise, it returns one of the following errors:
    
    INVALID_EVENT if event is not a valid user event object.
    
    INVALID_VALUE if the execution_status is not COMPLETE or a negative integer value.
    
    INVALID_OPERATION if the execution_status for event has already been changed by a previous call to clSetUserEventStatus.
    
    OUT_OF_RESOURCES if there is a failure to allocate resources required by the OpenCL implementation on the device.
    
    OUT_OF_HOST_MEMORY if there is a failure to allocate resources required by the OpenCL implementation on the host.
    See Also:
    
    Reference Page
  - nclSetEventCallback
```
public static int nclSetEventCallback(long event,
                                      int command_exec_callback_type,
                                      long pfn_notify,
                                      long user_data)
```
    Unsafe version of: SetEventCallback
  - clSetEventCallback
```
public static int clSetEventCallback(long event,
                                     int command_exec_callback_type,
                                     CLEventCallbackI pfn_notify,
                                     long user_data)
```
    Registers a user callback function for a specific command execution status. The registered callback function will be called when the execution status of command associated with event changes to an execution status equal to or past the status specified by command_exec_status.
    Each call to clSetEventCallback registers the specified user callback function on a callback stack associated with event. The order in which the registered user callback functions are called is undefined.
    
    All callbacks registered for an event object must be called. All enqueued callbacks shall be called before the event object is destroyed. Callbacks must return promptly. The behavior of calling expensive system routines, OpenCL API calls to create contexts or command-queues, or blocking OpenCL operations from the following list below, in a callback is undefined.
    - Finish,
    - WaitForEvents,
    - blocking calls to EnqueueReadBuffer, EnqueueReadBufferRect, EnqueueWriteBuffer, EnqueueWriteBufferRect,
    - blocking calls to EnqueueReadImage and EnqueueWriteImage,
    - blocking calls to EnqueueMapBuffer and EnqueueMapImage,
    - blocking calls to BuildProgram, CompileProgram or LinkProgram
    If an application needs to wait for completion of a routine from the above list in a callback, please use the non-blocking form of the function, and assign a completion callback to it to do the remainder of your work. Note that when a callback (or other code) enqueues commands to a command-queue, the commands are not required to begin execution until the queue is flushed. In standard usage, blocking enqueue calls serve this role by implicitly flushing the queue. Since blocking calls are not permitted in callbacks, those callbacks that enqueue commands on a command queue should either call Flush on the queue before returning or arrange for Flush to be called later on another thread.
    Parameters:
    
    event - a valid event object
    
    command_exec_callback_type - the command execution status for which the callback is registered. There is no guarantee that the callback functions registered for various execution status values for an event will be called in the exact order that the execution status of a command changes. Furthermore, it should be noted that receiving a call back for an event with a status other than COMPLETE, in no way implies that the memory model or execution model as defined by the OpenCL specification has changed. For example, it is not valid to assume that a corresponding memory transfer has completed unless the event is in a state COMPLETE. One of:
    SUBMITTED RUNNING COMPLETE
    
    pfn_notify - the event callback function that can be registered by the application. This callback function may be called asynchronously by the OpenCL implementation. It is the application's responsibility to ensure that the callback function is thread-safe.
    
    user_data - will be passed as the user_data argument when pfn_notify is called. user_data can be NULL.
    
    Returns:
    SUCCESS if the function is executed successfully. Otherwise, it returns one of the following errors:
    
    INVALID_EVENT if event is not a valid event object.
    
    INVALID_VALUE if pfn_event_notify is NULL or if command_exec_callback_type is not SUBMITTED, RUNNING or COMPLETE.
    
    INVALID_VALUE if event is a user event object and command_exec_callback_type is not COMPLETE.
    
    OUT_OF_RESOURCES if there is a failure to allocate resources required by the OpenCL implementation on the device.
    
    OUT_OF_HOST_MEMORY if there is a failure to allocate resources required by the OpenCL implementation on the host.
    See Also:
    
    Reference Page
  - clCreateSubBuffer
```
public static long clCreateSubBuffer(long buffer,
                                     long flags,
                                     int buffer_create_type,
                                     java.nio.ByteBuffer buffer_create_info,
                                     @Nullable
                                     int[] errcode_ret)
```
    Array version of: CreateSubBuffer
    
    See Also:
    
    Reference Page
  - clEnqueueReadBufferRect
```
public static int clEnqueueReadBufferRect(long command_queue,
                                          long buffer,
                                          boolean blocking_read,
                                          org.lwjgl.PointerBuffer buffer_offset,
                                          org.lwjgl.PointerBuffer host_offset,
                                          org.lwjgl.PointerBuffer region,
                                          long buffer_row_pitch,
                                          long buffer_slice_pitch,
                                          long host_row_pitch,
                                          long host_slice_pitch,
                                          short[] ptr,
                                          @Nullable
                                          org.lwjgl.PointerBuffer event_wait_list,
                                          @Nullable
                                          org.lwjgl.PointerBuffer event)
```
    Array version of: EnqueueReadBufferRect
    
    See Also:
    
    Reference Page
  - clEnqueueReadBufferRect
```
public static int clEnqueueReadBufferRect(long command_queue,
                                          long buffer,
                                          boolean blocking_read,
                                          org.lwjgl.PointerBuffer buffer_offset,
                                          org.lwjgl.PointerBuffer host_offset,
                                          org.lwjgl.PointerBuffer region,
                                          long buffer_row_pitch,
                                          long buffer_slice_pitch,
                                          long host_row_pitch,
                                          long host_slice_pitch,
                                          int[] ptr,
                                          @Nullable
                                          org.lwjgl.PointerBuffer event_wait_list,
                                          @Nullable
                                          org.lwjgl.PointerBuffer event)
```
    Array version of: EnqueueReadBufferRect
    
    See Also:
    
    Reference Page
  - clEnqueueReadBufferRect
```
public static int clEnqueueReadBufferRect(long command_queue,
                                          long buffer,
                                          boolean blocking_read,
                                          org.lwjgl.PointerBuffer buffer_offset,
                                          org.lwjgl.PointerBuffer host_offset,
                                          org.lwjgl.PointerBuffer region,
                                          long buffer_row_pitch,
                                          long buffer_slice_pitch,
                                          long host_row_pitch,
                                          long host_slice_pitch,
                                          float[] ptr,
                                          @Nullable
                                          org.lwjgl.PointerBuffer event_wait_list,
                                          @Nullable
                                          org.lwjgl.PointerBuffer event)
```
    Array version of: EnqueueReadBufferRect
    
    See Also:
    
    Reference Page
  - clEnqueueReadBufferRect
```
public static int clEnqueueReadBufferRect(long command_queue,
                                          long buffer,
                                          boolean blocking_read,
                                          org.lwjgl.PointerBuffer buffer_offset,
                                          org.lwjgl.PointerBuffer host_offset,
                                          org.lwjgl.PointerBuffer region,
                                          long buffer_row_pitch,
                                          long buffer_slice_pitch,
                                          long host_row_pitch,
                                          long host_slice_pitch,
                                          double[] ptr,
                                          @Nullable
                                          org.lwjgl.PointerBuffer event_wait_list,
                                          @Nullable
                                          org.lwjgl.PointerBuffer event)
```
    Array version of: EnqueueReadBufferRect
    
    See Also:
    
    Reference Page
  - clEnqueueWriteBufferRect
```
public static int clEnqueueWriteBufferRect(long command_queue,
                                           long buffer,
                                           boolean blocking_write,
                                           org.lwjgl.PointerBuffer buffer_offset,
                                           org.lwjgl.PointerBuffer host_offset,
                                           org.lwjgl.PointerBuffer region,
                                           long buffer_row_pitch,
                                           long buffer_slice_pitch,
                                           long host_row_pitch,
                                           long host_slice_pitch,
                                           short[] ptr,
                                           @Nullable
                                           org.lwjgl.PointerBuffer event_wait_list,
                                           @Nullable
                                           org.lwjgl.PointerBuffer event)
```
    Array version of: EnqueueWriteBufferRect
    
    See Also:
    
    Reference Page
  - clEnqueueWriteBufferRect
```
public static int clEnqueueWriteBufferRect(long command_queue,
                                           long buffer,
                                           boolean blocking_write,
                                           org.lwjgl.PointerBuffer buffer_offset,
                                           org.lwjgl.PointerBuffer host_offset,
                                           org.lwjgl.PointerBuffer region,
                                           long buffer_row_pitch,
                                           long buffer_slice_pitch,
                                           long host_row_pitch,
                                           long host_slice_pitch,
                                           int[] ptr,
                                           @Nullable
                                           org.lwjgl.PointerBuffer event_wait_list,
                                           @Nullable
                                           org.lwjgl.PointerBuffer event)
```
    Array version of: EnqueueWriteBufferRect
    
    See Also:
    
    Reference Page
  - clEnqueueWriteBufferRect
```
public static int clEnqueueWriteBufferRect(long command_queue,
                                           long buffer,
                                           boolean blocking_write,
                                           org.lwjgl.PointerBuffer buffer_offset,
                                           org.lwjgl.PointerBuffer host_offset,
                                           org.lwjgl.PointerBuffer region,
                                           long buffer_row_pitch,
                                           long buffer_slice_pitch,
                                           long host_row_pitch,
                                           long host_slice_pitch,
                                           float[] ptr,
                                           @Nullable
                                           org.lwjgl.PointerBuffer event_wait_list,
                                           @Nullable
                                           org.lwjgl.PointerBuffer event)
```
    Array version of: EnqueueWriteBufferRect
    
    See Also:
    
    Reference Page
  - clEnqueueWriteBufferRect
```
public static int clEnqueueWriteBufferRect(long command_queue,
                                           long buffer,
                                           boolean blocking_write,
                                           org.lwjgl.PointerBuffer buffer_offset,
                                           org.lwjgl.PointerBuffer host_offset,
                                           org.lwjgl.PointerBuffer region,
                                           long buffer_row_pitch,
                                           long buffer_slice_pitch,
                                           long host_row_pitch,
                                           long host_slice_pitch,
                                           double[] ptr,
                                           @Nullable
                                           org.lwjgl.PointerBuffer event_wait_list,
                                           @Nullable
                                           org.lwjgl.PointerBuffer event)
```
    Array version of: EnqueueWriteBufferRect
    
    See Also:
    
    Reference Page
  - clCreateUserEvent
```
public static long clCreateUserEvent(long context,
                                     @Nullable
                                     int[] errcode_ret)
```
    Array version of: CreateUserEvent
    
    See Also:
    
    Reference Page

Class CL11

Field Summary

Fields inherited from class org.lwjgl.opencl.CL10

Method Summary

Methods inherited from class org.lwjgl.opencl.CL10

Methods inherited from class java.lang.Object

Field Detail

CL_MISALIGNED_SUB_BUFFER_OFFSET

CL_EXEC_STATUS_ERROR_FOR_EVENTS_IN_WAIT_LIST

CL_INVALID_PROPERTY

CL_VERSION_1_1

CL_DEVICE_PREFERRED_VECTOR_WIDTH_HALF

CL_DEVICE_HOST_UNIFIED_MEMORY

CL_DEVICE_NATIVE_VECTOR_WIDTH_CHAR

CL_DEVICE_NATIVE_VECTOR_WIDTH_SHORT

CL_DEVICE_NATIVE_VECTOR_WIDTH_INT

CL_DEVICE_NATIVE_VECTOR_WIDTH_LONG

CL_DEVICE_NATIVE_VECTOR_WIDTH_FLOAT

CL_DEVICE_NATIVE_VECTOR_WIDTH_DOUBLE

CL_DEVICE_NATIVE_VECTOR_WIDTH_HALF

CL_DEVICE_OPENCL_C_VERSION

CL_FP_SOFT_FLOAT

CL_CONTEXT_NUM_DEVICES

CL_Rx

CL_RGx

CL_RGBx

CL_MEM_ASSOCIATED_MEMOBJECT

CL_MEM_OFFSET

CL_ADDRESS_MIRRORED_REPEAT

CL_KERNEL_PREFERRED_WORK_GROUP_SIZE_MULTIPLE

CL_KERNEL_PRIVATE_MEM_SIZE

CL_EVENT_CONTEXT

CL_COMMAND_READ_BUFFER_RECT

CL_COMMAND_WRITE_BUFFER_RECT

CL_COMMAND_COPY_BUFFER_RECT

CL_COMMAND_USER

CL_BUFFER_CREATE_TYPE_REGION

Method Detail

nclCreateSubBuffer

clCreateSubBuffer

nclSetMemObjectDestructorCallback

clSetMemObjectDestructorCallback

nclEnqueueReadBufferRect

clEnqueueReadBufferRect

clEnqueueReadBufferRect

clEnqueueReadBufferRect

clEnqueueReadBufferRect

clEnqueueReadBufferRect

nclEnqueueWriteBufferRect

clEnqueueWriteBufferRect

clEnqueueWriteBufferRect

clEnqueueWriteBufferRect

clEnqueueWriteBufferRect

clEnqueueWriteBufferRect

nclEnqueueCopyBufferRect

clEnqueueCopyBufferRect

nclCreateUserEvent

clCreateUserEvent

clSetUserEventStatus

nclSetEventCallback

clSetEventCallback

clCreateSubBuffer

clEnqueueReadBufferRect

clEnqueueReadBufferRect

clEnqueueReadBufferRect

clEnqueueReadBufferRect

clEnqueueWriteBufferRect

clEnqueueWriteBufferRect

clEnqueueWriteBufferRect

clEnqueueWriteBufferRect

clCreateUserEvent