Class CL21
- Direct Known Subclasses:
CL22
-
Field Summary
Modifier and TypeFieldDescriptionstatic final int
static final int
static final int
static final int
static final int
static final int
static final int
static final int
static final int
static final int
static final int
static final int
cl_channel_typestatic final int
OpenCL Version.Fields inherited from class org.lwjgl.opencl.CL20
CL_ABGR, CL_COMMAND_SVM_FREE, CL_COMMAND_SVM_MAP, CL_COMMAND_SVM_MEMCPY, CL_COMMAND_SVM_MEMFILL, CL_COMMAND_SVM_UNMAP, CL_DEVICE_GLOBAL_VARIABLE_PREFERRED_TOTAL_SIZE, CL_DEVICE_IMAGE_BASE_ADDRESS_ALIGNMENT, CL_DEVICE_IMAGE_PITCH_ALIGNMENT, CL_DEVICE_MAX_GLOBAL_VARIABLE_SIZE, CL_DEVICE_MAX_ON_DEVICE_EVENTS, CL_DEVICE_MAX_ON_DEVICE_QUEUES, CL_DEVICE_MAX_PIPE_ARGS, CL_DEVICE_MAX_READ_WRITE_IMAGE_ARGS, CL_DEVICE_PIPE_MAX_ACTIVE_RESERVATIONS, CL_DEVICE_PIPE_MAX_PACKET_SIZE, CL_DEVICE_PREFERRED_GLOBAL_ATOMIC_ALIGNMENT, CL_DEVICE_PREFERRED_LOCAL_ATOMIC_ALIGNMENT, CL_DEVICE_PREFERRED_PLATFORM_ATOMIC_ALIGNMENT, CL_DEVICE_QUEUE_ON_DEVICE_MAX_SIZE, CL_DEVICE_QUEUE_ON_DEVICE_PREFERRED_SIZE, CL_DEVICE_QUEUE_ON_DEVICE_PROPERTIES, CL_DEVICE_QUEUE_ON_HOST_PROPERTIES, CL_DEVICE_SVM_ATOMICS, CL_DEVICE_SVM_CAPABILITIES, CL_DEVICE_SVM_COARSE_GRAIN_BUFFER, CL_DEVICE_SVM_FINE_GRAIN_BUFFER, CL_DEVICE_SVM_FINE_GRAIN_SYSTEM, CL_INVALID_DEVICE_QUEUE, CL_INVALID_PIPE_SIZE, CL_KERNEL_ARG_TYPE_PIPE, CL_KERNEL_EXEC_INFO_SVM_FINE_GRAIN_SYSTEM, CL_KERNEL_EXEC_INFO_SVM_PTRS, CL_MEM_KERNEL_READ_AND_WRITE, CL_MEM_OBJECT_PIPE, CL_MEM_SVM_ATOMICS, CL_MEM_SVM_FINE_GRAIN_BUFFER, CL_MEM_USES_SVM_POINTER, CL_PIPE_MAX_PACKETS, CL_PIPE_PACKET_SIZE, CL_PROFILING_COMMAND_COMPLETE, CL_PROGRAM_BUILD_GLOBAL_VARIABLE_TOTAL_SIZE, CL_QUEUE_ON_DEVICE, CL_QUEUE_ON_DEVICE_DEFAULT, CL_QUEUE_SIZE, CL_SAMPLER_LOD_MAX, CL_SAMPLER_LOD_MIN, CL_SAMPLER_MIP_FILTER_MODE, CL_sBGRA, CL_sRGB, CL_sRGBA, CL_sRGBx, CL_VERSION_2_0
Fields inherited from class org.lwjgl.opencl.CL12
CL_BLOCKING, CL_COMMAND_BARRIER, CL_COMMAND_FILL_BUFFER, CL_COMMAND_FILL_IMAGE, CL_COMMAND_MIGRATE_MEM_OBJECTS, CL_COMPILE_PROGRAM_FAILURE, CL_CONTEXT_INTEROP_USER_SYNC, CL_DEVICE_AFFINITY_DOMAIN_L1_CACHE, CL_DEVICE_AFFINITY_DOMAIN_L2_CACHE, CL_DEVICE_AFFINITY_DOMAIN_L3_CACHE, CL_DEVICE_AFFINITY_DOMAIN_L4_CACHE, CL_DEVICE_AFFINITY_DOMAIN_NEXT_PARTITIONABLE, CL_DEVICE_AFFINITY_DOMAIN_NUMA, CL_DEVICE_BUILT_IN_KERNELS, CL_DEVICE_DOUBLE_FP_CONFIG, CL_DEVICE_IMAGE_MAX_ARRAY_SIZE, CL_DEVICE_IMAGE_MAX_BUFFER_SIZE, CL_DEVICE_LINKER_AVAILABLE, CL_DEVICE_PARENT_DEVICE, CL_DEVICE_PARTITION_AFFINITY_DOMAIN, CL_DEVICE_PARTITION_BY_AFFINITY_DOMAIN, CL_DEVICE_PARTITION_BY_COUNTS, CL_DEVICE_PARTITION_BY_COUNTS_LIST_END, CL_DEVICE_PARTITION_EQUALLY, CL_DEVICE_PARTITION_FAILED, CL_DEVICE_PARTITION_MAX_SUB_DEVICES, CL_DEVICE_PARTITION_PROPERTIES, CL_DEVICE_PARTITION_TYPE, CL_DEVICE_PREFERRED_INTEROP_USER_SYNC, CL_DEVICE_PRINTF_BUFFER_SIZE, CL_DEVICE_REFERENCE_COUNT, CL_DEVICE_TYPE_CUSTOM, CL_FP_CORRECTLY_ROUNDED_DIVIDE_SQRT, CL_IMAGE_ARRAY_SIZE, CL_IMAGE_BUFFER, CL_IMAGE_NUM_MIP_LEVELS, CL_IMAGE_NUM_SAMPLES, CL_INVALID_COMPILER_OPTIONS, CL_INVALID_DEVICE_PARTITION_COUNT, CL_INVALID_IMAGE_DESCRIPTOR, CL_INVALID_LINKER_OPTIONS, CL_KERNEL_ARG_ACCESS_NONE, CL_KERNEL_ARG_ACCESS_QUALIFIER, CL_KERNEL_ARG_ACCESS_READ_ONLY, CL_KERNEL_ARG_ACCESS_READ_WRITE, CL_KERNEL_ARG_ACCESS_WRITE_ONLY, CL_KERNEL_ARG_ADDRESS_CONSTANT, CL_KERNEL_ARG_ADDRESS_GLOBAL, CL_KERNEL_ARG_ADDRESS_LOCAL, CL_KERNEL_ARG_ADDRESS_PRIVATE, CL_KERNEL_ARG_ADDRESS_QUALIFIER, CL_KERNEL_ARG_INFO_NOT_AVAILABLE, CL_KERNEL_ARG_NAME, CL_KERNEL_ARG_TYPE_CONST, CL_KERNEL_ARG_TYPE_NAME, CL_KERNEL_ARG_TYPE_NONE, CL_KERNEL_ARG_TYPE_QUALIFIER, CL_KERNEL_ARG_TYPE_RESTRICT, CL_KERNEL_ARG_TYPE_VOLATILE, CL_KERNEL_ATTRIBUTES, CL_KERNEL_GLOBAL_WORK_SIZE, CL_LINK_PROGRAM_FAILURE, CL_LINKER_NOT_AVAILABLE, CL_MAP_WRITE_INVALIDATE_REGION, CL_MEM_HOST_NO_ACCESS, CL_MEM_HOST_READ_ONLY, CL_MEM_HOST_WRITE_ONLY, CL_MEM_OBJECT_IMAGE1D, CL_MEM_OBJECT_IMAGE1D_ARRAY, CL_MEM_OBJECT_IMAGE1D_BUFFER, CL_MEM_OBJECT_IMAGE2D_ARRAY, CL_MIGRATE_MEM_OBJECT_CONTENT_UNDEFINED, CL_MIGRATE_MEM_OBJECT_HOST, CL_NON_BLOCKING, CL_PROGRAM_BINARY_TYPE, CL_PROGRAM_BINARY_TYPE_COMPILED_OBJECT, CL_PROGRAM_BINARY_TYPE_EXECUTABLE, CL_PROGRAM_BINARY_TYPE_LIBRARY, CL_PROGRAM_BINARY_TYPE_NONE, CL_PROGRAM_KERNEL_NAMES, CL_PROGRAM_NUM_KERNELS, CL_VERSION_1_2
Fields inherited from class org.lwjgl.opencl.CL11
CL_ADDRESS_MIRRORED_REPEAT, CL_BUFFER_CREATE_TYPE_REGION, CL_COMMAND_COPY_BUFFER_RECT, CL_COMMAND_READ_BUFFER_RECT, CL_COMMAND_USER, CL_COMMAND_WRITE_BUFFER_RECT, CL_CONTEXT_NUM_DEVICES, CL_DEVICE_HOST_UNIFIED_MEMORY, CL_DEVICE_NATIVE_VECTOR_WIDTH_CHAR, CL_DEVICE_NATIVE_VECTOR_WIDTH_DOUBLE, CL_DEVICE_NATIVE_VECTOR_WIDTH_FLOAT, CL_DEVICE_NATIVE_VECTOR_WIDTH_HALF, CL_DEVICE_NATIVE_VECTOR_WIDTH_INT, CL_DEVICE_NATIVE_VECTOR_WIDTH_LONG, CL_DEVICE_NATIVE_VECTOR_WIDTH_SHORT, CL_DEVICE_OPENCL_C_VERSION, CL_DEVICE_PREFERRED_VECTOR_WIDTH_HALF, CL_EVENT_CONTEXT, CL_EXEC_STATUS_ERROR_FOR_EVENTS_IN_WAIT_LIST, CL_FP_SOFT_FLOAT, CL_INVALID_PROPERTY, CL_KERNEL_PREFERRED_WORK_GROUP_SIZE_MULTIPLE, CL_KERNEL_PRIVATE_MEM_SIZE, CL_MEM_ASSOCIATED_MEMOBJECT, CL_MEM_OFFSET, CL_MISALIGNED_SUB_BUFFER_OFFSET, CL_RGBx, CL_RGx, CL_Rx, CL_VERSION_1_1
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
Modifier and TypeMethodDescriptionstatic long
clCloneKernel
(long source_kernel, int[] errcode_ret) Array version of:CloneKernel
static long
clCloneKernel
(long source_kernel, IntBuffer errcode_ret) Makes a shallow copy of the kernel object, its arguments and any information passed to the kernel object usingSetKernelExecInfo
.static long
clCreateProgramWithIL
(long context, ByteBuffer il, int[] errcode_ret) Array version of:CreateProgramWithIL
static long
clCreateProgramWithIL
(long context, ByteBuffer il, IntBuffer errcode_ret) Creates a program object for a context, and loads the IL pointed to byil
and with length in byteslength
into the program object.static int
clEnqueueSVMMigrateMem
(long command_queue, PointerBuffer svm_pointers, PointerBuffer sizes, long flags, PointerBuffer event_wait_list, PointerBuffer event) Enqueues a command to indicate which device a set of ranges of SVM allocations should be associated with.static int
clGetDeviceAndHostTimer
(long device, long[] device_timestamp, long[] host_timestamp) Array version of:GetDeviceAndHostTimer
static int
clGetDeviceAndHostTimer
(long device, LongBuffer device_timestamp, LongBuffer host_timestamp) Returns a reasonably synchronized pair of timestamps from the device timer and the host timer as seen by device.static int
clGetHostTimer
(long device, long[] host_timestamp) Array version of:GetHostTimer
static int
clGetHostTimer
(long device, LongBuffer host_timestamp) Returns the current value of the host clock as seen by device.static int
clGetKernelSubGroupInfo
(long kernel, long device, int param_name, ByteBuffer input_value, ByteBuffer param_value, PointerBuffer param_value_size_ret) Returns information about the kernel object.static int
clGetKernelSubGroupInfo
(long kernel, long device, int param_name, ByteBuffer input_value, PointerBuffer param_value, PointerBuffer param_value_size_ret) Returns information about the kernel object.static int
clSetDefaultDeviceCommandQueue
(long context, long device, long command_queue) Replaces a default device command queue created withCreateCommandQueueWithProperties
and theQUEUE_ON_DEVICE_DEFAULT
flag.static long
nclCloneKernel
(long source_kernel, long errcode_ret) Unsafe version of:CloneKernel
static long
nclCreateProgramWithIL
(long context, long il, long length, long errcode_ret) Unsafe version of:CreateProgramWithIL
static int
nclEnqueueSVMMigrateMem
(long command_queue, int num_svm_pointers, long svm_pointers, long sizes, long flags, int num_events_in_wait_list, long event_wait_list, long event) Unsafe version of:EnqueueSVMMigrateMem
static int
nclGetDeviceAndHostTimer
(long device, long device_timestamp, long host_timestamp) Unsafe version of:GetDeviceAndHostTimer
static int
nclGetHostTimer
(long device, long host_timestamp) Unsafe version of:GetHostTimer
static int
nclGetKernelSubGroupInfo
(long kernel, long device, int param_name, long input_value_size, long input_value, long param_value_size, long param_value, long param_value_size_ret) Unsafe version of:GetKernelSubGroupInfo
Methods inherited from class org.lwjgl.opencl.CL20
clCreateCommandQueueWithProperties, clCreateCommandQueueWithProperties, clCreatePipe, clCreatePipe, clCreateSamplerWithProperties, clCreateSamplerWithProperties, clEnqueueSVMFree, clEnqueueSVMMap, clEnqueueSVMMemcpy, clEnqueueSVMMemFill, clEnqueueSVMUnmap, clGetPipeInfo, clGetPipeInfo, clGetPipeInfo, clSetKernelArgSVMPointer, clSetKernelExecInfo, clSetKernelExecInfo, clSetKernelExecInfo, clSetKernelExecInfo, clSVMAlloc, clSVMFree, nclCreateCommandQueueWithProperties, nclCreatePipe, nclCreateSamplerWithProperties, nclEnqueueSVMFree, nclEnqueueSVMMap, nclEnqueueSVMMemcpy, nclEnqueueSVMMemFill, nclEnqueueSVMUnmap, nclGetPipeInfo, nclSetKernelArgSVMPointer, nclSetKernelExecInfo, nclSVMAlloc, nclSVMFree
Methods inherited from class org.lwjgl.opencl.CL12
clCompileProgram, clCompileProgram, clCreateImage, clCreateImage, clCreateImage, clCreateImage, clCreateImage, clCreateImage, clCreateImage, clCreateImage, clCreateProgramWithBuiltInKernels, clCreateProgramWithBuiltInKernels, clCreateProgramWithBuiltInKernels, clCreateProgramWithBuiltInKernels, clCreateProgramWithBuiltInKernels, clCreateSubDevices, clCreateSubDevices, clEnqueueBarrierWithWaitList, clEnqueueFillBuffer, clEnqueueFillImage, clEnqueueFillImage, clEnqueueFillImage, clEnqueueFillImage, clEnqueueFillImage, clEnqueueMarkerWithWaitList, clEnqueueMigrateMemObjects, clGetExtensionFunctionAddressForPlatform, clGetExtensionFunctionAddressForPlatform, clGetKernelArgInfo, clGetKernelArgInfo, clGetKernelArgInfo, clGetKernelArgInfo, clGetKernelArgInfo, clLinkProgram, clLinkProgram, clLinkProgram, clLinkProgram, clLinkProgram, clReleaseDevice, clRetainDevice, clUnloadPlatformCompiler, nclCompileProgram, nclCreateImage, nclCreateProgramWithBuiltInKernels, nclCreateSubDevices, nclEnqueueBarrierWithWaitList, nclEnqueueFillBuffer, nclEnqueueFillImage, nclEnqueueMarkerWithWaitList, nclEnqueueMigrateMemObjects, nclGetExtensionFunctionAddressForPlatform, nclGetKernelArgInfo, nclLinkProgram
Methods inherited from class org.lwjgl.opencl.CL11
clCreateSubBuffer, clCreateSubBuffer, clCreateUserEvent, clCreateUserEvent, clEnqueueCopyBufferRect, clEnqueueReadBufferRect, clEnqueueReadBufferRect, clEnqueueReadBufferRect, clEnqueueReadBufferRect, clEnqueueReadBufferRect, clEnqueueReadBufferRect, clEnqueueReadBufferRect, clEnqueueReadBufferRect, clEnqueueReadBufferRect, clEnqueueWriteBufferRect, clEnqueueWriteBufferRect, clEnqueueWriteBufferRect, clEnqueueWriteBufferRect, clEnqueueWriteBufferRect, clEnqueueWriteBufferRect, clEnqueueWriteBufferRect, clEnqueueWriteBufferRect, clEnqueueWriteBufferRect, clSetEventCallback, clSetMemObjectDestructorCallback, clSetUserEventStatus, nclCreateSubBuffer, nclCreateUserEvent, nclEnqueueCopyBufferRect, nclEnqueueReadBufferRect, nclEnqueueWriteBufferRect, nclSetEventCallback, nclSetMemObjectDestructorCallback
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
-
Field Details
-
CL_VERSION_2_1
public static final int CL_VERSION_2_1OpenCL Version.- See Also:
-
CL_PLATFORM_HOST_TIMER_RESOLUTION
public static final int CL_PLATFORM_HOST_TIMER_RESOLUTIONAccepted as theparam_name
parameter ofGetPlatformInfo
, returns acl_ulong
value.Returns the resolution of the host timer in nanoseconds as used by
GetDeviceAndHostTimer
.Support for device and host timer synchronization is required for platforms supporting OpenCL 2.1 or 2.2. This value must be 0 for devices that do not support device and host timer synchronization.
- See Also:
-
CL_DEVICE_IL_VERSION
public static final int CL_DEVICE_IL_VERSIONAccepted as theparam_name
parameter ofGetDeviceInfo
, returns achar[]
value.The intermediate languages that can be supported by
CreateProgramWithIL
for this device. Returns a space-separated list of IL version strings of the form<IL_Prefix>_<Major_Version>.<Minor_Version>
.For an OpenCL 2.1 or 2.2 device, SPIR-V is a required IL prefix.
If the device does not support intermediate language programs, the value must be
""
(an empty string).- See Also:
-
CL_DEVICE_MAX_NUM_SUB_GROUPS
public static final int CL_DEVICE_MAX_NUM_SUB_GROUPSAccepted as theparam_name
parameter ofGetDeviceInfo
, returns acl_uint
value.Maximum number of sub-groups in a workgroup that a device is capable of executing on a single compute unit, for any given kernel instance running on the device.
The minimum value is 1 if the device supports subgroups, and must be 0 for devices that do not support subgroups. Support for subgroups is required for an OpenCL 2.1 or 2.2 device.
- See Also:
-
CL_DEVICE_SUB_GROUP_INDEPENDENT_FORWARD_PROGRESS
public static final int CL_DEVICE_SUB_GROUP_INDEPENDENT_FORWARD_PROGRESSAccepted as theparam_name
parameter ofGetDeviceInfo
, returns acl_bool
value.Is
TRUE
if this device supports independent forward progress of sub-groups,FALSE
otherwise.This query must return
TRUE
for devices that support thecl_khr_subgroups
extension, and must returnFALSE
for devices that do not support subgroups.- See Also:
-
CL_QUEUE_DEVICE_DEFAULT
public static final int CL_QUEUE_DEVICE_DEFAULTAccepted as theparam_name
parameter ofGetCommandQueueInfo
, returns acl_command_queue
value.Return the current default command queue for the underlying device.
- See Also:
-
CL_UNORM_INT_101010_2
public static final int CL_UNORM_INT_101010_2cl_channel_type- See Also:
-
CL_PROGRAM_IL
public static final int CL_PROGRAM_ILAccepted as theparam_name
parameter ofGetProgramInfo
, returns achar[]
value.Returns the program IL for programs created with
CreateProgramWithIL
.If program is created with
CreateProgramWithSource
,CreateProgramWithBinary
orCreateProgramWithBuiltInKernels
the memory pointed to byparam_value
will be unchanged andparam_value_size_ret
will be set to 0.- See Also:
-
CL_KERNEL_MAX_NUM_SUB_GROUPS
public static final int CL_KERNEL_MAX_NUM_SUB_GROUPSAccepted as theparam_name
parameter ofGetKernelInfo
, returns asize_t
value.This provides a mechanism for the application to query the maximum number of sub-groups that may make up each workgroup to execute a kernel on a specific device given by device. The OpenCL implementation uses the resource requirements of the kernel (register usage etc.) to determine what this work-group size should be. The returned value may be used to compute a work-group size to enqueue the kernel with to give a round number of sub-groups for an enqueue.
- See Also:
-
CL_KERNEL_COMPILE_NUM_SUB_GROUPS
public static final int CL_KERNEL_COMPILE_NUM_SUB_GROUPSAccepted as theparam_name
parameter ofGetKernelInfo
, returns asize_t
value.Returns the number of sub-groups per workgroup specified in the kernel source or IL. If the sub-group count is not specified then 0 is returned.
- See Also:
-
CL_KERNEL_MAX_SUB_GROUP_SIZE_FOR_NDRANGE
public static final int CL_KERNEL_MAX_SUB_GROUP_SIZE_FOR_NDRANGEAccepted as theparam_name
parameter ofGetKernelSubGroupInfo
, returns asize_t
value.Returns the maximum sub-group size for this kernel. All sub-groups must be the same size, while the last subgroup in any work-group (i.e. the subgroup with the maximum index) could be the same or smaller size.
The
input_value
must be an array ofsize_t
values corresponding to the local work size parameter of the intended dispatch. The number of dimensions in the ND-range will be inferred from the value specified forinput_value_size
.- See Also:
-
CL_KERNEL_SUB_GROUP_COUNT_FOR_NDRANGE
public static final int CL_KERNEL_SUB_GROUP_COUNT_FOR_NDRANGEAccepted as theparam_name
parameter ofGetKernelSubGroupInfo
, returns asize_t
value.Returns the number of sub-groups that will be present in each workgroup for a given local work size. All workgroups, apart from the last workgroup in each dimension in the presence of nonuniform work-group sizes, will have the same number of subgroups.
The
input_value
must be an array ofsize_t
values corresponding to the local work size parameter of the intended dispatch. The number of dimensions in the ND-range will be inferred from the value specified forinput_value_size
.- See Also:
-
CL_KERNEL_LOCAL_SIZE_FOR_SUB_GROUP_COUNT
public static final int CL_KERNEL_LOCAL_SIZE_FOR_SUB_GROUP_COUNTAccepted as theparam_name
parameter ofGetKernelSubGroupInfo
, returns asize_t[]
value.Returns the local size that will generate the requested number of sub-groups for the kernel. The output array must be an array of
size_t
values corresponding to the local size parameter. Any returned workgroup will have one dimension. Other dimensions inferred from the value specified forparam_value_size
will be filled with the value 1. The returned value will produce an exact number of sub-groups and result in no partial groups for an executing kernel except in the case where the last work-group in a dimension has a size different from that of the other groups. If no work-group size can accommodate the requested number of sub-groups, 0 will be returned in each element of the return array.- See Also:
-
-
Method Details
-
clSetDefaultDeviceCommandQueue
public static int clSetDefaultDeviceCommandQueue(long context, long device, long command_queue) Replaces a default device command queue created withCreateCommandQueueWithProperties
and theQUEUE_ON_DEVICE_DEFAULT
flag.- Parameters:
context
- a valid OpenCL contextdevice
- a OpenCL device associated withcontext
command_queue
- a valid command-queue fordevice
- Returns:
SUCCESS
if the function is executed successfully. Otherwise, it returns one of the following errors:INVALID_CONTEXT
ifcontext
is not a valid context.INVALID_DEVICE
ifdevice
is not a valid device or is not associated withcontext
.INVALID_COMMAND_QUEUE
ifcommand_queue
is not a valid command-queue.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:
-
nclGetDeviceAndHostTimer
public static int nclGetDeviceAndHostTimer(long device, long device_timestamp, long host_timestamp) Unsafe version of:GetDeviceAndHostTimer
-
clGetDeviceAndHostTimer
public static int clGetDeviceAndHostTimer(long device, LongBuffer device_timestamp, LongBuffer host_timestamp) Returns a reasonably synchronized pair of timestamps from the device timer and the host timer as seen by device. Implementations may need to execute this query with a high latency in order to provide reasonable synchronization of the timestamps. The host timestamp and device timestamp returned by this function andGetHostTimer
each have an implementation defined timebase. The timestamps will always be in their respective timebases regardless of which query function is used. The timestamp returned fromGetEventProfilingInfo
for an event on a device and a device timestamp queried from the same device will always be in the same timebase.- Parameters:
device
- a device returned byGetDeviceIDs
device_timestamp
- will be updated with the value of the device timer in nanoseconds. The resolution of the timer is the same as the device profiling timer returned byGetDeviceInfo
and theDEVICE_PROFILING_TIMER_RESOLUTION
query.host_timestamp
- will be updated with the value of the host timer in nanoseconds at the closest possible point in time to that at whichdevice_timestamp
was returned. The resolution of the timer may be queried viaGetPlatformInfo
and the flagPLATFORM_HOST_TIMER_RESOLUTION
.- Returns:
SUCCESS
with a time value inhost_timestamp
if provided. Otherwise, it returns one of the following errors:INVALID_DEVICE
ifdevice
is not a valid OpenCL device.INVALID_VALUE
ifhost_timestamp
ordevice_timestamp
isNULL
.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:
-
nclGetHostTimer
public static int nclGetHostTimer(long device, long host_timestamp) Unsafe version of:GetHostTimer
-
clGetHostTimer
Returns the current value of the host clock as seen by device. This value is in the same timebase as thehost_timestamp
returned fromGetDeviceAndHostTimer
. The implementation will return with as low a latency as possible to allow a correlation with a subsequent application sampled time. The host timestamp and device timestamp returned by this function andGetDeviceAndHostTimer
each have an implementation defined timebase. The timestamps will always be in their respective timebases regardless of which query function is used. The timestamp returned fromGetEventProfilingInfo
for an event on a device and a device timestamp queried from the same device will always be in the same timebase.- Parameters:
device
- a device returned byGetDeviceIDs
host_timestamp
- will be updated with the value of the current timer in nanoseconds. The resolution of the timer may be queried viaGetPlatformInfo
and the flagPLATFORM_HOST_TIMER_RESOLUTION
.- Returns:
SUCCESS
with a time value inhost_timestamp
if provided. Otherwise, it returns one of the following errors:INVALID_DEVICE
ifdevice
is not a valid OpenCL device.INVALID_VALUE
ifhost_timestamp
isNULL
.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:
-
nclCreateProgramWithIL
public static long nclCreateProgramWithIL(long context, long il, long length, long errcode_ret) Unsafe version of:CreateProgramWithIL
- Parameters:
length
- the number of bytes inil
-
clCreateProgramWithIL
public static long clCreateProgramWithIL(long context, ByteBuffer il, @Nullable IntBuffer errcode_ret) Creates a program object for a context, and loads the IL pointed to byil
and with length in byteslength
into the program object.- Parameters:
context
- a valid OpenCL contextil
- a pointer to alength
-byte block of memory containing SPIR-V or an implementation-defined intermediate languageerrcode_ret
- will return an appropriate error code. Iferrcode_ret
isNULL
, no error code is returned.- Returns:
- a valid non-zero program object and
errcode_ret
is set toSUCCESS
if the program object is created successfully. Otherwise, it returns aNULL
value with one of the following error values returned inerrcode_ret
:INVALID_CONTEXT
ifcontext
is not a valid context.INVALID_VALUE
ifil
isNULL
or iflength
is zero.INVALID_VALUE
if thelength
-byte memory pointed to byil
does not contain well-formed intermediate language input that can be consumed by the OpenCL runtime.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:
-
nclCloneKernel
public static long nclCloneKernel(long source_kernel, long errcode_ret) Unsafe version of:CloneKernel
-
clCloneKernel
Makes a shallow copy of the kernel object, its arguments and any information passed to the kernel object usingSetKernelExecInfo
. If the kernel object was ready to be enqueued before copying it, the clone of the kernel object is ready to enqueue.The returned kernel object is an exact copy of
source_kernel
, with one caveat: the reference count on the returned kernel object is set as if it had been returned byCreateKernel
. The reference count ofsource_kernel
will not be changed.The resulting kernel will be in the same state as if
CreateKernel
is called to create the resultant kernel with the same arguments as those used to createsource_kernel
, the latest call toSetKernelArg
orSetKernelArgSVMPointer
for each argument index applied to kernel and the last call toSetKernelExecInfo
for each value of the param name parameter are applied to the new kernel object.All arguments of the new kernel object must be intact and it may be correctly used in the same situations as kernel except those that assume a pre-existing reference count. Setting arguments on the new kernel object will not affect
source_kernel
except insofar as the argument points to a shared underlying entity and in that situation behavior is as if two kernel objects had been created and the same argument applied to each. Only the data stored in the kernel object is copied; data referenced by the kernel's arguments are not copied. For example, if a buffer or pointer argument is set on a kernel object, the pointer is copied but the underlying memory allocation is not.- Parameters:
source_kernel
- a validcl_kernel
object that will be copied.source_kernel
will not be modified in any way by this function.errcode_ret
- will return an appropriate error code. Iferrcode_ret
isNULL
, no error code is returned.- Returns:
- a valid non-zero kernel object and
errcode_ret
is set toSUCCESS
if the kernel is successfully copied. Otherwise it returns aNULL
value with one of the following error values returned inerrcode_ret
:INVALID_KERNEL
ifsource_kernel
is not a valid kernel 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:
-
nclGetKernelSubGroupInfo
public static int nclGetKernelSubGroupInfo(long kernel, long device, int param_name, long input_value_size, long input_value, long param_value_size, long param_value, long param_value_size_ret) Unsafe version of:GetKernelSubGroupInfo
- Parameters:
input_value_size
- the size in bytes of memory pointed to byinput_value
param_value_size
- the size in bytes of memory pointed to byparam_value
. This size must be ≥ size of return type. Ifparam_value
isNULL
, it is ignored.
-
clGetKernelSubGroupInfo
public static int clGetKernelSubGroupInfo(long kernel, long device, int param_name, @Nullable ByteBuffer input_value, @Nullable ByteBuffer param_value, @Nullable PointerBuffer param_value_size_ret) Returns information about the kernel object.- Parameters:
kernel
- the kernel object being querieddevice
- a specific device in the list of devices associated withkernel
. The list of devices is the list of devices in the OpenCL context that is associated withkernel
. If the list of devices associated with kernel is a single device, device can be aNULL
value.param_name
- the information to query. One of:KERNEL_MAX_NUM_SUB_GROUPS
KERNEL_COMPILE_NUM_SUB_GROUPS
KERNEL_MAX_SUB_GROUP_SIZE_FOR_NDRANGE
KERNEL_SUB_GROUP_COUNT_FOR_NDRANGE
KERNEL_LOCAL_SIZE_FOR_SUB_GROUP_COUNT
input_value
- a pointer to memory where the appropriate parameterization of the query is passed from. Ifinput_value
isNULL
, it is ignored.param_value
- a pointer to memory where the appropriate result being queried is returned. Ifparam_value
isNULL
, it is ignored.param_value_size_ret
- the actual size in bytes of data being queried byparam_value
. IfNULL
, it is ignored.- Returns:
SUCCESS
if the function is executed successfully. Otherwise, it returns one of the following errors:INVALID_DEVICE
ifdevice
is not in the list of devices associated withkernel
or ifdevice
isNULL
but there is more than one device associated withkernel
.INVALID_VALUE
ifparam_name
is not valid, or if size in bytes specified byparam_value
is < size of return type andparam_value
is notNULL
.INVALID_VALUE
ifparam_name
isKERNEL_SUB_GROUP_SIZE_FOR_NDRANGE
and the size in bytes specified byinput_value_size
is not valid or ifinput_value
isNULL
.INVALID_KERNEL
ifkernel
is not a valid kernel 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:
-
clGetKernelSubGroupInfo
public static int clGetKernelSubGroupInfo(long kernel, long device, int param_name, @Nullable ByteBuffer input_value, @Nullable PointerBuffer param_value, @Nullable PointerBuffer param_value_size_ret) Returns information about the kernel object.- Parameters:
kernel
- the kernel object being querieddevice
- a specific device in the list of devices associated withkernel
. The list of devices is the list of devices in the OpenCL context that is associated withkernel
. If the list of devices associated with kernel is a single device, device can be aNULL
value.param_name
- the information to query. One of:KERNEL_MAX_NUM_SUB_GROUPS
KERNEL_COMPILE_NUM_SUB_GROUPS
KERNEL_MAX_SUB_GROUP_SIZE_FOR_NDRANGE
KERNEL_SUB_GROUP_COUNT_FOR_NDRANGE
KERNEL_LOCAL_SIZE_FOR_SUB_GROUP_COUNT
input_value
- a pointer to memory where the appropriate parameterization of the query is passed from. Ifinput_value
isNULL
, it is ignored.param_value
- a pointer to memory where the appropriate result being queried is returned. Ifparam_value
isNULL
, it is ignored.param_value_size_ret
- the actual size in bytes of data being queried byparam_value
. IfNULL
, it is ignored.- Returns:
SUCCESS
if the function is executed successfully. Otherwise, it returns one of the following errors:INVALID_DEVICE
ifdevice
is not in the list of devices associated withkernel
or ifdevice
isNULL
but there is more than one device associated withkernel
.INVALID_VALUE
ifparam_name
is not valid, or if size in bytes specified byparam_value
is < size of return type andparam_value
is notNULL
.INVALID_VALUE
ifparam_name
isKERNEL_SUB_GROUP_SIZE_FOR_NDRANGE
and the size in bytes specified byinput_value_size
is not valid or ifinput_value
isNULL
.INVALID_KERNEL
ifkernel
is not a valid kernel 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:
-
nclEnqueueSVMMigrateMem
public static int nclEnqueueSVMMigrateMem(long command_queue, int num_svm_pointers, long svm_pointers, long sizes, long flags, int num_events_in_wait_list, long event_wait_list, long event) Unsafe version of:EnqueueSVMMigrateMem
- Parameters:
num_svm_pointers
- the number of pointers in the specifiedsvm_pointers
array, and the number of sizes in thesizes
array, ifsizes
is notNULL
.num_events_in_wait_list
- the number of events inevent_wait_list
-
clEnqueueSVMMigrateMem
public static int clEnqueueSVMMigrateMem(long command_queue, PointerBuffer svm_pointers, @Nullable PointerBuffer sizes, long flags, @Nullable PointerBuffer event_wait_list, @Nullable PointerBuffer event) Enqueues a command to indicate which device a set of ranges of SVM allocations should be associated with. Once the event returned byclEnqueueSVMMigrateMem
has becomeCOMPLETE
, the ranges specified by svm pointers and sizes have been successfully migrated to the device associated with command queue.The user is responsible for managing the event dependencies associated with this command in order to avoid overlapping access to SVM allocations. Improperly specified event dependencies passed to
clEnqueueSVMMigrateMem
could result in undefined results.- Parameters:
command_queue
- a valid host command queue. The specified set of allocation ranges will be migrated to the OpenCL device associated withcommand_queue
.svm_pointers
- a pointer to an array of pointers. Each pointer in this array must be within an allocation produced by a call toSVMAlloc
.sizes
- an array of sizes. The pairsvm_pointers[i]
andsizes[i]
together define the starting address and number of bytes in a range to be migrated.sizes
may beNULL
indicating that every allocation containing anysvm_pointer[i]
is to be migrated. Also, ifsizes[i]
is zero, then the entire allocation containingsvm_pointer[i]
is migrated.flags
- a bit-field that is used to specify migration optionsevent_wait_list
- a list of events that need to complete before this particular command can be executed. Ifevent_wait_list
isNULL
, then this particular command does not wait on any event to complete. The events specified inevent_wait_list
act as synchronization points. The context associated with events inevent_wait_list
andcommand_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 beNULL
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 theevent_wait_list
and theevent
arguments are notNULL
, the event argument should not refer to an element of theevent_wait_list
array.- Returns:
SUCCESS
if the function is executed successfully. Otherwise, it returns one of the following errors:INVALID_COMMAND_QUEUE
ifcommand_queue
is not a valid command-queue.INVALID_CONTEXT
if the context associated withcommand_queue
and events inevent_wait_list
are not the sameINVALID_VALUE
ifnum_svm_pointers
is zero orsvm_pointers
isNULL
.INVALID_VALUE
ifsizes[i]
is non-zero range[svm_pointers[i], svm_pointers[i]+sizes[i])
is not contained within an existingSVMAlloc
allocation.INVALID_EVENT_WAIT_LIST
ifevent_wait_list
isNULL
andnum_events_in_wait_list
> 0, orevent_wait_list
is notNULL
andnum_events_in_wait_list
is 0, or if event objects inevent_wait_list
are not valid events.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:
-
clGetDeviceAndHostTimer
public static int clGetDeviceAndHostTimer(long device, long[] device_timestamp, long[] host_timestamp) Array version of:GetDeviceAndHostTimer
- See Also:
-
clGetHostTimer
public static int clGetHostTimer(long device, long[] host_timestamp) Array version of:GetHostTimer
- See Also:
-
clCreateProgramWithIL
Array version of:CreateProgramWithIL
- See Also:
-
clCloneKernel
public static long clCloneKernel(long source_kernel, @Nullable int[] errcode_ret) Array version of:CloneKernel
- See Also:
-