org.lwjgl.opencl.CLCapabilities Maven / Gradle / Ivy
Go to download
Show more of this group Show more artifacts with this name
Show all versions of lwjgl-opencl Show documentation
Show all versions of lwjgl-opencl Show documentation
An open, royalty-free standard for cross-platform, parallel programming of diverse processors found in personal computers, servers, mobile devices and embedded platforms.
/*
* Copyright LWJGL. All rights reserved.
* License terms: https://www.lwjgl.org/license
* MACHINE GENERATED FILE, DO NOT EDIT
*/
package org.lwjgl.opencl;
import org.lwjgl.system.*;
import java.util.Set;
/**
* Defines the capabilities of an OpenCL platform or device.
*
* The instance returned by {@link CL#createPlatformCapabilities} exposes the functionality present on either the platform or any of its devices.
* This is unlike the {@link CL10#CL_PLATFORM_EXTENSIONS PLATFORM_EXTENSIONS} string, which returns only platform functionality, supported across all platform devices.
*
* The instance returned by {@link CL#createDeviceCapabilities} exposes only the functionality available on that particular device.
*/
public class CLCapabilities {
public final long
clBuildProgram,
clCloneKernel,
clCompileProgram,
clCreateAcceleratorINTEL,
clCreateBuffer,
clCreateCommandQueue,
clCreateCommandQueueWithProperties,
clCreateCommandQueueWithPropertiesAPPLE,
clCreateContext,
clCreateContextFromType,
clCreateEventFromEGLSyncKHR,
clCreateEventFromGLsyncKHR,
clCreateFromEGLImageKHR,
clCreateFromGLBuffer,
clCreateFromGLRenderbuffer,
clCreateFromGLTexture,
clCreateFromGLTexture2D,
clCreateFromGLTexture3D,
clCreateFromVA_APIMediaSurfaceINTEL,
clCreateImage,
clCreateImage2D,
clCreateImage3D,
clCreateKernel,
clCreateKernelsInProgram,
clCreatePipe,
clCreateProgramWithBinary,
clCreateProgramWithBuiltInKernels,
clCreateProgramWithIL,
clCreateProgramWithSource,
clCreateSampler,
clCreateSamplerWithProperties,
clCreateSubBuffer,
clCreateSubDevices,
clCreateSubDevicesEXT,
clCreateUserEvent,
clEnqueueAcquireEGLObjectsKHR,
clEnqueueAcquireGLObjects,
clEnqueueAcquireVA_APIMediaSurfacesINTEL,
clEnqueueBarrier,
clEnqueueBarrierWithWaitList,
clEnqueueCopyBuffer,
clEnqueueCopyBufferRect,
clEnqueueCopyBufferToImage,
clEnqueueCopyImage,
clEnqueueCopyImageToBuffer,
clEnqueueFillBuffer,
clEnqueueFillImage,
clEnqueueMakeBuffersResidentAMD,
clEnqueueMapBuffer,
clEnqueueMapImage,
clEnqueueMarker,
clEnqueueMarkerWithWaitList,
clEnqueueMigrateMemObjectEXT,
clEnqueueMigrateMemObjects,
clEnqueueNDRangeKernel,
clEnqueueNativeKernel,
clEnqueueReadBuffer,
clEnqueueReadBufferRect,
clEnqueueReadImage,
clEnqueueReleaseEGLObjectsKHR,
clEnqueueReleaseGLObjects,
clEnqueueReleaseVA_APIMediaSurfacesINTEL,
clEnqueueSVMFree,
clEnqueueSVMMap,
clEnqueueSVMMemFill,
clEnqueueSVMMemcpy,
clEnqueueSVMMigrateMem,
clEnqueueSVMUnmap,
clEnqueueTask,
clEnqueueUnmapMemObject,
clEnqueueWaitForEvents,
clEnqueueWaitSignalAMD,
clEnqueueWriteBuffer,
clEnqueueWriteBufferRect,
clEnqueueWriteImage,
clEnqueueWriteSignalAMD,
clFinish,
clFlush,
clGetAcceleratorInfoINTEL,
clGetCommandQueueInfo,
clGetContextInfo,
clGetDeviceAndHostTimer,
clGetDeviceIDs,
clGetDeviceIDsFromVA_APIMediaAdapterINTEL,
clGetDeviceImageInfoQCOM,
clGetDeviceInfo,
clGetEventInfo,
clGetEventProfilingInfo,
clGetExtensionFunctionAddress,
clGetExtensionFunctionAddressForPlatform,
clGetGLContextInfoAPPLE,
clGetGLContextInfoKHR,
clGetGLObjectInfo,
clGetGLTextureInfo,
clGetHostTimer,
clGetImageInfo,
clGetKernelArgInfo,
clGetKernelInfo,
clGetKernelSubGroupInfo,
clGetKernelSubGroupInfoKHR,
clGetKernelWorkGroupInfo,
clGetMemObjectInfo,
clGetPipeInfo,
clGetPlatformIDs,
clGetPlatformInfo,
clGetProgramBuildInfo,
clGetProgramInfo,
clGetSamplerInfo,
clGetSupportedImageFormats,
clLinkProgram,
clLogMessagesToStderrAPPLE,
clLogMessagesToStdoutAPPLE,
clLogMessagesToSystemLogAPPLE,
clReleaseAcceleratorINTEL,
clReleaseCommandQueue,
clReleaseContext,
clReleaseDevice,
clReleaseDeviceEXT,
clReleaseEvent,
clReleaseKernel,
clReleaseMemObject,
clReleaseProgram,
clReleaseSampler,
clReportLiveObjectsAltera,
clRetainAcceleratorINTEL,
clRetainCommandQueue,
clRetainContext,
clRetainDevice,
clRetainDeviceEXT,
clRetainEvent,
clRetainKernel,
clRetainMemObject,
clRetainProgram,
clRetainSampler,
clSVMAlloc,
clSVMFree,
clSetDefaultDeviceCommandQueue,
clSetEventCallback,
clSetKernelArg,
clSetKernelArgSVMPointer,
clSetKernelExecInfo,
clSetMemObjectDestructorCallback,
clSetUserEventStatus,
clTerminateContextKHR,
clTrackLiveObjectsAltera,
clUnloadCompiler,
clUnloadPlatformCompiler,
clWaitForEvents;
/** When true, {@link CL10} is supported. */
public final boolean OpenCL10;
/** When true, {@link CL10GL} is supported. */
public final boolean OpenCL10GL;
/** When true, {@link CL11} is supported. */
public final boolean OpenCL11;
/** When true, {@link CL12} is supported. */
public final boolean OpenCL12;
/** When true, {@link CL12GL} is supported. */
public final boolean OpenCL12GL;
/** When true, {@link CL20} is supported. */
public final boolean OpenCL20;
/** When true, {@link CL21} is supported. */
public final boolean OpenCL21;
/** When true, {@link ALTERACompilerMode} is supported. */
public final boolean cl_altera_compiler_mode;
/** When true, {@link ALTERADeviceTemperature} is supported. */
public final boolean cl_altera_device_temperature;
/** When true, {@link ALTERALiveObjectTracking} is supported. */
public final boolean cl_altera_live_object_tracking;
/** When true, {@link AMDBusAddressableMemory} is supported. */
public final boolean cl_amd_bus_addressable_memory;
/**
* When true, the amd_compile_options extension is supported.
*
* This extension adds the following options, which are not part of the OpenCL specification:
*
*
* - -g – This is an experimental feature that lets you use the GNU project debugger, GDB, to debug kernels on x86 CPUs running Linux or
* cygwin/minGW under Windows. This option does not affect the default optimization of the OpenCL code.
* - -O0 – Specifies to the compiler not to optimize. This is equivalent to the OpenCL standard option -cl-opt-disable.
* - -f[no-]bin-source – Does [not] generate OpenCL source in the .source section. By default, the source is NOT generated.
* - -f[no-]bin-llvmir – Does [not] generate LLVM IR in the .llvmir section. By default, LLVM IR IS generated.
* - -f[no-]bin-amdil – Does [not] generate AMD IL in the .amdil section. By Default, AMD IL is NOT generated.
* - -f[no-]bin-exe – Does [not] generate the executable (ISA) in .text section. By default, the executable IS generated.
* - -f[no-]bin-hsail – Does [not] generate HSAIL/BRIG in the binary. By default, HSA IL/BRIG is NOT generated.
*
*
* To avoid source changes, there are two environment variables that can be used to change CL options during the runtime:
*
*
* - AMD_OCL_BUILD_OPTIONS – Overrides the CL options specified in {@link CL10#clBuildProgram BuildProgram}.
* - AMD_OCL_BUILD_OPTIONS_APPEND – Appends options to the options specified in {@link CL10#clBuildProgram BuildProgram}.
*
*/
public final boolean cl_amd_compile_options;
/** When true, {@link AMDDeviceAttributeQuery} is supported. */
public final boolean cl_amd_device_attribute_query;
/** When true, {@link AMDDeviceBoardName} is supported. */
public final boolean cl_amd_device_board_name;
/** When true, {@link AMDDevicePersistentMemory} is supported. */
public final boolean cl_amd_device_persistent_memory;
/** When true, {@link AMDDeviceProfilingTimerOffset} is supported. */
public final boolean cl_amd_device_profiling_timer_offset;
/** When true, {@link AMDDeviceTopology} is supported. */
public final boolean cl_amd_device_topology;
/**
* When true, the amd_event_callback extension is supported.
*
* This extension provides the ability to register event callbacks for states other than {@link CL10#CL_COMPLETE COMPLETE}. The full set of event states are allowed:
* {@link CL10#CL_QUEUED QUEUED}, {@link CL10#CL_SUBMITTED SUBMITTED}, and {@link CL10#CL_RUNNING RUNNING}.
*/
public final boolean cl_amd_event_callback;
/**
* When true, the amd_fp64 extension is supported.
*
* This extension provides a subset of the functionality of that provided by the cl_khr_fp64 extension. When enabled, the compiler recognizes the double
* scalar and vector types, compiles expressions involving those types, and accepts calls to all builtin functions enabled by the cl_khr_fp64 extension.
* However, this extension does not guarantee that all cl_khr_fp64 built in functions are implemented and does not guarantee that the built in functions
* that have been implemented would be considered conformant to the cl_khr_fp64 extension.
*/
public final boolean cl_amd_fp64;
/**
* When true, the amd_media_ops extension is supported.
*
* The directive when enabled adds the following built-in functions to the OpenCL language.
*
* Note: typen denote opencl scalar type {n = 1} and vector types {n = 4, 8, 16}.
Build-in Function
uint amd_pack(float4 src)
Description
dst = ((((uint)src.s0) & 0xff) )
+ ((((uint)src.s1) & 0xff) << 8)
+ ((((uint)src.s2) & 0xff) << 16)
+ ((((uint)src.s3) & 0xff) << 24)
Build-in Function
floatn amd_unpack3(unitn src)
Description
dst.s0 = (float)((src.s0 >> 24) & 0xff)
similar operation applied to other components of the vectors
Build-in Function
floatn amd_unpack2 (unitn src)
Description
dst.s0 = (float)((src.s0 >> 16) & 0xff)
similar operation applied to other components of the vectors
Build-in Function
floatn amd_unpack1 (unitn src)
Description
dst.s0 = (float)((src.s0 >> 8) & 0xff)
similar operation applied to other components of the vectors
Build-in Function
floatn amd_unpack0 (unitn src)
Description
dst.s0 = (float)(src.s0 & 0xff)
similar operation applied to other components of the vectors
Build-in Function
uintn amd_bitalign (uintn src0, uintn src1, uintn src2)
Description
dst.s0 = (uint) (((((long)src0.s0) << 32) | (long)src1.s0) >> (src2.s0 & 31))
similar operation applied to other components of the vectors.
Build-in Function
uintn amd_bytealign (uintn src0, uintn src1, uintn src2)
Description
dst.s0 = (uint) (((((long)src0.s0) << 32) | (long)src1.s0) >> ((src2.s0 & 3)*8))
similar operation applied to other components of the vectors
Build-in Function
uintn amd_lerp (uintn src0, uintn src1, uintn src2)
Description
dst.s0 = (((((src0.s0 >> 0) & 0xff) + ((src1.s0 >> 0) & 0xff) + ((src2.s0 >> 0) & 1)) >> 1) << 0) +
(((((src0.s0 >> 8) & 0xff) + ((src1.s0 >> 8) & 0xff) + ((src2.s0 >> 8) & 1)) >> 1) << 8) +
(((((src0.s0 >> 16) & 0xff) + ((src1.s0 >> 16) & 0xff) + ((src2.s0 >> 16) & 1)) >> 1) << 16) +
(((((src0.s0 >> 24) & 0xff) + ((src1.s0 >> 24) & 0xff) + ((src2.s0 >> 24) & 1)) >> 1) << 24);
similar operation applied to other components of the vectors
Build-in Function
uintn amd_sad (uintn src0, uintn src1, uintn src2)
Description
dst.s0 = src2.s0 +
abs(((src0.s0 >> 0) & 0xff) - ((src1.s0 >> 0) & 0xff)) +
abs(((src0.s0 >> 8) & 0xff) - ((src1.s0 >> 8) & 0xff)) +
abs(((src0.s0 >> 16) & 0xff) - ((src1.s0 >> 16) & 0xff)) +
abs(((src0.s0 >> 24) & 0xff) - ((src1.s0 >> 24) & 0xff));
similar operation applied to other components of the vectors
Build-in Function
uintn amd_sadhi (uintn src0, uintn src1n, uintn src2)
Description
dst.s0 = src2.s0 +
(abs(((src0.s0 >> 0) & 0xff) - ((src1.s0 >> 0) & 0xff)) << 16) +
(abs(((src0.s0 >> 8) & 0xff) - ((src1.s0 >> 8) & 0xff)) << 16) +
(abs(((src0.s0 >> 16) & 0xff) - ((src1.s0 >> 16) & 0xff)) << 16) +
(abs(((src0.s0 >> 24) & 0xff) - ((src1.s0 >> 24) & 0xff)) << 16);
similar operation applied to other components of the vectors
Build-in Function
uint amd_sad4(uint4 src0, uint4 src1, uint src2)
Description
dst = src2 +
abs(((src0.s0 >> 0) & 0xff) - ((src1.s0 >> 0) & 0xff)) +
abs(((src0.s0 >> 8) & 0xff) - ((src1.s0 >> 8) & 0xff)) +
abs(((src0.s0 >> 16) & 0xff) - ((src1.s0 >> 16) & 0xff)) +
abs(((src0.s0 >> 24) & 0xff) - ((src1.s0 >> 24) & 0xff)) +
abs(((src0.s1 >> 0) & 0xff) - ((src1.s0 >> 0) & 0xff)) +
abs(((src0.s1 >> 8) & 0xff) - ((src1.s1 >> 8) & 0xff)) +
abs(((src0.s1 >> 16) & 0xff) - ((src1.s1 >> 16) & 0xff)) +
abs(((src0.s1 >> 24) & 0xff) - ((src1.s1 >> 24) & 0xff)) +
abs(((src0.s2 >> 0) & 0xff) - ((src1.s2 >> 0) & 0xff)) +
abs(((src0.s2 >> 8) & 0xff) - ((src1.s2 >> 8) & 0xff)) +
abs(((src0.s2 >> 16) & 0xff) - ((src1.s2 >> 16) & 0xff)) +
abs(((src0.s2 >> 24) & 0xff) - ((src1.s2 >> 24) & 0xff)) +
abs(((src0.s3 >> 0) & 0xff) - ((src1.s3 >> 0) & 0xff)) +
abs(((src0.s3 >> 8) & 0xff) - ((src1.s3 >> 8) & 0xff)) +
abs(((src0.s3 >> 16) & 0xff) - ((src1.s3 >> 16) & 0xff)) +
abs(((src0.s3 >> 24) & 0xff) - ((src1.s3 >> 24) & 0xff));
*/
public final boolean cl_amd_media_ops;
/**
* When true, the amd_media_ops2 extension is supported.
*
* The directive when enabled adds the following built-in functions to the OpenCL language.
*
* Note: typen denote open scalar type { n = 1 } and vector types { n = 2, 4, 8, 16 }.
Build-in Function
uintn amd_msad (uintn src0, uintn src1, uintn src2)
Description
uchar4 src0u8 = as_uchar4(src0.s0);
uchar4 src1u8 = as_uchar4(src1.s0);
dst.s0 = src2.s0 +
((src1u8.s0 == 0) ? 0 : abs(src0u8.s0 - src1u8.s0)) +
((src1u8.s1 == 0) ? 0 : abs(src0u8.s1 - src1u8.s1)) +
((src1u8.s2 == 0) ? 0 : abs(src0u8.s2 - src1u8.s2)) +
((src1u8.s3 == 0) ? 0 : abs(src0u8.s3 - src1u8.s3));
similar operation applied to other components of the vectors
Build-in Function
ulongn amd_qsad (ulongn src0, uintn src1, ulongn src2)
Description
uchar8 src0u8 = as_uchar8(src0.s0);
ushort4 src2u16 = as_ushort4(src2.s0);
ushort4 dstu16;
dstu16.s0 = amd_sad(as_uint(src0u8.s0123), src1.s0, src2u16.s0);
dstu16.s1 = amd_sad(as_uint(src0u8.s1234), src1.s0, src2u16.s1);
dstu16.s2 = amd_sad(as_uint(src0u8.s2345), src1.s0, src2u16.s2);
dstu16.s3 = amd_sad(as_uint(src0u8.s3456), src1.s0, src2u16.s3);
dst.s0 = as_uint2(dstu16);
similar operation applied to other components of the vectors
Build-in Function
ulongn amd_mqsad (ulongn src0, uintn src1, ulongn src2)
Description
uchar8 src0u8 = as_uchar8(src0.s0);
ushort4 src2u16 = as_ushort4(src2.s0);
ushort4 dstu16;
dstu16.s0 = amd_msad(as_uint(src0u8.s0123), src1.s0, src2u16.s0);
dstu16.s1 = amd_msad(as_uint(src0u8.s1234), src1.s0, src2u16.s1);
dstu16.s2 = amd_msad(as_uint(src0u8.s2345), src1.s0, src2u16.s2);
dstu16.s3 = amd_msad(as_uint(src0u8.s3456), src1.s0, src2u16.s3);
dst.s0 = as_uint2(dstu16);
similar operation applied to other components of the vectors
Build-in Function
uintn amd_sadw (uintn src0, uintn src1, uintn src2)
Description
ushort2 src0u16 = as_ushort2(src0.s0);
ushort2 src1u16 = as_ushort2(src1.s0);
dst.s0 = src2.s0 +
abs(src0u16.s0 - src1u16.s0) +
abs(src0u16.s1 - src1u16.s1);
similar operation applied to other components of the vectors
Build-in Function
uintn amd_sadd (uintn src0, uintn src1, uintn src2)
Description
dst.s0 = src2.s0 + abs(src0.s0 - src1.s0);
similar operation applied to other components of the vectors
Built-in Function:
uintn amd_bfm (uintn src0, uintn src1)
Description
dst.s0 = ((1 << (src0.s0 & 0x1f)) - 1) << (src1.s0 & 0x1f);
similar operation applied to other components of the vectors
Built-in Function:
uintn amd_bfe (uintn src0, uintn src1, uintn src2)
Description
NOTE: operator >> below represent logical right shift
offset = src1.s0 & 31;
width = src2.s0 & 31;
if width = 0
dst.s0 = 0;
else if (offset + width) < 32
dst.s0 = (src0.s0 << (32 - offset - width)) >> (32 - width);
else
dst.s0 = src0.s0 >> offset;
similar operation applied to other components of the vectors
Built-in Function:
intn amd_bfe (intn src0, uintn src1, uintn src2)
Description
NOTE: operator >> below represent arithmetic right shift
offset = src1.s0 & 31;
width = src2.s0 & 31;
if width = 0
dst.s0 = 0;
else if (offset + width) < 32
dst.s0 = src0.s0 << (32-offset-width) >> 32-width;
else
dst.s0 = src0.s0 >> offset;
similar operation applied to other components of the vectors
Built-in Function:
intn amd_median3 (intn src0, intn src1, intn src2)
uintn amd_median3 (uintn src0, uintn src1, uintn src2)
floatn amd_median3 (floatn src0, floatn src1, floattn src2)
Description
returns median of src0, src1, and src2
Built-in Function:
intn amd_min3 (intn src0, intn src1, intn src2)
uintn amd_min3 (uintn src0, uintn src1, uintn src2)
floatn amd_min3 (floatn src0, floatn src1, floattn src2)
Description
returns min of src0, src1, and src2
Built-in Function:
intn amd_max3 (intn src0, intn src1, intn src2)
uintn amd_max3 (uintn src0, uintn src1, uintn src2)
floatn amd_max3 (floatn src0, floatn src1, floattn src2)
Description
returns max of src0, src1, and src2
*/
public final boolean cl_amd_media_ops2;
/** When true, {@link AMDOfflineDevices} is supported. */
public final boolean cl_amd_offline_devices;
/**
* When true, the amd_popcnt extension is supported.
*
* This extension introduces a “population count” function called popcnt. This extension was taken into core OpenCL 1.2, and the function was renamed
* popcount. The core 1.2 popcount function is identical to the AMD extension popcnt function.
*/
public final boolean cl_amd_popcnt;
/**
* When true, the amd_predefined_macros extension is supported.
*
* The following macros are predefined when compiling OpenCL™ C kernels. These macros are defined automatically based on the device for which the code is
* being compiled.
*
* GPU devices
*
*
* - __Barts__
* - __BeaverCreek__
* - __Bheem__
* - __Bonaire__
* - __Caicos__
* - __Capeverde__
* - __Carrizo__
* - __Cayman__
* - __Cedar__
* - __Cypress__
* - __Devastator__
* - __Hainan__
* - __Iceland__
* - __Juniper__
* - __Kalindi__
* - __Kauai__
* - __Lombok__
* - __Loveland__
* - __Mullins__
* - __Oland__
* - __Pitcairn__
* - __RV710__
* - __RV730__
* - __RV740__
* - __RV770__
* - __RV790__
* - __Redwood__
* - __Scrapper__
* - __Spectre__
* - __Spooky__
* - __Tahiti__
* - __Tonga__
* - __Turks__
* - __WinterPark__
* - __GPU__
*
*
* CPU devices
*
*
* - __CPU__
* - __X86__
* - __X86_64__
*
*
* Note that __GPU__ or __CPU__ are predefined whenever a GPU or CPU device is the compilation target.
*/
public final boolean cl_amd_predefined_macros;
/**
* When true, the amd_printf extension is supported.
*
* This extension adds the built-in function printf(__constant char * restrict format, …);
*
* This function writes output to the stdout stream associated with the host application. The format string is a character sequence that:
*
*
* - is null-terminated and composed of zero and more directives,
* - ordinary characters (i.e. not %), which are copied directly to the output stream unchanged, and
* - conversion specifications, each of which can result in fetching zero or more arguments, converting them, and then writing the final result to the
* output stream.
*
*
* The format string must be resolvable at compile time; thus, it cannot be dynamically created by the executing program. (Note that the use of variadic
* arguments in the built-in printf does not imply its use in other builtins; more importantly, it is not valid to use printf in user-defined functions or
* kernels.)
*
* The OpenCL C printf closely matches the definition found as part of the C99 standard. Note that conversions introduced in the format string with % are
* supported with the following guidelines:
*
*
* - A 32-bit floating point argument is not converted to a 64-bit double, unless the extension cl_khr_fp64 is supported and enabled. This includes the
* double variants if cl_khr_fp64 is supported and defined in the corresponding compilation unit.
* - 64-bit integer types can be printed using %ld / %lx / %lu.
* - %lld / %llx / %llu are not supported and reserved for 128-bit integer types (long long).
* - All OpenCL vector types can be explicitly passed and printed using the modifier vn, where n can be 2, 3, 4, 8, or 16. This modifier appears before
* the original conversion specifier for the vector’s component type (for example, to print a float4 %v4f). Since vn is a conversion specifier, it is
* valid to apply optional flags, such as field width and precision, just as it is when printing the component types. Since a vector is an aggregate
* type, the comma separator is used between the components: 0:1, … , n-2:n-1.
*
*/
public final boolean cl_amd_printf;
/**
* When true, the amd_vec3 extension is supported.
*
* This extension adds support for vectors with three elements: float3, short3, char3, etc. This data type was added to OpenCL 1.1 as a core feature.
*/
public final boolean cl_amd_vec3;
/** When true, {@link APPLEBiasedFixedPointImageFormats} is supported. */
public final boolean cl_APPLE_biased_fixed_point_image_formats;
/** When true, {@link APPLECommandQueuePriority} is supported. */
public final boolean cl_APPLE_command_queue_priority;
/** When true, {@link APPLECommandQueueSelectComputeUnits} is supported. */
public final boolean cl_APPLE_command_queue_select_compute_units;
/** When true, {@link APPLEContextLoggingFunctions} is supported. */
public final boolean cl_APPLE_ContextLoggingFunctions;
/** When true, {@link APPLEFixedAlphaChannelOrders} is supported. */
public final boolean cl_APPLE_fixed_alpha_channel_orders;
/** When true, {@code APPLE_fp64_basic_ops} is supported. */
public final boolean cl_APPLE_fp64_basic_ops;
/** When true, {@link APPLEGLSharing} is supported. */
public final boolean cl_APPLE_gl_sharing;
/** When true, {@link APPLEQueryKernelNames} is supported. */
public final boolean cl_APPLE_query_kernel_names;
/**
* When true, the arm_core_id extension is supported.
*
* This extension provides a built-in function ({@code uint arm_get_core_id( void )}) which returns the physical core id (OpenCL Compute Unit) that a
* work-group is running on. This value is uniform for a work-group.
*
* This value can be used for a core-specific cache or atomic pool where the storage is required to be in global memory and persistent (but not ordered)
* between work-groups. This does not provide any additional ordering on top of the existing guarantees between workgroups, nor does it provide any
* guarantee of concurrent execution.
*/
public final boolean cl_arm_core_id;
/** When true, {@link ARMPrintf} is supported. */
public final boolean cl_arm_printf;
/** When true, {@link EXTAtomicCounters32} is supported. */
public final boolean cl_ext_atomic_counters_32;
/** When true, {@link EXTAtomicCounters64} is supported. */
public final boolean cl_ext_atomic_counters_64;
/** When true, {@link EXTDeviceFission} is supported. */
public final boolean cl_ext_device_fission;
/** When true, {@link EXTMigrateMemobject} is supported. */
public final boolean cl_ext_migrate_memobject;
/** When true, {@link INTELAccelerator} is supported. */
public final boolean cl_intel_accelerator;
/** When true, {@link INTELAdvancedMotionEstimation} is supported. */
public final boolean cl_intel_advanced_motion_estimation;
/** When true, {@link INTELDevicePartitionByNames} is supported. */
public final boolean cl_intel_device_partition_by_names;
/** When true, {@link INTELDriverDiagnostics} is supported. */
public final boolean cl_intel_driver_diagnostics;
/** When true, {@link INTELEGLImageYUV} is supported. */
public final boolean cl_intel_egl_image_yuv;
/** When true, {@link INTELMotionEstimation} is supported. */
public final boolean cl_intel_motion_estimation;
/** When true, {@link INTELPackedYUV} is supported. */
public final boolean cl_intel_packed_yuv;
/** When true, {@code intel_printf} is supported. */
public final boolean cl_intel_printf;
/** When true, {@link INTELRequiredSubgroupSize} is supported. */
public final boolean cl_intel_required_subgroup_size;
/** When true, {@link INTELSimultaneousSharing} is supported. */
public final boolean cl_intel_simultaneous_sharing;
/** When true, {@link INTELSubgroups} is supported. */
public final boolean cl_intel_subgroups;
/** When true, {@link INTELThreadLocalExec} is supported. */
public final boolean cl_intel_thread_local_exec;
/** When true, {@link INTELVAAPIMediaSharing} is supported. */
public final boolean cl_intel_va_api_media_sharing;
/**
* When true, the khr_3d_image_writes extension is supported.
*
* This extension adds support for kernel writes to 3D images.
*/
public final boolean cl_khr_3d_image_writes;
/**
* When true, the khr_byte_addressable_store extension is supported.
*
* This extension eliminates the restriction of not allowing writes to a pointer (or array elements) of types less than 32-bit wide in kernel program.
*/
public final boolean cl_khr_byte_addressable_store;
/** When true, {@link KHRDepthImages} is supported. */
public final boolean cl_khr_depth_images;
/**
* When true, the khr_device_enqueue_local_arg_types extension is supported.
*
* This extension allows arguments to blocks passed to enqueue_kernel functions to be declared as a pointer to any type (built-in or user-defined) in
* local memory instead of just local void *.
*/
public final boolean cl_khr_device_enqueue_local_arg_types;
/** When true, {@link KHREGLEvent} is supported. */
public final boolean cl_khr_egl_event;
/** When true, {@link KHREGLImage} is supported. */
public final boolean cl_khr_egl_image;
/** When true, {@link KHRFP16} is supported. */
public final boolean cl_khr_fp16;
/** When true, {@link KHRFP64} is supported. */
public final boolean cl_khr_fp64;
/** When true, {@link KHRGLDepthImages} is supported. */
public final boolean cl_khr_gl_depth_images;
/** When true, {@link KHRGLEvent} is supported. */
public final boolean cl_khr_gl_event;
/** When true, {@link KHRGLMSAASharing} is supported. */
public final boolean cl_khr_gl_msaa_sharing;
/** When true, {@link KHRGLSharing} is supported. */
public final boolean cl_khr_gl_sharing;
/**
* When true, the khr_global_int32_base_atomics extension is supported.
*
* This extension adds basic atomic operations on 32-bit integers in global memory.
*/
public final boolean cl_khr_global_int32_base_atomics;
/**
* When true, the khr_global_int32_extended_atomics extension is supported.
*
* This extension adds extended atomic operations on 32-bit integers in global memory.
*/
public final boolean cl_khr_global_int32_extended_atomics;
/** When true, {@link KHRICD} is supported. */
public final boolean cl_khr_icd;
/** When true, {@link KHRImage2DFromBuffer} is supported. */
public final boolean cl_khr_image2d_from_buffer;
/** When true, {@link KHRInitializeMemory} is supported. */
public final boolean cl_khr_initialize_memory;
/**
* When true, the khr_int64_base_atomics extension is supported.
*
* This extension adds basic atomic operations on 64-bit integers in both global and local memory.
*/
public final boolean cl_khr_int64_base_atomics;
/**
* When true, the khr_int64_extended_atomics extension is supported.
*
* This extension adds extended atomic operations on 64-bit integers in both global and local memory.
*/
public final boolean cl_khr_int64_extended_atomics;
/**
* When true, the khr_local_int32_base_atomics extension is supported.
*
* This extension adds basic atomic operations on 32-bit integers in local memory.
*/
public final boolean cl_khr_local_int32_base_atomics;
/**
* When true, the khr_local_int32_extended_atomics extension is supported.
*
* This extension adds extended atomic operations on 32-bit integers in local memory.
*/
public final boolean cl_khr_local_int32_extended_atomics;
/** When true, {@link KHRMipmapImage} is supported. */
public final boolean cl_khr_mipmap_image;
/**
* When true, the khr_mipmap_image_writes extension is supported.
*
* This extension adds built-in functions that can be used to write a mip-mapped image in an OpenCL C program.
*/
public final boolean cl_khr_mipmap_image_writes;
/** When true, {@link KHRPriorityHints} is supported. */
public final boolean cl_khr_priority_hints;
/**
* When true, the khr_select_fprounding_mode extension is supported.
*
* This extension adds support for specifying the rounding mode for an instruction or group of instructions in the program source.
*
* The appropriate rounding mode can be specified using #pragma OPENCL SELECT_ROUNDING_MODE rounding-mode in the program source.
*
* The #pragma OPENCL SELECT_ROUNDING_MODE sets the rounding mode for all instructions that operate on floating-point types (scalar or vector
* types) or produce floating-point values that follow this pragma in the program source until the next #pragma OPENCL SELECT_ROUNDING_MODE is
* encountered. Note that the rounding mode specified for a block of code is known at compile time. Except where otherwise documented, the callee
* functions do not inherit the rounding mode of the caller function.
*
* If this extension is enabled, the {@code __ROUNDING_MODE__} preprocessor symbol shall be defined to be one of the following according to the current
* rounding mode:
*
* #define __ROUNDING_MODE__ rte
#define __ROUNDING_MODE__ rtz
#define __ROUNDING_MODE__ rtp
#define __ROUNDING_MODE__ rtz
*
* The default rounding mode is round to nearest even. The built-in math functions, the common functions, and the geometric functions are implemented with
* the round to nearest even rounding mode.
*
* Various built-in conversions and the vstore_half and vstorea_halfn built-in functions that do not specify a rounding mode inherit the current rounding
* mode. Conversions from floating-point to integer type always use rtz mode, except where the user specifically asks for another rounding mode.
*
* Notes The above four rounding modes are defined by IEEE 754. Floating-point calculations may be carried out internally with extra precision and then
* rounded to fit into the destination type. Round to nearest even is currently the only rounding mode required by the OpenCL specification and is
* therefore the default rounding mode. In addition, only static selection of rounding mode is supported. Dynamically reconfiguring the rounding modes as
* specified by the IEEE 754 spec is not a requirement.
*/
public final boolean cl_khr_select_fprounding_mode;
/** When true, {@link KHRSPIR} is supported. */
public final boolean cl_khr_spir;
/** When true, {@link KHRTerminateContext} is supported. */
public final boolean cl_khr_terminate_context;
/** When true, {@link KHRThrottleHints} is supported. */
public final boolean cl_khr_throttle_hints;
/**
* When true, the nv_compiler_options extension is supported.
*
* This extension allows the programmer to pass options to the PTX assembler allowing greater control over code generation.
*
* -cl-nv-maxrregcount
Passed on to ptxas as --maxrregcount
N is a positive integer.
Specify the maximum number of registers that GPU functions can use.
Until a function-specific limit, a higher value will generally increase
the performance of individual GPU threads that execute this function.
However, because thread registers are allocated from a global register
pool on each GPU, a higher value of this option will also reduce the
maximum thread block size, thereby reducing the amount of thread
parallelism. Hence, a good maxrregcount value is the result of a
trade-off.
If this option is not specified, then no maximum is assumed. Otherwise
the specified value will be rounded to the next multiple of 4 registers
until the GPU specific maximum of 128 registers.
-cl-nv-opt-level
Passed on to ptxas as --opt-level
N is a positive integer, or 0 (no optimization).
Specify optimization level.
Default value: 3.
-cl-nv-verbose
Passed on to ptxas as --verbose
Enable verbose mode.
Output will be reported in the build log (accessible through the
callback parameter to clBuildProgram).
*/
public final boolean cl_nv_compiler_options;
/** When true, {@link NVDeviceAttributeQuery} is supported. */
public final boolean cl_nv_device_attribute_query;
/**
* When true, the nv_pragma_unroll extension is supported.
*
* Overview
*
* This extension extends the OpenCL C language with a hint that allows loops to be unrolled. This pragma must be used for a loop and can be used to
* specify full unrolling or partial unrolling by a certain amount. This is a hint and the compiler may ignore this pragma for any reason.
*
* Goals
*
* The principal goal of the pragma unroll is to improve the performance of loops via unrolling. Typically this enables other optimizations or improves
* instruction level parallelism of a thread.
*
* Details
*
* A user may specify that a loop in the source program be unrolled. This is done via a pragma. The syntax of this pragma is as follows
*
* #pragma unroll [unroll-factor]
*
* The pragma unroll may optionally specify an unroll factor. The pragma must be placed immediately before the loop and only applies to that loop.
*
* If unroll factor is not specified then the compiler will try to do complete or full unrolling of the loop. If a loop unroll factor is specified the
* compiler will perform partial loop unrolling. The loop factor, if specified, must be a compile time non negative integer constant.
*
* A loop unroll factor of 1 means that the compiler should not unroll the loop.
*
* A complete unroll specification has no effect if the trip count of the loop is not compile-time computable.
*/
public final boolean cl_nv_pragma_unroll;
/** When true, {@link QCOMEXTHostPtr} is supported. */
public final boolean cl_qcom_ext_host_ptr;
CLCapabilities(FunctionProvider provider, Set ext) {
this(ext,
provider.getFunctionAddress("clBuildProgram"),
provider.getFunctionAddress("clCloneKernel"),
provider.getFunctionAddress("clCompileProgram"),
provider.getFunctionAddress("clCreateAcceleratorINTEL"),
provider.getFunctionAddress("clCreateBuffer"),
provider.getFunctionAddress("clCreateCommandQueue"),
provider.getFunctionAddress("clCreateCommandQueueWithProperties"),
provider.getFunctionAddress("clCreateCommandQueueWithPropertiesAPPLE"),
provider.getFunctionAddress("clCreateContext"),
provider.getFunctionAddress("clCreateContextFromType"),
provider.getFunctionAddress("clCreateEventFromEGLSyncKHR"),
provider.getFunctionAddress("clCreateEventFromGLsyncKHR"),
provider.getFunctionAddress("clCreateFromEGLImageKHR"),
provider.getFunctionAddress("clCreateFromGLBuffer"),
provider.getFunctionAddress("clCreateFromGLRenderbuffer"),
provider.getFunctionAddress("clCreateFromGLTexture"),
provider.getFunctionAddress("clCreateFromGLTexture2D"),
provider.getFunctionAddress("clCreateFromGLTexture3D"),
provider.getFunctionAddress("clCreateFromVA_APIMediaSurfaceINTEL"),
provider.getFunctionAddress("clCreateImage"),
provider.getFunctionAddress("clCreateImage2D"),
provider.getFunctionAddress("clCreateImage3D"),
provider.getFunctionAddress("clCreateKernel"),
provider.getFunctionAddress("clCreateKernelsInProgram"),
provider.getFunctionAddress("clCreatePipe"),
provider.getFunctionAddress("clCreateProgramWithBinary"),
provider.getFunctionAddress("clCreateProgramWithBuiltInKernels"),
provider.getFunctionAddress("clCreateProgramWithIL"),
provider.getFunctionAddress("clCreateProgramWithSource"),
provider.getFunctionAddress("clCreateSampler"),
provider.getFunctionAddress("clCreateSamplerWithProperties"),
provider.getFunctionAddress("clCreateSubBuffer"),
provider.getFunctionAddress("clCreateSubDevices"),
provider.getFunctionAddress("clCreateSubDevicesEXT"),
provider.getFunctionAddress("clCreateUserEvent"),
provider.getFunctionAddress("clEnqueueAcquireEGLObjectsKHR"),
provider.getFunctionAddress("clEnqueueAcquireGLObjects"),
provider.getFunctionAddress("clEnqueueAcquireVA_APIMediaSurfacesINTEL"),
provider.getFunctionAddress("clEnqueueBarrier"),
provider.getFunctionAddress("clEnqueueBarrierWithWaitList"),
provider.getFunctionAddress("clEnqueueCopyBuffer"),
provider.getFunctionAddress("clEnqueueCopyBufferRect"),
provider.getFunctionAddress("clEnqueueCopyBufferToImage"),
provider.getFunctionAddress("clEnqueueCopyImage"),
provider.getFunctionAddress("clEnqueueCopyImageToBuffer"),
provider.getFunctionAddress("clEnqueueFillBuffer"),
provider.getFunctionAddress("clEnqueueFillImage"),
provider.getFunctionAddress("clEnqueueMakeBuffersResidentAMD"),
provider.getFunctionAddress("clEnqueueMapBuffer"),
provider.getFunctionAddress("clEnqueueMapImage"),
provider.getFunctionAddress("clEnqueueMarker"),
provider.getFunctionAddress("clEnqueueMarkerWithWaitList"),
provider.getFunctionAddress("clEnqueueMigrateMemObjectEXT"),
provider.getFunctionAddress("clEnqueueMigrateMemObjects"),
provider.getFunctionAddress("clEnqueueNDRangeKernel"),
provider.getFunctionAddress("clEnqueueNativeKernel"),
provider.getFunctionAddress("clEnqueueReadBuffer"),
provider.getFunctionAddress("clEnqueueReadBufferRect"),
provider.getFunctionAddress("clEnqueueReadImage"),
provider.getFunctionAddress("clEnqueueReleaseEGLObjectsKHR"),
provider.getFunctionAddress("clEnqueueReleaseGLObjects"),
provider.getFunctionAddress("clEnqueueReleaseVA_APIMediaSurfacesINTEL"),
provider.getFunctionAddress("clEnqueueSVMFree"),
provider.getFunctionAddress("clEnqueueSVMMap"),
provider.getFunctionAddress("clEnqueueSVMMemFill"),
provider.getFunctionAddress("clEnqueueSVMMemcpy"),
provider.getFunctionAddress("clEnqueueSVMMigrateMem"),
provider.getFunctionAddress("clEnqueueSVMUnmap"),
provider.getFunctionAddress("clEnqueueTask"),
provider.getFunctionAddress("clEnqueueUnmapMemObject"),
provider.getFunctionAddress("clEnqueueWaitForEvents"),
provider.getFunctionAddress("clEnqueueWaitSignalAMD"),
provider.getFunctionAddress("clEnqueueWriteBuffer"),
provider.getFunctionAddress("clEnqueueWriteBufferRect"),
provider.getFunctionAddress("clEnqueueWriteImage"),
provider.getFunctionAddress("clEnqueueWriteSignalAMD"),
provider.getFunctionAddress("clFinish"),
provider.getFunctionAddress("clFlush"),
provider.getFunctionAddress("clGetAcceleratorInfoINTEL"),
provider.getFunctionAddress("clGetCommandQueueInfo"),
provider.getFunctionAddress("clGetContextInfo"),
provider.getFunctionAddress("clGetDeviceAndHostTimer"),
provider.getFunctionAddress("clGetDeviceIDs"),
provider.getFunctionAddress("clGetDeviceIDsFromVA_APIMediaAdapterINTEL"),
provider.getFunctionAddress("clGetDeviceImageInfoQCOM"),
provider.getFunctionAddress("clGetDeviceInfo"),
provider.getFunctionAddress("clGetEventInfo"),
provider.getFunctionAddress("clGetEventProfilingInfo"),
provider.getFunctionAddress("clGetExtensionFunctionAddress"),
provider.getFunctionAddress("clGetExtensionFunctionAddressForPlatform"),
provider.getFunctionAddress("clGetGLContextInfoAPPLE"),
provider.getFunctionAddress("clGetGLContextInfoKHR"),
provider.getFunctionAddress("clGetGLObjectInfo"),
provider.getFunctionAddress("clGetGLTextureInfo"),
provider.getFunctionAddress("clGetHostTimer"),
provider.getFunctionAddress("clGetImageInfo"),
provider.getFunctionAddress("clGetKernelArgInfo"),
provider.getFunctionAddress("clGetKernelInfo"),
provider.getFunctionAddress("clGetKernelSubGroupInfo"),
provider.getFunctionAddress("clGetKernelSubGroupInfoKHR"),
provider.getFunctionAddress("clGetKernelWorkGroupInfo"),
provider.getFunctionAddress("clGetMemObjectInfo"),
provider.getFunctionAddress("clGetPipeInfo"),
provider.getFunctionAddress("clGetPlatformIDs"),
provider.getFunctionAddress("clGetPlatformInfo"),
provider.getFunctionAddress("clGetProgramBuildInfo"),
provider.getFunctionAddress("clGetProgramInfo"),
provider.getFunctionAddress("clGetSamplerInfo"),
provider.getFunctionAddress("clGetSupportedImageFormats"),
provider.getFunctionAddress("clLinkProgram"),
provider.getFunctionAddress("clLogMessagesToStderrAPPLE"),
provider.getFunctionAddress("clLogMessagesToStdoutAPPLE"),
provider.getFunctionAddress("clLogMessagesToSystemLogAPPLE"),
provider.getFunctionAddress("clReleaseAcceleratorINTEL"),
provider.getFunctionAddress("clReleaseCommandQueue"),
provider.getFunctionAddress("clReleaseContext"),
provider.getFunctionAddress("clReleaseDevice"),
provider.getFunctionAddress("clReleaseDeviceEXT"),
provider.getFunctionAddress("clReleaseEvent"),
provider.getFunctionAddress("clReleaseKernel"),
provider.getFunctionAddress("clReleaseMemObject"),
provider.getFunctionAddress("clReleaseProgram"),
provider.getFunctionAddress("clReleaseSampler"),
provider.getFunctionAddress("clReportLiveObjectsAltera"),
provider.getFunctionAddress("clRetainAcceleratorINTEL"),
provider.getFunctionAddress("clRetainCommandQueue"),
provider.getFunctionAddress("clRetainContext"),
provider.getFunctionAddress("clRetainDevice"),
provider.getFunctionAddress("clRetainDeviceEXT"),
provider.getFunctionAddress("clRetainEvent"),
provider.getFunctionAddress("clRetainKernel"),
provider.getFunctionAddress("clRetainMemObject"),
provider.getFunctionAddress("clRetainProgram"),
provider.getFunctionAddress("clRetainSampler"),
provider.getFunctionAddress("clSVMAlloc"),
provider.getFunctionAddress("clSVMFree"),
provider.getFunctionAddress("clSetDefaultDeviceCommandQueue"),
provider.getFunctionAddress("clSetEventCallback"),
provider.getFunctionAddress("clSetKernelArg"),
provider.getFunctionAddress("clSetKernelArgSVMPointer"),
provider.getFunctionAddress("clSetKernelExecInfo"),
provider.getFunctionAddress("clSetMemObjectDestructorCallback"),
provider.getFunctionAddress("clSetUserEventStatus"),
provider.getFunctionAddress("clTerminateContextKHR"),
provider.getFunctionAddress("clTrackLiveObjectsAltera"),
provider.getFunctionAddress("clUnloadCompiler"),
provider.getFunctionAddress("clUnloadPlatformCompiler"),
provider.getFunctionAddress("clWaitForEvents")
);
}
CLCapabilities(CLCapabilities caps, Set ext) {
this(ext,
caps.clBuildProgram,
caps.clCloneKernel,
caps.clCompileProgram,
caps.clCreateAcceleratorINTEL,
caps.clCreateBuffer,
caps.clCreateCommandQueue,
caps.clCreateCommandQueueWithProperties,
caps.clCreateCommandQueueWithPropertiesAPPLE,
caps.clCreateContext,
caps.clCreateContextFromType,
caps.clCreateEventFromEGLSyncKHR,
caps.clCreateEventFromGLsyncKHR,
caps.clCreateFromEGLImageKHR,
caps.clCreateFromGLBuffer,
caps.clCreateFromGLRenderbuffer,
caps.clCreateFromGLTexture,
caps.clCreateFromGLTexture2D,
caps.clCreateFromGLTexture3D,
caps.clCreateFromVA_APIMediaSurfaceINTEL,
caps.clCreateImage,
caps.clCreateImage2D,
caps.clCreateImage3D,
caps.clCreateKernel,
caps.clCreateKernelsInProgram,
caps.clCreatePipe,
caps.clCreateProgramWithBinary,
caps.clCreateProgramWithBuiltInKernels,
caps.clCreateProgramWithIL,
caps.clCreateProgramWithSource,
caps.clCreateSampler,
caps.clCreateSamplerWithProperties,
caps.clCreateSubBuffer,
caps.clCreateSubDevices,
caps.clCreateSubDevicesEXT,
caps.clCreateUserEvent,
caps.clEnqueueAcquireEGLObjectsKHR,
caps.clEnqueueAcquireGLObjects,
caps.clEnqueueAcquireVA_APIMediaSurfacesINTEL,
caps.clEnqueueBarrier,
caps.clEnqueueBarrierWithWaitList,
caps.clEnqueueCopyBuffer,
caps.clEnqueueCopyBufferRect,
caps.clEnqueueCopyBufferToImage,
caps.clEnqueueCopyImage,
caps.clEnqueueCopyImageToBuffer,
caps.clEnqueueFillBuffer,
caps.clEnqueueFillImage,
caps.clEnqueueMakeBuffersResidentAMD,
caps.clEnqueueMapBuffer,
caps.clEnqueueMapImage,
caps.clEnqueueMarker,
caps.clEnqueueMarkerWithWaitList,
caps.clEnqueueMigrateMemObjectEXT,
caps.clEnqueueMigrateMemObjects,
caps.clEnqueueNDRangeKernel,
caps.clEnqueueNativeKernel,
caps.clEnqueueReadBuffer,
caps.clEnqueueReadBufferRect,
caps.clEnqueueReadImage,
caps.clEnqueueReleaseEGLObjectsKHR,
caps.clEnqueueReleaseGLObjects,
caps.clEnqueueReleaseVA_APIMediaSurfacesINTEL,
caps.clEnqueueSVMFree,
caps.clEnqueueSVMMap,
caps.clEnqueueSVMMemFill,
caps.clEnqueueSVMMemcpy,
caps.clEnqueueSVMMigrateMem,
caps.clEnqueueSVMUnmap,
caps.clEnqueueTask,
caps.clEnqueueUnmapMemObject,
caps.clEnqueueWaitForEvents,
caps.clEnqueueWaitSignalAMD,
caps.clEnqueueWriteBuffer,
caps.clEnqueueWriteBufferRect,
caps.clEnqueueWriteImage,
caps.clEnqueueWriteSignalAMD,
caps.clFinish,
caps.clFlush,
caps.clGetAcceleratorInfoINTEL,
caps.clGetCommandQueueInfo,
caps.clGetContextInfo,
caps.clGetDeviceAndHostTimer,
caps.clGetDeviceIDs,
caps.clGetDeviceIDsFromVA_APIMediaAdapterINTEL,
caps.clGetDeviceImageInfoQCOM,
caps.clGetDeviceInfo,
caps.clGetEventInfo,
caps.clGetEventProfilingInfo,
caps.clGetExtensionFunctionAddress,
caps.clGetExtensionFunctionAddressForPlatform,
caps.clGetGLContextInfoAPPLE,
caps.clGetGLContextInfoKHR,
caps.clGetGLObjectInfo,
caps.clGetGLTextureInfo,
caps.clGetHostTimer,
caps.clGetImageInfo,
caps.clGetKernelArgInfo,
caps.clGetKernelInfo,
caps.clGetKernelSubGroupInfo,
caps.clGetKernelSubGroupInfoKHR,
caps.clGetKernelWorkGroupInfo,
caps.clGetMemObjectInfo,
caps.clGetPipeInfo,
caps.clGetPlatformIDs,
caps.clGetPlatformInfo,
caps.clGetProgramBuildInfo,
caps.clGetProgramInfo,
caps.clGetSamplerInfo,
caps.clGetSupportedImageFormats,
caps.clLinkProgram,
caps.clLogMessagesToStderrAPPLE,
caps.clLogMessagesToStdoutAPPLE,
caps.clLogMessagesToSystemLogAPPLE,
caps.clReleaseAcceleratorINTEL,
caps.clReleaseCommandQueue,
caps.clReleaseContext,
caps.clReleaseDevice,
caps.clReleaseDeviceEXT,
caps.clReleaseEvent,
caps.clReleaseKernel,
caps.clReleaseMemObject,
caps.clReleaseProgram,
caps.clReleaseSampler,
caps.clReportLiveObjectsAltera,
caps.clRetainAcceleratorINTEL,
caps.clRetainCommandQueue,
caps.clRetainContext,
caps.clRetainDevice,
caps.clRetainDeviceEXT,
caps.clRetainEvent,
caps.clRetainKernel,
caps.clRetainMemObject,
caps.clRetainProgram,
caps.clRetainSampler,
caps.clSVMAlloc,
caps.clSVMFree,
caps.clSetDefaultDeviceCommandQueue,
caps.clSetEventCallback,
caps.clSetKernelArg,
caps.clSetKernelArgSVMPointer,
caps.clSetKernelExecInfo,
caps.clSetMemObjectDestructorCallback,
caps.clSetUserEventStatus,
caps.clTerminateContextKHR,
caps.clTrackLiveObjectsAltera,
caps.clUnloadCompiler,
caps.clUnloadPlatformCompiler,
caps.clWaitForEvents
);
}
private CLCapabilities(Set ext, long... functions) {
clBuildProgram = functions[0];
clCloneKernel = functions[1];
clCompileProgram = functions[2];
clCreateAcceleratorINTEL = functions[3];
clCreateBuffer = functions[4];
clCreateCommandQueue = functions[5];
clCreateCommandQueueWithProperties = functions[6];
clCreateCommandQueueWithPropertiesAPPLE = functions[7];
clCreateContext = functions[8];
clCreateContextFromType = functions[9];
clCreateEventFromEGLSyncKHR = functions[10];
clCreateEventFromGLsyncKHR = functions[11];
clCreateFromEGLImageKHR = functions[12];
clCreateFromGLBuffer = functions[13];
clCreateFromGLRenderbuffer = functions[14];
clCreateFromGLTexture = functions[15];
clCreateFromGLTexture2D = functions[16];
clCreateFromGLTexture3D = functions[17];
clCreateFromVA_APIMediaSurfaceINTEL = functions[18];
clCreateImage = functions[19];
clCreateImage2D = functions[20];
clCreateImage3D = functions[21];
clCreateKernel = functions[22];
clCreateKernelsInProgram = functions[23];
clCreatePipe = functions[24];
clCreateProgramWithBinary = functions[25];
clCreateProgramWithBuiltInKernels = functions[26];
clCreateProgramWithIL = functions[27];
clCreateProgramWithSource = functions[28];
clCreateSampler = functions[29];
clCreateSamplerWithProperties = functions[30];
clCreateSubBuffer = functions[31];
clCreateSubDevices = functions[32];
clCreateSubDevicesEXT = functions[33];
clCreateUserEvent = functions[34];
clEnqueueAcquireEGLObjectsKHR = functions[35];
clEnqueueAcquireGLObjects = functions[36];
clEnqueueAcquireVA_APIMediaSurfacesINTEL = functions[37];
clEnqueueBarrier = functions[38];
clEnqueueBarrierWithWaitList = functions[39];
clEnqueueCopyBuffer = functions[40];
clEnqueueCopyBufferRect = functions[41];
clEnqueueCopyBufferToImage = functions[42];
clEnqueueCopyImage = functions[43];
clEnqueueCopyImageToBuffer = functions[44];
clEnqueueFillBuffer = functions[45];
clEnqueueFillImage = functions[46];
clEnqueueMakeBuffersResidentAMD = functions[47];
clEnqueueMapBuffer = functions[48];
clEnqueueMapImage = functions[49];
clEnqueueMarker = functions[50];
clEnqueueMarkerWithWaitList = functions[51];
clEnqueueMigrateMemObjectEXT = functions[52];
clEnqueueMigrateMemObjects = functions[53];
clEnqueueNDRangeKernel = functions[54];
clEnqueueNativeKernel = functions[55];
clEnqueueReadBuffer = functions[56];
clEnqueueReadBufferRect = functions[57];
clEnqueueReadImage = functions[58];
clEnqueueReleaseEGLObjectsKHR = functions[59];
clEnqueueReleaseGLObjects = functions[60];
clEnqueueReleaseVA_APIMediaSurfacesINTEL = functions[61];
clEnqueueSVMFree = functions[62];
clEnqueueSVMMap = functions[63];
clEnqueueSVMMemFill = functions[64];
clEnqueueSVMMemcpy = functions[65];
clEnqueueSVMMigrateMem = functions[66];
clEnqueueSVMUnmap = functions[67];
clEnqueueTask = functions[68];
clEnqueueUnmapMemObject = functions[69];
clEnqueueWaitForEvents = functions[70];
clEnqueueWaitSignalAMD = functions[71];
clEnqueueWriteBuffer = functions[72];
clEnqueueWriteBufferRect = functions[73];
clEnqueueWriteImage = functions[74];
clEnqueueWriteSignalAMD = functions[75];
clFinish = functions[76];
clFlush = functions[77];
clGetAcceleratorInfoINTEL = functions[78];
clGetCommandQueueInfo = functions[79];
clGetContextInfo = functions[80];
clGetDeviceAndHostTimer = functions[81];
clGetDeviceIDs = functions[82];
clGetDeviceIDsFromVA_APIMediaAdapterINTEL = functions[83];
clGetDeviceImageInfoQCOM = functions[84];
clGetDeviceInfo = functions[85];
clGetEventInfo = functions[86];
clGetEventProfilingInfo = functions[87];
clGetExtensionFunctionAddress = functions[88];
clGetExtensionFunctionAddressForPlatform = functions[89];
clGetGLContextInfoAPPLE = functions[90];
clGetGLContextInfoKHR = functions[91];
clGetGLObjectInfo = functions[92];
clGetGLTextureInfo = functions[93];
clGetHostTimer = functions[94];
clGetImageInfo = functions[95];
clGetKernelArgInfo = functions[96];
clGetKernelInfo = functions[97];
clGetKernelSubGroupInfo = functions[98];
clGetKernelSubGroupInfoKHR = functions[99];
clGetKernelWorkGroupInfo = functions[100];
clGetMemObjectInfo = functions[101];
clGetPipeInfo = functions[102];
clGetPlatformIDs = functions[103];
clGetPlatformInfo = functions[104];
clGetProgramBuildInfo = functions[105];
clGetProgramInfo = functions[106];
clGetSamplerInfo = functions[107];
clGetSupportedImageFormats = functions[108];
clLinkProgram = functions[109];
clLogMessagesToStderrAPPLE = functions[110];
clLogMessagesToStdoutAPPLE = functions[111];
clLogMessagesToSystemLogAPPLE = functions[112];
clReleaseAcceleratorINTEL = functions[113];
clReleaseCommandQueue = functions[114];
clReleaseContext = functions[115];
clReleaseDevice = functions[116];
clReleaseDeviceEXT = functions[117];
clReleaseEvent = functions[118];
clReleaseKernel = functions[119];
clReleaseMemObject = functions[120];
clReleaseProgram = functions[121];
clReleaseSampler = functions[122];
clReportLiveObjectsAltera = functions[123];
clRetainAcceleratorINTEL = functions[124];
clRetainCommandQueue = functions[125];
clRetainContext = functions[126];
clRetainDevice = functions[127];
clRetainDeviceEXT = functions[128];
clRetainEvent = functions[129];
clRetainKernel = functions[130];
clRetainMemObject = functions[131];
clRetainProgram = functions[132];
clRetainSampler = functions[133];
clSVMAlloc = functions[134];
clSVMFree = functions[135];
clSetDefaultDeviceCommandQueue = functions[136];
clSetEventCallback = functions[137];
clSetKernelArg = functions[138];
clSetKernelArgSVMPointer = functions[139];
clSetKernelExecInfo = functions[140];
clSetMemObjectDestructorCallback = functions[141];
clSetUserEventStatus = functions[142];
clTerminateContextKHR = functions[143];
clTrackLiveObjectsAltera = functions[144];
clUnloadCompiler = functions[145];
clUnloadPlatformCompiler = functions[146];
clWaitForEvents = functions[147];
OpenCL10 = ext.contains("OpenCL10") && CL.checkExtension("OpenCL10", CL10.isAvailable(this));
OpenCL10GL = ext.contains("OpenCL10GL") && CL.checkExtension("OpenCL10GL", CL10GL.isAvailable(this));
OpenCL11 = ext.contains("OpenCL11") && CL.checkExtension("OpenCL11", CL11.isAvailable(this));
OpenCL12 = ext.contains("OpenCL12") && CL.checkExtension("OpenCL12", CL12.isAvailable(this));
OpenCL12GL = ext.contains("OpenCL12GL") && CL.checkExtension("OpenCL12GL", CL12GL.isAvailable(this));
OpenCL20 = ext.contains("OpenCL20") && CL.checkExtension("OpenCL20", CL20.isAvailable(this));
OpenCL21 = ext.contains("OpenCL21") && CL.checkExtension("OpenCL21", CL21.isAvailable(this));
cl_altera_compiler_mode = ext.contains("cl_altera_compiler_mode");
cl_altera_device_temperature = ext.contains("cl_altera_device_temperature");
cl_altera_live_object_tracking = ext.contains("cl_altera_live_object_tracking") && CL.checkExtension("cl_altera_live_object_tracking", ALTERALiveObjectTracking.isAvailable(this));
cl_amd_bus_addressable_memory = ext.contains("cl_amd_bus_addressable_memory") && CL.checkExtension("cl_amd_bus_addressable_memory", AMDBusAddressableMemory.isAvailable(this));
cl_amd_compile_options = ext.contains("cl_amd_compile_options");
cl_amd_device_attribute_query = ext.contains("cl_amd_device_attribute_query");
cl_amd_device_board_name = ext.contains("cl_amd_device_board_name");
cl_amd_device_persistent_memory = ext.contains("cl_amd_device_persistent_memory");
cl_amd_device_profiling_timer_offset = ext.contains("cl_amd_device_profiling_timer_offset");
cl_amd_device_topology = ext.contains("cl_amd_device_topology");
cl_amd_event_callback = ext.contains("cl_amd_event_callback");
cl_amd_fp64 = ext.contains("cl_amd_fp64");
cl_amd_media_ops = ext.contains("cl_amd_media_ops");
cl_amd_media_ops2 = ext.contains("cl_amd_media_ops2");
cl_amd_offline_devices = ext.contains("cl_amd_offline_devices");
cl_amd_popcnt = ext.contains("cl_amd_popcnt");
cl_amd_predefined_macros = ext.contains("cl_amd_predefined_macros");
cl_amd_printf = ext.contains("cl_amd_printf");
cl_amd_vec3 = ext.contains("cl_amd_vec3");
cl_APPLE_biased_fixed_point_image_formats = ext.contains("cl_APPLE_biased_fixed_point_image_formats");
cl_APPLE_command_queue_priority = ext.contains("cl_APPLE_command_queue_priority") && CL.checkExtension("cl_APPLE_command_queue_priority", APPLECommandQueuePriority.isAvailable(this));
cl_APPLE_command_queue_select_compute_units = ext.contains("cl_APPLE_command_queue_select_compute_units") && CL.checkExtension("cl_APPLE_command_queue_select_compute_units", APPLECommandQueueSelectComputeUnits.isAvailable(this));
cl_APPLE_ContextLoggingFunctions = ext.contains("cl_APPLE_ContextLoggingFunctions") && CL.checkExtension("cl_APPLE_ContextLoggingFunctions", APPLEContextLoggingFunctions.isAvailable(this));
cl_APPLE_fixed_alpha_channel_orders = ext.contains("cl_APPLE_fixed_alpha_channel_orders");
cl_APPLE_fp64_basic_ops = ext.contains("cl_APPLE_fp64_basic_ops");
cl_APPLE_gl_sharing = ext.contains("cl_APPLE_gl_sharing") && CL.checkExtension("cl_APPLE_gl_sharing", APPLEGLSharing.isAvailable(this));
cl_APPLE_query_kernel_names = ext.contains("cl_APPLE_query_kernel_names");
cl_arm_core_id = ext.contains("cl_arm_core_id");
cl_arm_printf = ext.contains("cl_arm_printf");
cl_ext_atomic_counters_32 = ext.contains("cl_ext_atomic_counters_32");
cl_ext_atomic_counters_64 = ext.contains("cl_ext_atomic_counters_64");
cl_ext_device_fission = ext.contains("cl_ext_device_fission") && CL.checkExtension("cl_ext_device_fission", EXTDeviceFission.isAvailable(this));
cl_ext_migrate_memobject = ext.contains("cl_ext_migrate_memobject") && CL.checkExtension("cl_ext_migrate_memobject", EXTMigrateMemobject.isAvailable(this));
cl_intel_accelerator = ext.contains("cl_intel_accelerator") && CL.checkExtension("cl_intel_accelerator", INTELAccelerator.isAvailable(this));
cl_intel_advanced_motion_estimation = ext.contains("cl_intel_advanced_motion_estimation");
cl_intel_device_partition_by_names = ext.contains("cl_intel_device_partition_by_names");
cl_intel_driver_diagnostics = ext.contains("cl_intel_driver_diagnostics");
cl_intel_egl_image_yuv = ext.contains("cl_intel_egl_image_yuv");
cl_intel_motion_estimation = ext.contains("cl_intel_motion_estimation");
cl_intel_packed_yuv = ext.contains("cl_intel_packed_yuv");
cl_intel_printf = ext.contains("cl_intel_printf");
cl_intel_required_subgroup_size = ext.contains("cl_intel_required_subgroup_size");
cl_intel_simultaneous_sharing = ext.contains("cl_intel_simultaneous_sharing");
cl_intel_subgroups = ext.contains("cl_intel_subgroups") && CL.checkExtension("cl_intel_subgroups", INTELSubgroups.isAvailable(this));
cl_intel_thread_local_exec = ext.contains("cl_intel_thread_local_exec");
cl_intel_va_api_media_sharing = ext.contains("cl_intel_va_api_media_sharing") && CL.checkExtension("cl_intel_va_api_media_sharing", INTELVAAPIMediaSharing.isAvailable(this));
cl_khr_3d_image_writes = ext.contains("cl_khr_3d_image_writes");
cl_khr_byte_addressable_store = ext.contains("cl_khr_byte_addressable_store");
cl_khr_depth_images = ext.contains("cl_khr_depth_images");
cl_khr_device_enqueue_local_arg_types = ext.contains("cl_khr_device_enqueue_local_arg_types");
cl_khr_egl_event = ext.contains("cl_khr_egl_event") && CL.checkExtension("cl_khr_egl_event", KHREGLEvent.isAvailable(this));
cl_khr_egl_image = ext.contains("cl_khr_egl_image") && CL.checkExtension("cl_khr_egl_image", KHREGLImage.isAvailable(this));
cl_khr_fp16 = ext.contains("cl_khr_fp16");
cl_khr_fp64 = ext.contains("cl_khr_fp64");
cl_khr_gl_depth_images = ext.contains("cl_khr_gl_depth_images");
cl_khr_gl_event = ext.contains("cl_khr_gl_event") && CL.checkExtension("cl_khr_gl_event", KHRGLEvent.isAvailable(this));
cl_khr_gl_msaa_sharing = ext.contains("cl_khr_gl_msaa_sharing");
cl_khr_gl_sharing = ext.contains("cl_khr_gl_sharing") && CL.checkExtension("cl_khr_gl_sharing", KHRGLSharing.isAvailable(this));
cl_khr_global_int32_base_atomics = ext.contains("cl_khr_global_int32_base_atomics");
cl_khr_global_int32_extended_atomics = ext.contains("cl_khr_global_int32_extended_atomics");
cl_khr_icd = ext.contains("cl_khr_icd");
cl_khr_image2d_from_buffer = ext.contains("cl_khr_image2d_from_buffer");
cl_khr_initialize_memory = ext.contains("cl_khr_initialize_memory");
cl_khr_int64_base_atomics = ext.contains("cl_khr_int64_base_atomics");
cl_khr_int64_extended_atomics = ext.contains("cl_khr_int64_extended_atomics");
cl_khr_local_int32_base_atomics = ext.contains("cl_khr_local_int32_base_atomics");
cl_khr_local_int32_extended_atomics = ext.contains("cl_khr_local_int32_extended_atomics");
cl_khr_mipmap_image = ext.contains("cl_khr_mipmap_image");
cl_khr_mipmap_image_writes = ext.contains("cl_khr_mipmap_image_writes");
cl_khr_priority_hints = ext.contains("cl_khr_priority_hints");
cl_khr_select_fprounding_mode = ext.contains("cl_khr_select_fprounding_mode");
cl_khr_spir = ext.contains("cl_khr_spir");
cl_khr_terminate_context = ext.contains("cl_khr_terminate_context") && CL.checkExtension("cl_khr_terminate_context", KHRTerminateContext.isAvailable(this));
cl_khr_throttle_hints = ext.contains("cl_khr_throttle_hints");
cl_nv_compiler_options = ext.contains("cl_nv_compiler_options");
cl_nv_device_attribute_query = ext.contains("cl_nv_device_attribute_query");
cl_nv_pragma_unroll = ext.contains("cl_nv_pragma_unroll");
cl_qcom_ext_host_ptr = ext.contains("cl_qcom_ext_host_ptr") && CL.checkExtension("cl_qcom_ext_host_ptr", QCOMEXTHostPtr.isAvailable(this));
}
}