[Mesa-dev] [PATCH v3 01/21] include/CL: Update to the latest OpenCL 2.2 headers
Karol Herbst
kherbst at redhat.com
Thu Feb 22 10:13:18 UTC 2018
Acked-by: Karol Herbst <kherbst at redhat.com>
On Wed, Feb 21, 2018 at 11:50 PM, Pierre Moreau <pierre.morrow at free.fr> wrote:
> Signed-off-by: Pierre Moreau <pierre.morrow at free.fr>
> ---
> include/CL/cl.h | 472 ++++++++++++++++++++++-------
> include/CL/cl_d3d10.h | 7 +-
> include/CL/cl_d3d11.h | 7 +-
> include/CL/cl_dx9_media_sharing.h | 9 +-
> include/CL/cl_dx9_media_sharing_intel.h | 182 +++++++++++
> include/CL/cl_egl.h | 9 +-
> include/CL/cl_ext.h | 301 +++++++++++++++++-
> include/CL/cl_ext_intel.h | 429 ++++++++++++++++++++++++++
> include/CL/cl_gl.h | 7 +-
> include/CL/cl_gl_ext.h | 7 +-
> include/CL/cl_platform.h | 328 +++++++++++++++-----
> include/CL/cl_va_api_media_sharing_intel.h | 172 +++++++++++
> include/CL/opencl.h | 7 +-
> 13 files changed, 1739 insertions(+), 198 deletions(-)
> create mode 100644 include/CL/cl_dx9_media_sharing_intel.h
> create mode 100644 include/CL/cl_ext_intel.h
> create mode 100644 include/CL/cl_va_api_media_sharing_intel.h
>
> diff --git a/include/CL/cl.h b/include/CL/cl.h
> index 316565d6e4..1e164eb839 100644
> --- a/include/CL/cl.h
> +++ b/include/CL/cl.h
> @@ -1,5 +1,5 @@
> /*******************************************************************************
> - * Copyright (c) 2008 - 2012 The Khronos Group Inc.
> + * Copyright (c) 2008-2015 The Khronos Group Inc.
> *
> * Permission is hereby granted, free of charge, to any person obtaining a
> * copy of this software and/or associated documentation files (the
> @@ -12,6 +12,11 @@
> * The above copyright notice and this permission notice shall be included
> * in all copies or substantial portions of the Materials.
> *
> + * MODIFICATIONS TO THIS FILE MAY MEAN IT NO LONGER ACCURATELY REFLECTS
> + * KHRONOS STANDARDS. THE UNMODIFIED, NORMATIVE VERSIONS OF KHRONOS
> + * SPECIFICATIONS AND HEADER INFORMATION ARE LOCATED AT
> + * https://www.khronos.org/registry/
> + *
> * THE MATERIALS ARE PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND,
> * EXPRESS OR IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF
> * MERCHANTABILITY, FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT.
> @@ -55,16 +60,19 @@ typedef cl_bitfield cl_device_fp_config;
> typedef cl_uint cl_device_mem_cache_type;
> typedef cl_uint cl_device_local_mem_type;
> typedef cl_bitfield cl_device_exec_capabilities;
> +typedef cl_bitfield cl_device_svm_capabilities;
> typedef cl_bitfield cl_command_queue_properties;
> typedef intptr_t cl_device_partition_property;
> typedef cl_bitfield cl_device_affinity_domain;
>
> typedef intptr_t cl_context_properties;
> typedef cl_uint cl_context_info;
> +typedef cl_bitfield cl_queue_properties;
> typedef cl_uint cl_command_queue_info;
> typedef cl_uint cl_channel_order;
> typedef cl_uint cl_channel_type;
> typedef cl_bitfield cl_mem_flags;
> +typedef cl_bitfield cl_svm_mem_flags;
> typedef cl_uint cl_mem_object_type;
> typedef cl_uint cl_mem_info;
> typedef cl_bitfield cl_mem_migration_flags;
> @@ -74,6 +82,8 @@ typedef cl_uint cl_addressing_mode;
> typedef cl_uint cl_filter_mode;
> typedef cl_uint cl_sampler_info;
> typedef cl_bitfield cl_map_flags;
> +typedef intptr_t cl_pipe_properties;
> +typedef cl_uint cl_pipe_info;
> typedef cl_uint cl_program_info;
> typedef cl_uint cl_program_build_info;
> typedef cl_uint cl_program_binary_type;
> @@ -84,10 +94,12 @@ typedef cl_uint cl_kernel_arg_address_qualifier;
> typedef cl_uint cl_kernel_arg_access_qualifier;
> typedef cl_bitfield cl_kernel_arg_type_qualifier;
> typedef cl_uint cl_kernel_work_group_info;
> +typedef cl_uint cl_kernel_sub_group_info;
> typedef cl_uint cl_event_info;
> typedef cl_uint cl_command_type;
> typedef cl_uint cl_profiling_info;
> -
> +typedef cl_bitfield cl_sampler_properties;
> +typedef cl_uint cl_kernel_exec_info;
>
> typedef struct _cl_image_format {
> cl_channel_order image_channel_order;
> @@ -104,7 +116,13 @@ typedef struct _cl_image_desc {
> size_t image_slice_pitch;
> cl_uint num_mip_levels;
> cl_uint num_samples;
> - cl_mem buffer;
> +#ifdef __GNUC__
> + __extension__ /* Prevents warnings about anonymous union in -pedantic builds */
> +#endif
> + union {
> + cl_mem buffer;
> + cl_mem mem_object;
> + };
> } cl_image_desc;
>
> typedef struct _cl_buffer_region {
> @@ -176,11 +194,18 @@ typedef struct _cl_buffer_region {
> #define CL_INVALID_COMPILER_OPTIONS -66
> #define CL_INVALID_LINKER_OPTIONS -67
> #define CL_INVALID_DEVICE_PARTITION_COUNT -68
> +#define CL_INVALID_PIPE_SIZE -69
> +#define CL_INVALID_DEVICE_QUEUE -70
> +#define CL_INVALID_SPEC_ID -71
> +#define CL_MAX_SIZE_RESTRICTION_EXCEEDED -72
>
> /* OpenCL Version */
> #define CL_VERSION_1_0 1
> #define CL_VERSION_1_1 1
> #define CL_VERSION_1_2 1
> +#define CL_VERSION_2_0 1
> +#define CL_VERSION_2_1 1
> +#define CL_VERSION_2_2 1
>
> /* cl_bool */
> #define CL_FALSE 0
> @@ -194,6 +219,7 @@ typedef struct _cl_buffer_region {
> #define CL_PLATFORM_NAME 0x0902
> #define CL_PLATFORM_VENDOR 0x0903
> #define CL_PLATFORM_EXTENSIONS 0x0904
> +#define CL_PLATFORM_HOST_TIMER_RESOLUTION 0x0905
>
> /* cl_device_type - bitfield */
> #define CL_DEVICE_TYPE_DEFAULT (1 << 0)
> @@ -204,82 +230,101 @@ typedef struct _cl_buffer_region {
> #define CL_DEVICE_TYPE_ALL 0xFFFFFFFF
>
> /* cl_device_info */
> -#define CL_DEVICE_TYPE 0x1000
> -#define CL_DEVICE_VENDOR_ID 0x1001
> -#define CL_DEVICE_MAX_COMPUTE_UNITS 0x1002
> -#define CL_DEVICE_MAX_WORK_ITEM_DIMENSIONS 0x1003
> -#define CL_DEVICE_MAX_WORK_GROUP_SIZE 0x1004
> -#define CL_DEVICE_MAX_WORK_ITEM_SIZES 0x1005
> -#define CL_DEVICE_PREFERRED_VECTOR_WIDTH_CHAR 0x1006
> -#define CL_DEVICE_PREFERRED_VECTOR_WIDTH_SHORT 0x1007
> -#define CL_DEVICE_PREFERRED_VECTOR_WIDTH_INT 0x1008
> -#define CL_DEVICE_PREFERRED_VECTOR_WIDTH_LONG 0x1009
> -#define CL_DEVICE_PREFERRED_VECTOR_WIDTH_FLOAT 0x100A
> -#define CL_DEVICE_PREFERRED_VECTOR_WIDTH_DOUBLE 0x100B
> -#define CL_DEVICE_MAX_CLOCK_FREQUENCY 0x100C
> -#define CL_DEVICE_ADDRESS_BITS 0x100D
> -#define CL_DEVICE_MAX_READ_IMAGE_ARGS 0x100E
> -#define CL_DEVICE_MAX_WRITE_IMAGE_ARGS 0x100F
> -#define CL_DEVICE_MAX_MEM_ALLOC_SIZE 0x1010
> -#define CL_DEVICE_IMAGE2D_MAX_WIDTH 0x1011
> -#define CL_DEVICE_IMAGE2D_MAX_HEIGHT 0x1012
> -#define CL_DEVICE_IMAGE3D_MAX_WIDTH 0x1013
> -#define CL_DEVICE_IMAGE3D_MAX_HEIGHT 0x1014
> -#define CL_DEVICE_IMAGE3D_MAX_DEPTH 0x1015
> -#define CL_DEVICE_IMAGE_SUPPORT 0x1016
> -#define CL_DEVICE_MAX_PARAMETER_SIZE 0x1017
> -#define CL_DEVICE_MAX_SAMPLERS 0x1018
> -#define CL_DEVICE_MEM_BASE_ADDR_ALIGN 0x1019
> -#define CL_DEVICE_MIN_DATA_TYPE_ALIGN_SIZE 0x101A
> -#define CL_DEVICE_SINGLE_FP_CONFIG 0x101B
> -#define CL_DEVICE_GLOBAL_MEM_CACHE_TYPE 0x101C
> -#define CL_DEVICE_GLOBAL_MEM_CACHELINE_SIZE 0x101D
> -#define CL_DEVICE_GLOBAL_MEM_CACHE_SIZE 0x101E
> -#define CL_DEVICE_GLOBAL_MEM_SIZE 0x101F
> -#define CL_DEVICE_MAX_CONSTANT_BUFFER_SIZE 0x1020
> -#define CL_DEVICE_MAX_CONSTANT_ARGS 0x1021
> -#define CL_DEVICE_LOCAL_MEM_TYPE 0x1022
> -#define CL_DEVICE_LOCAL_MEM_SIZE 0x1023
> -#define CL_DEVICE_ERROR_CORRECTION_SUPPORT 0x1024
> -#define CL_DEVICE_PROFILING_TIMER_RESOLUTION 0x1025
> -#define CL_DEVICE_ENDIAN_LITTLE 0x1026
> -#define CL_DEVICE_AVAILABLE 0x1027
> -#define CL_DEVICE_COMPILER_AVAILABLE 0x1028
> -#define CL_DEVICE_EXECUTION_CAPABILITIES 0x1029
> -#define CL_DEVICE_QUEUE_PROPERTIES 0x102A
> -#define CL_DEVICE_NAME 0x102B
> -#define CL_DEVICE_VENDOR 0x102C
> -#define CL_DRIVER_VERSION 0x102D
> -#define CL_DEVICE_PROFILE 0x102E
> -#define CL_DEVICE_VERSION 0x102F
> -#define CL_DEVICE_EXTENSIONS 0x1030
> -#define CL_DEVICE_PLATFORM 0x1031
> -#define CL_DEVICE_DOUBLE_FP_CONFIG 0x1032
> -/* 0x1033 reserved for CL_DEVICE_HALF_FP_CONFIG */
> -#define CL_DEVICE_PREFERRED_VECTOR_WIDTH_HALF 0x1034
> -#define CL_DEVICE_HOST_UNIFIED_MEMORY 0x1035
> -#define CL_DEVICE_NATIVE_VECTOR_WIDTH_CHAR 0x1036
> -#define CL_DEVICE_NATIVE_VECTOR_WIDTH_SHORT 0x1037
> -#define CL_DEVICE_NATIVE_VECTOR_WIDTH_INT 0x1038
> -#define CL_DEVICE_NATIVE_VECTOR_WIDTH_LONG 0x1039
> -#define CL_DEVICE_NATIVE_VECTOR_WIDTH_FLOAT 0x103A
> -#define CL_DEVICE_NATIVE_VECTOR_WIDTH_DOUBLE 0x103B
> -#define CL_DEVICE_NATIVE_VECTOR_WIDTH_HALF 0x103C
> -#define CL_DEVICE_OPENCL_C_VERSION 0x103D
> -#define CL_DEVICE_LINKER_AVAILABLE 0x103E
> -#define CL_DEVICE_BUILT_IN_KERNELS 0x103F
> -#define CL_DEVICE_IMAGE_MAX_BUFFER_SIZE 0x1040
> -#define CL_DEVICE_IMAGE_MAX_ARRAY_SIZE 0x1041
> -#define CL_DEVICE_PARENT_DEVICE 0x1042
> -#define CL_DEVICE_PARTITION_MAX_SUB_DEVICES 0x1043
> -#define CL_DEVICE_PARTITION_PROPERTIES 0x1044
> -#define CL_DEVICE_PARTITION_AFFINITY_DOMAIN 0x1045
> -#define CL_DEVICE_PARTITION_TYPE 0x1046
> -#define CL_DEVICE_REFERENCE_COUNT 0x1047
> -#define CL_DEVICE_PREFERRED_INTEROP_USER_SYNC 0x1048
> -#define CL_DEVICE_PRINTF_BUFFER_SIZE 0x1049
> -#define CL_DEVICE_IMAGE_PITCH_ALIGNMENT 0x104A
> -#define CL_DEVICE_IMAGE_BASE_ADDRESS_ALIGNMENT 0x104B
> +#define CL_DEVICE_TYPE 0x1000
> +#define CL_DEVICE_VENDOR_ID 0x1001
> +#define CL_DEVICE_MAX_COMPUTE_UNITS 0x1002
> +#define CL_DEVICE_MAX_WORK_ITEM_DIMENSIONS 0x1003
> +#define CL_DEVICE_MAX_WORK_GROUP_SIZE 0x1004
> +#define CL_DEVICE_MAX_WORK_ITEM_SIZES 0x1005
> +#define CL_DEVICE_PREFERRED_VECTOR_WIDTH_CHAR 0x1006
> +#define CL_DEVICE_PREFERRED_VECTOR_WIDTH_SHORT 0x1007
> +#define CL_DEVICE_PREFERRED_VECTOR_WIDTH_INT 0x1008
> +#define CL_DEVICE_PREFERRED_VECTOR_WIDTH_LONG 0x1009
> +#define CL_DEVICE_PREFERRED_VECTOR_WIDTH_FLOAT 0x100A
> +#define CL_DEVICE_PREFERRED_VECTOR_WIDTH_DOUBLE 0x100B
> +#define CL_DEVICE_MAX_CLOCK_FREQUENCY 0x100C
> +#define CL_DEVICE_ADDRESS_BITS 0x100D
> +#define CL_DEVICE_MAX_READ_IMAGE_ARGS 0x100E
> +#define CL_DEVICE_MAX_WRITE_IMAGE_ARGS 0x100F
> +#define CL_DEVICE_MAX_MEM_ALLOC_SIZE 0x1010
> +#define CL_DEVICE_IMAGE2D_MAX_WIDTH 0x1011
> +#define CL_DEVICE_IMAGE2D_MAX_HEIGHT 0x1012
> +#define CL_DEVICE_IMAGE3D_MAX_WIDTH 0x1013
> +#define CL_DEVICE_IMAGE3D_MAX_HEIGHT 0x1014
> +#define CL_DEVICE_IMAGE3D_MAX_DEPTH 0x1015
> +#define CL_DEVICE_IMAGE_SUPPORT 0x1016
> +#define CL_DEVICE_MAX_PARAMETER_SIZE 0x1017
> +#define CL_DEVICE_MAX_SAMPLERS 0x1018
> +#define CL_DEVICE_MEM_BASE_ADDR_ALIGN 0x1019
> +#define CL_DEVICE_MIN_DATA_TYPE_ALIGN_SIZE 0x101A
> +#define CL_DEVICE_SINGLE_FP_CONFIG 0x101B
> +#define CL_DEVICE_GLOBAL_MEM_CACHE_TYPE 0x101C
> +#define CL_DEVICE_GLOBAL_MEM_CACHELINE_SIZE 0x101D
> +#define CL_DEVICE_GLOBAL_MEM_CACHE_SIZE 0x101E
> +#define CL_DEVICE_GLOBAL_MEM_SIZE 0x101F
> +#define CL_DEVICE_MAX_CONSTANT_BUFFER_SIZE 0x1020
> +#define CL_DEVICE_MAX_CONSTANT_ARGS 0x1021
> +#define CL_DEVICE_LOCAL_MEM_TYPE 0x1022
> +#define CL_DEVICE_LOCAL_MEM_SIZE 0x1023
> +#define CL_DEVICE_ERROR_CORRECTION_SUPPORT 0x1024
> +#define CL_DEVICE_PROFILING_TIMER_RESOLUTION 0x1025
> +#define CL_DEVICE_ENDIAN_LITTLE 0x1026
> +#define CL_DEVICE_AVAILABLE 0x1027
> +#define CL_DEVICE_COMPILER_AVAILABLE 0x1028
> +#define CL_DEVICE_EXECUTION_CAPABILITIES 0x1029
> +#define CL_DEVICE_QUEUE_PROPERTIES 0x102A /* deprecated */
> +#define CL_DEVICE_QUEUE_ON_HOST_PROPERTIES 0x102A
> +#define CL_DEVICE_NAME 0x102B
> +#define CL_DEVICE_VENDOR 0x102C
> +#define CL_DRIVER_VERSION 0x102D
> +#define CL_DEVICE_PROFILE 0x102E
> +#define CL_DEVICE_VERSION 0x102F
> +#define CL_DEVICE_EXTENSIONS 0x1030
> +#define CL_DEVICE_PLATFORM 0x1031
> +#define CL_DEVICE_DOUBLE_FP_CONFIG 0x1032
> +#define CL_DEVICE_HALF_FP_CONFIG 0x1033
> +#define CL_DEVICE_PREFERRED_VECTOR_WIDTH_HALF 0x1034
> +#define CL_DEVICE_HOST_UNIFIED_MEMORY 0x1035 /* deprecated */
> +#define CL_DEVICE_NATIVE_VECTOR_WIDTH_CHAR 0x1036
> +#define CL_DEVICE_NATIVE_VECTOR_WIDTH_SHORT 0x1037
> +#define CL_DEVICE_NATIVE_VECTOR_WIDTH_INT 0x1038
> +#define CL_DEVICE_NATIVE_VECTOR_WIDTH_LONG 0x1039
> +#define CL_DEVICE_NATIVE_VECTOR_WIDTH_FLOAT 0x103A
> +#define CL_DEVICE_NATIVE_VECTOR_WIDTH_DOUBLE 0x103B
> +#define CL_DEVICE_NATIVE_VECTOR_WIDTH_HALF 0x103C
> +#define CL_DEVICE_OPENCL_C_VERSION 0x103D
> +#define CL_DEVICE_LINKER_AVAILABLE 0x103E
> +#define CL_DEVICE_BUILT_IN_KERNELS 0x103F
> +#define CL_DEVICE_IMAGE_MAX_BUFFER_SIZE 0x1040
> +#define CL_DEVICE_IMAGE_MAX_ARRAY_SIZE 0x1041
> +#define CL_DEVICE_PARENT_DEVICE 0x1042
> +#define CL_DEVICE_PARTITION_MAX_SUB_DEVICES 0x1043
> +#define CL_DEVICE_PARTITION_PROPERTIES 0x1044
> +#define CL_DEVICE_PARTITION_AFFINITY_DOMAIN 0x1045
> +#define CL_DEVICE_PARTITION_TYPE 0x1046
> +#define CL_DEVICE_REFERENCE_COUNT 0x1047
> +#define CL_DEVICE_PREFERRED_INTEROP_USER_SYNC 0x1048
> +#define CL_DEVICE_PRINTF_BUFFER_SIZE 0x1049
> +#define CL_DEVICE_IMAGE_PITCH_ALIGNMENT 0x104A
> +#define CL_DEVICE_IMAGE_BASE_ADDRESS_ALIGNMENT 0x104B
> +#define CL_DEVICE_MAX_READ_WRITE_IMAGE_ARGS 0x104C
> +#define CL_DEVICE_MAX_GLOBAL_VARIABLE_SIZE 0x104D
> +#define CL_DEVICE_QUEUE_ON_DEVICE_PROPERTIES 0x104E
> +#define CL_DEVICE_QUEUE_ON_DEVICE_PREFERRED_SIZE 0x104F
> +#define CL_DEVICE_QUEUE_ON_DEVICE_MAX_SIZE 0x1050
> +#define CL_DEVICE_MAX_ON_DEVICE_QUEUES 0x1051
> +#define CL_DEVICE_MAX_ON_DEVICE_EVENTS 0x1052
> +#define CL_DEVICE_SVM_CAPABILITIES 0x1053
> +#define CL_DEVICE_GLOBAL_VARIABLE_PREFERRED_TOTAL_SIZE 0x1054
> +#define CL_DEVICE_MAX_PIPE_ARGS 0x1055
> +#define CL_DEVICE_PIPE_MAX_ACTIVE_RESERVATIONS 0x1056
> +#define CL_DEVICE_PIPE_MAX_PACKET_SIZE 0x1057
> +#define CL_DEVICE_PREFERRED_PLATFORM_ATOMIC_ALIGNMENT 0x1058
> +#define CL_DEVICE_PREFERRED_GLOBAL_ATOMIC_ALIGNMENT 0x1059
> +#define CL_DEVICE_PREFERRED_LOCAL_ATOMIC_ALIGNMENT 0x105A
> +#define CL_DEVICE_IL_VERSION 0x105B
> +#define CL_DEVICE_MAX_NUM_SUB_GROUPS 0x105C
> +#define CL_DEVICE_SUB_GROUP_INDEPENDENT_FORWARD_PROGRESS 0x105D
>
> /* cl_device_fp_config - bitfield */
> #define CL_FP_DENORM (1 << 0)
> @@ -307,6 +352,8 @@ typedef struct _cl_buffer_region {
> /* cl_command_queue_properties - bitfield */
> #define CL_QUEUE_OUT_OF_ORDER_EXEC_MODE_ENABLE (1 << 0)
> #define CL_QUEUE_PROFILING_ENABLE (1 << 1)
> +#define CL_QUEUE_ON_DEVICE (1 << 2)
> +#define CL_QUEUE_ON_DEVICE_DEFAULT (1 << 3)
>
> /* cl_context_info */
> #define CL_CONTEXT_REFERENCE_COUNT 0x1080
> @@ -325,20 +372,28 @@ typedef struct _cl_buffer_region {
> #define CL_DEVICE_PARTITION_BY_AFFINITY_DOMAIN 0x1088
>
> /* cl_device_affinity_domain */
> -#define CL_DEVICE_AFFINITY_DOMAIN_NUMA (1 << 0)
> -#define CL_DEVICE_AFFINITY_DOMAIN_L4_CACHE (1 << 1)
> -#define CL_DEVICE_AFFINITY_DOMAIN_L3_CACHE (1 << 2)
> -#define CL_DEVICE_AFFINITY_DOMAIN_L2_CACHE (1 << 3)
> -#define CL_DEVICE_AFFINITY_DOMAIN_L1_CACHE (1 << 4)
> -#define CL_DEVICE_AFFINITY_DOMAIN_NEXT_PARTITIONABLE (1 << 5)
> +#define CL_DEVICE_AFFINITY_DOMAIN_NUMA (1 << 0)
> +#define CL_DEVICE_AFFINITY_DOMAIN_L4_CACHE (1 << 1)
> +#define CL_DEVICE_AFFINITY_DOMAIN_L3_CACHE (1 << 2)
> +#define CL_DEVICE_AFFINITY_DOMAIN_L2_CACHE (1 << 3)
> +#define CL_DEVICE_AFFINITY_DOMAIN_L1_CACHE (1 << 4)
> +#define CL_DEVICE_AFFINITY_DOMAIN_NEXT_PARTITIONABLE (1 << 5)
> +
> +/* cl_device_svm_capabilities */
> +#define CL_DEVICE_SVM_COARSE_GRAIN_BUFFER (1 << 0)
> +#define CL_DEVICE_SVM_FINE_GRAIN_BUFFER (1 << 1)
> +#define CL_DEVICE_SVM_FINE_GRAIN_SYSTEM (1 << 2)
> +#define CL_DEVICE_SVM_ATOMICS (1 << 3)
>
> /* cl_command_queue_info */
> #define CL_QUEUE_CONTEXT 0x1090
> #define CL_QUEUE_DEVICE 0x1091
> #define CL_QUEUE_REFERENCE_COUNT 0x1092
> #define CL_QUEUE_PROPERTIES 0x1093
> +#define CL_QUEUE_SIZE 0x1094
> +#define CL_QUEUE_DEVICE_DEFAULT 0x1095
>
> -/* cl_mem_flags - bitfield */
> +/* cl_mem_flags and cl_svm_mem_flags - bitfield */
> #define CL_MEM_READ_WRITE (1 << 0)
> #define CL_MEM_WRITE_ONLY (1 << 1)
> #define CL_MEM_READ_ONLY (1 << 2)
> @@ -349,6 +404,9 @@ typedef struct _cl_buffer_region {
> #define CL_MEM_HOST_WRITE_ONLY (1 << 7)
> #define CL_MEM_HOST_READ_ONLY (1 << 8)
> #define CL_MEM_HOST_NO_ACCESS (1 << 9)
> +#define CL_MEM_SVM_FINE_GRAIN_BUFFER (1 << 10) /* used by cl_svm_mem_flags only */
> +#define CL_MEM_SVM_ATOMICS (1 << 11) /* used by cl_svm_mem_flags only */
> +#define CL_MEM_KERNEL_READ_AND_WRITE (1 << 12)
>
> /* cl_mem_migration_flags - bitfield */
> #define CL_MIGRATE_MEM_OBJECT_HOST (1 << 0)
> @@ -370,6 +428,11 @@ typedef struct _cl_buffer_region {
> #define CL_RGBx 0x10BC
> #define CL_DEPTH 0x10BD
> #define CL_DEPTH_STENCIL 0x10BE
> +#define CL_sRGB 0x10BF
> +#define CL_sRGBx 0x10C0
> +#define CL_sRGBA 0x10C1
> +#define CL_sBGRA 0x10C2
> +#define CL_ABGR 0x10C3
>
> /* cl_channel_type */
> #define CL_SNORM_INT8 0x10D0
> @@ -388,6 +451,7 @@ typedef struct _cl_buffer_region {
> #define CL_HALF_FLOAT 0x10DD
> #define CL_FLOAT 0x10DE
> #define CL_UNORM_INT24 0x10DF
> +#define CL_UNORM_INT_101010_2 0x10E0
>
> /* cl_mem_object_type */
> #define CL_MEM_OBJECT_BUFFER 0x10F0
> @@ -397,6 +461,7 @@ typedef struct _cl_buffer_region {
> #define CL_MEM_OBJECT_IMAGE1D 0x10F4
> #define CL_MEM_OBJECT_IMAGE1D_ARRAY 0x10F5
> #define CL_MEM_OBJECT_IMAGE1D_BUFFER 0x10F6
> +#define CL_MEM_OBJECT_PIPE 0x10F7
>
> /* cl_mem_info */
> #define CL_MEM_TYPE 0x1100
> @@ -408,6 +473,7 @@ typedef struct _cl_buffer_region {
> #define CL_MEM_CONTEXT 0x1106
> #define CL_MEM_ASSOCIATED_MEMOBJECT 0x1107
> #define CL_MEM_OFFSET 0x1108
> +#define CL_MEM_USES_SVM_POINTER 0x1109
>
> /* cl_image_info */
> #define CL_IMAGE_FORMAT 0x1110
> @@ -421,6 +487,10 @@ typedef struct _cl_buffer_region {
> #define CL_IMAGE_BUFFER 0x1118
> #define CL_IMAGE_NUM_MIP_LEVELS 0x1119
> #define CL_IMAGE_NUM_SAMPLES 0x111A
> +
> +/* cl_pipe_info */
> +#define CL_PIPE_PACKET_SIZE 0x1120
> +#define CL_PIPE_MAX_PACKETS 0x1121
>
> /* cl_addressing_mode */
> #define CL_ADDRESS_NONE 0x1130
> @@ -439,6 +509,9 @@ typedef struct _cl_buffer_region {
> #define CL_SAMPLER_NORMALIZED_COORDS 0x1152
> #define CL_SAMPLER_ADDRESSING_MODE 0x1153
> #define CL_SAMPLER_FILTER_MODE 0x1154
> +#define CL_SAMPLER_MIP_FILTER_MODE 0x1155
> +#define CL_SAMPLER_LOD_MIN 0x1156
> +#define CL_SAMPLER_LOD_MAX 0x1157
>
> /* cl_map_flags - bitfield */
> #define CL_MAP_READ (1 << 0)
> @@ -455,12 +528,16 @@ typedef struct _cl_buffer_region {
> #define CL_PROGRAM_BINARIES 0x1166
> #define CL_PROGRAM_NUM_KERNELS 0x1167
> #define CL_PROGRAM_KERNEL_NAMES 0x1168
> +#define CL_PROGRAM_IL 0x1169
> +#define CL_PROGRAM_SCOPE_GLOBAL_CTORS_PRESENT 0x116A
> +#define CL_PROGRAM_SCOPE_GLOBAL_DTORS_PRESENT 0x116B
>
> /* cl_program_build_info */
> #define CL_PROGRAM_BUILD_STATUS 0x1181
> #define CL_PROGRAM_BUILD_OPTIONS 0x1182
> #define CL_PROGRAM_BUILD_LOG 0x1183
> #define CL_PROGRAM_BINARY_TYPE 0x1184
> +#define CL_PROGRAM_BUILD_GLOBAL_VARIABLE_TOTAL_SIZE 0x1185
>
> /* cl_program_binary_type */
> #define CL_PROGRAM_BINARY_TYPE_NONE 0x0
> @@ -481,6 +558,8 @@ typedef struct _cl_buffer_region {
> #define CL_KERNEL_CONTEXT 0x1193
> #define CL_KERNEL_PROGRAM 0x1194
> #define CL_KERNEL_ATTRIBUTES 0x1195
> +#define CL_KERNEL_MAX_NUM_SUB_GROUPS 0x11B9
> +#define CL_KERNEL_COMPILE_NUM_SUB_GROUPS 0x11BA
>
> /* cl_kernel_arg_info */
> #define CL_KERNEL_ARG_ADDRESS_QUALIFIER 0x1196
> @@ -501,11 +580,12 @@ typedef struct _cl_buffer_region {
> #define CL_KERNEL_ARG_ACCESS_READ_WRITE 0x11A2
> #define CL_KERNEL_ARG_ACCESS_NONE 0x11A3
>
> -/* cl_kernel_arg_type_qualifer */
> +/* cl_kernel_arg_type_qualifier */
> #define CL_KERNEL_ARG_TYPE_NONE 0
> #define CL_KERNEL_ARG_TYPE_CONST (1 << 0)
> #define CL_KERNEL_ARG_TYPE_RESTRICT (1 << 1)
> #define CL_KERNEL_ARG_TYPE_VOLATILE (1 << 2)
> +#define CL_KERNEL_ARG_TYPE_PIPE (1 << 3)
>
> /* cl_kernel_work_group_info */
> #define CL_KERNEL_WORK_GROUP_SIZE 0x11B0
> @@ -515,6 +595,15 @@ typedef struct _cl_buffer_region {
> #define CL_KERNEL_PRIVATE_MEM_SIZE 0x11B4
> #define CL_KERNEL_GLOBAL_WORK_SIZE 0x11B5
>
> +/* cl_kernel_sub_group_info */
> +#define CL_KERNEL_MAX_SUB_GROUP_SIZE_FOR_NDRANGE 0x2033
> +#define CL_KERNEL_SUB_GROUP_COUNT_FOR_NDRANGE 0x2034
> +#define CL_KERNEL_LOCAL_SIZE_FOR_SUB_GROUP_COUNT 0x11B8
> +
> +/* cl_kernel_exec_info */
> +#define CL_KERNEL_EXEC_INFO_SVM_PTRS 0x11B6
> +#define CL_KERNEL_EXEC_INFO_SVM_FINE_GRAIN_SYSTEM 0x11B7
> +
> /* cl_event_info */
> #define CL_EVENT_COMMAND_QUEUE 0x11D0
> #define CL_EVENT_COMMAND_TYPE 0x11D1
> @@ -548,6 +637,11 @@ typedef struct _cl_buffer_region {
> #define CL_COMMAND_MIGRATE_MEM_OBJECTS 0x1206
> #define CL_COMMAND_FILL_BUFFER 0x1207
> #define CL_COMMAND_FILL_IMAGE 0x1208
> +#define CL_COMMAND_SVM_FREE 0x1209
> +#define CL_COMMAND_SVM_MEMCPY 0x120A
> +#define CL_COMMAND_SVM_MEMFILL 0x120B
> +#define CL_COMMAND_SVM_MAP 0x120C
> +#define CL_COMMAND_SVM_UNMAP 0x120D
>
> /* command execution status */
> #define CL_COMPLETE 0x0
> @@ -563,6 +657,7 @@ typedef struct _cl_buffer_region {
> #define CL_PROFILING_COMMAND_SUBMIT 0x1281
> #define CL_PROFILING_COMMAND_START 0x1282
> #define CL_PROFILING_COMMAND_END 0x1283
> +#define CL_PROFILING_COMMAND_COMPLETE 0x1284
>
> /********************************************************************************************************/
>
> @@ -606,6 +701,21 @@ clRetainDevice(cl_device_id /* device */) CL_API_SUFFIX__VERSION_1_2;
>
> extern CL_API_ENTRY cl_int CL_API_CALL
> clReleaseDevice(cl_device_id /* device */) CL_API_SUFFIX__VERSION_1_2;
> +
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clSetDefaultDeviceCommandQueue(cl_context /* context */,
> + cl_device_id /* device */,
> + cl_command_queue /* command_queue */) CL_API_SUFFIX__VERSION_2_1;
> +
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clGetDeviceAndHostTimer(cl_device_id /* device */,
> + cl_ulong* /* device_timestamp */,
> + cl_ulong* /* host_timestamp */) CL_API_SUFFIX__VERSION_2_1;
> +
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clGetHostTimer(cl_device_id /* device */,
> + cl_ulong * /* host_timestamp */) CL_API_SUFFIX__VERSION_2_1;
> +
>
> /* Context APIs */
> extern CL_API_ENTRY cl_context CL_API_CALL
> @@ -638,10 +748,10 @@ clGetContextInfo(cl_context /* context */,
>
> /* Command Queue APIs */
> extern CL_API_ENTRY cl_command_queue CL_API_CALL
> -clCreateCommandQueue(cl_context /* context */,
> - cl_device_id /* device */,
> - cl_command_queue_properties /* properties */,
> - cl_int * /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0;
> +clCreateCommandQueueWithProperties(cl_context /* context */,
> + cl_device_id /* device */,
> + const cl_queue_properties * /* properties */,
> + cl_int * /* errcode_ret */) CL_API_SUFFIX__VERSION_2_0;
>
> extern CL_API_ENTRY cl_int CL_API_CALL
> clRetainCommandQueue(cl_command_queue /* command_queue */) CL_API_SUFFIX__VERSION_1_0;
> @@ -679,6 +789,14 @@ clCreateImage(cl_context /* context */,
> void * /* host_ptr */,
> cl_int * /* errcode_ret */) CL_API_SUFFIX__VERSION_1_2;
>
> +extern CL_API_ENTRY cl_mem CL_API_CALL
> +clCreatePipe(cl_context /* context */,
> + cl_mem_flags /* flags */,
> + cl_uint /* pipe_packet_size */,
> + cl_uint /* pipe_max_packets */,
> + const cl_pipe_properties * /* properties */,
> + cl_int * /* errcode_ret */) CL_API_SUFFIX__VERSION_2_0;
> +
> extern CL_API_ENTRY cl_int CL_API_CALL
> clRetainMemObject(cl_mem /* memobj */) CL_API_SUFFIX__VERSION_1_0;
>
> @@ -706,19 +824,36 @@ clGetImageInfo(cl_mem /* image */,
> size_t /* param_value_size */,
> void * /* param_value */,
> size_t * /* param_value_size_ret */) CL_API_SUFFIX__VERSION_1_0;
> +
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clGetPipeInfo(cl_mem /* pipe */,
> + cl_pipe_info /* param_name */,
> + size_t /* param_value_size */,
> + void * /* param_value */,
> + size_t * /* param_value_size_ret */) CL_API_SUFFIX__VERSION_2_0;
> +
>
> extern CL_API_ENTRY cl_int CL_API_CALL
> -clSetMemObjectDestructorCallback( cl_mem /* memobj */,
> - void (CL_CALLBACK * /*pfn_notify*/)( cl_mem /* memobj */, void* /*user_data*/),
> - void * /*user_data */ ) CL_API_SUFFIX__VERSION_1_1;
> +clSetMemObjectDestructorCallback(cl_mem /* memobj */,
> + void (CL_CALLBACK * /*pfn_notify*/)( cl_mem /* memobj */, void* /*user_data*/),
> + void * /*user_data */ ) CL_API_SUFFIX__VERSION_1_1;
>
> +/* SVM Allocation APIs */
> +extern CL_API_ENTRY void * CL_API_CALL
> +clSVMAlloc(cl_context /* context */,
> + cl_svm_mem_flags /* flags */,
> + size_t /* size */,
> + cl_uint /* alignment */) CL_API_SUFFIX__VERSION_2_0;
> +
> +extern CL_API_ENTRY void CL_API_CALL
> +clSVMFree(cl_context /* context */,
> + void * /* svm_pointer */) CL_API_SUFFIX__VERSION_2_0;
> +
> /* Sampler APIs */
> extern CL_API_ENTRY cl_sampler CL_API_CALL
> -clCreateSampler(cl_context /* context */,
> - cl_bool /* normalized_coords */,
> - cl_addressing_mode /* addressing_mode */,
> - cl_filter_mode /* filter_mode */,
> - cl_int * /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0;
> +clCreateSamplerWithProperties(cl_context /* context */,
> + const cl_sampler_properties * /* normalized_coords */,
> + cl_int * /* errcode_ret */) CL_API_SUFFIX__VERSION_2_0;
>
> extern CL_API_ENTRY cl_int CL_API_CALL
> clRetainSampler(cl_sampler /* sampler */) CL_API_SUFFIX__VERSION_1_0;
> @@ -757,6 +892,13 @@ clCreateProgramWithBuiltInKernels(cl_context /* context */,
> const char * /* kernel_names */,
> cl_int * /* errcode_ret */) CL_API_SUFFIX__VERSION_1_2;
>
> +extern CL_API_ENTRY cl_program CL_API_CALL
> +clCreateProgramWithIL(cl_context /* context */,
> + const void* /* il */,
> + size_t /* length */,
> + cl_int* /* errcode_ret */) CL_API_SUFFIX__VERSION_2_1;
> +
> +
> extern CL_API_ENTRY cl_int CL_API_CALL
> clRetainProgram(cl_program /* program */) CL_API_SUFFIX__VERSION_1_0;
>
> @@ -793,6 +935,17 @@ clLinkProgram(cl_context /* context */,
> void * /* user_data */,
> cl_int * /* errcode_ret */ ) CL_API_SUFFIX__VERSION_1_2;
>
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clSetProgramReleaseCallback(cl_program /* program */,
> + void (CL_CALLBACK * /* pfn_notify */)(cl_program /* program */, void * /* user_data */),
> + void * /* user_data */) CL_API_SUFFIX__VERSION_2_2;
> +
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clSetProgramSpecializationConstant(cl_program /* program */,
> + cl_uint /* spec_id */,
> + size_t /* spec_size */,
> + const void* /* spec_value */) CL_API_SUFFIX__VERSION_2_2;
> +
>
> extern CL_API_ENTRY cl_int CL_API_CALL
> clUnloadPlatformCompiler(cl_platform_id /* platform */) CL_API_SUFFIX__VERSION_1_2;
> @@ -824,6 +977,10 @@ clCreateKernelsInProgram(cl_program /* program */,
> cl_kernel * /* kernels */,
> cl_uint * /* num_kernels_ret */) CL_API_SUFFIX__VERSION_1_0;
>
> +extern CL_API_ENTRY cl_kernel CL_API_CALL
> +clCloneKernel(cl_kernel /* source_kernel */,
> + cl_int* /* errcode_ret */) CL_API_SUFFIX__VERSION_2_1;
> +
> extern CL_API_ENTRY cl_int CL_API_CALL
> clRetainKernel(cl_kernel /* kernel */) CL_API_SUFFIX__VERSION_1_0;
>
> @@ -836,6 +993,17 @@ clSetKernelArg(cl_kernel /* kernel */,
> size_t /* arg_size */,
> const void * /* arg_value */) CL_API_SUFFIX__VERSION_1_0;
>
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clSetKernelArgSVMPointer(cl_kernel /* kernel */,
> + cl_uint /* arg_index */,
> + const void * /* arg_value */) CL_API_SUFFIX__VERSION_2_0;
> +
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clSetKernelExecInfo(cl_kernel /* kernel */,
> + cl_kernel_exec_info /* param_name */,
> + size_t /* param_value_size */,
> + const void * /* param_value */) CL_API_SUFFIX__VERSION_2_0;
> +
> extern CL_API_ENTRY cl_int CL_API_CALL
> clGetKernelInfo(cl_kernel /* kernel */,
> cl_kernel_info /* param_name */,
> @@ -859,6 +1027,17 @@ clGetKernelWorkGroupInfo(cl_kernel /* kernel */,
> void * /* param_value */,
> size_t * /* param_value_size_ret */) CL_API_SUFFIX__VERSION_1_0;
>
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clGetKernelSubGroupInfo(cl_kernel /* kernel */,
> + cl_device_id /* device */,
> + cl_kernel_sub_group_info /* param_name */,
> + size_t /* input_value_size */,
> + const void* /*input_value */,
> + size_t /* param_value_size */,
> + void* /* param_value */,
> + size_t* /* param_value_size_ret */ ) CL_API_SUFFIX__VERSION_2_1;
> +
> +
> /* Event Object APIs */
> extern CL_API_ENTRY cl_int CL_API_CALL
> clWaitForEvents(cl_uint /* num_events */,
> @@ -1121,13 +1300,6 @@ clEnqueueNDRangeKernel(cl_command_queue /* command_queue */,
> const cl_event * /* event_wait_list */,
> cl_event * /* event */) CL_API_SUFFIX__VERSION_1_0;
>
> -extern CL_API_ENTRY cl_int CL_API_CALL
> -clEnqueueTask(cl_command_queue /* command_queue */,
> - cl_kernel /* kernel */,
> - cl_uint /* num_events_in_wait_list */,
> - const cl_event * /* event_wait_list */,
> - cl_event * /* event */) CL_API_SUFFIX__VERSION_1_0;
> -
> extern CL_API_ENTRY cl_int CL_API_CALL
> clEnqueueNativeKernel(cl_command_queue /* command_queue */,
> void (CL_CALLBACK * /*user_func*/)(void *),
> @@ -1141,17 +1313,77 @@ clEnqueueNativeKernel(cl_command_queue /* command_queue */,
> cl_event * /* event */) CL_API_SUFFIX__VERSION_1_0;
>
> extern CL_API_ENTRY cl_int CL_API_CALL
> -clEnqueueMarkerWithWaitList(cl_command_queue /* command_queue */,
> +clEnqueueMarkerWithWaitList(cl_command_queue /* command_queue */,
> cl_uint /* num_events_in_wait_list */,
> const cl_event * /* event_wait_list */,
> cl_event * /* event */) CL_API_SUFFIX__VERSION_1_2;
>
> extern CL_API_ENTRY cl_int CL_API_CALL
> -clEnqueueBarrierWithWaitList(cl_command_queue /* command_queue */,
> +clEnqueueBarrierWithWaitList(cl_command_queue /* command_queue */,
> cl_uint /* num_events_in_wait_list */,
> const cl_event * /* event_wait_list */,
> cl_event * /* event */) CL_API_SUFFIX__VERSION_1_2;
>
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clEnqueueSVMFree(cl_command_queue /* command_queue */,
> + cl_uint /* num_svm_pointers */,
> + void *[] /* svm_pointers[] */,
> + void (CL_CALLBACK * /*pfn_free_func*/)(cl_command_queue /* queue */,
> + cl_uint /* num_svm_pointers */,
> + void *[] /* svm_pointers[] */,
> + void * /* user_data */),
> + void * /* user_data */,
> + cl_uint /* num_events_in_wait_list */,
> + const cl_event * /* event_wait_list */,
> + cl_event * /* event */) CL_API_SUFFIX__VERSION_2_0;
> +
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clEnqueueSVMMemcpy(cl_command_queue /* command_queue */,
> + cl_bool /* blocking_copy */,
> + void * /* dst_ptr */,
> + const void * /* src_ptr */,
> + size_t /* size */,
> + cl_uint /* num_events_in_wait_list */,
> + const cl_event * /* event_wait_list */,
> + cl_event * /* event */) CL_API_SUFFIX__VERSION_2_0;
> +
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clEnqueueSVMMemFill(cl_command_queue /* command_queue */,
> + void * /* svm_ptr */,
> + const void * /* pattern */,
> + size_t /* pattern_size */,
> + size_t /* size */,
> + cl_uint /* num_events_in_wait_list */,
> + const cl_event * /* event_wait_list */,
> + cl_event * /* event */) CL_API_SUFFIX__VERSION_2_0;
> +
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clEnqueueSVMMap(cl_command_queue /* command_queue */,
> + cl_bool /* blocking_map */,
> + cl_map_flags /* flags */,
> + void * /* svm_ptr */,
> + size_t /* size */,
> + cl_uint /* num_events_in_wait_list */,
> + const cl_event * /* event_wait_list */,
> + cl_event * /* event */) CL_API_SUFFIX__VERSION_2_0;
> +
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clEnqueueSVMUnmap(cl_command_queue /* command_queue */,
> + void * /* svm_ptr */,
> + cl_uint /* num_events_in_wait_list */,
> + const cl_event * /* event_wait_list */,
> + cl_event * /* event */) CL_API_SUFFIX__VERSION_2_0;
> +
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clEnqueueSVMMigrateMem(cl_command_queue /* command_queue */,
> + cl_uint /* num_svm_pointers */,
> + const void ** /* svm_pointers */,
> + const size_t * /* sizes */,
> + cl_mem_migration_flags /* flags */,
> + cl_uint /* num_events_in_wait_list */,
> + const cl_event * /* event_wait_list */,
> + cl_event * /* event */) CL_API_SUFFIX__VERSION_2_1;
> +
>
> /* Extension function access
> *
> @@ -1205,7 +1437,29 @@ clUnloadCompiler(void) CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED;
>
> extern CL_API_ENTRY CL_EXT_PREFIX__VERSION_1_1_DEPRECATED void * CL_API_CALL
> clGetExtensionFunctionAddress(const char * /* func_name */) CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED;
> -
> +
> +/* Deprecated OpenCL 2.0 APIs */
> +extern CL_API_ENTRY CL_EXT_PREFIX__VERSION_1_2_DEPRECATED cl_command_queue CL_API_CALL
> +clCreateCommandQueue(cl_context /* context */,
> + cl_device_id /* device */,
> + cl_command_queue_properties /* properties */,
> + cl_int * /* errcode_ret */) CL_EXT_SUFFIX__VERSION_1_2_DEPRECATED;
> +
> +
> +extern CL_API_ENTRY CL_EXT_PREFIX__VERSION_1_2_DEPRECATED cl_sampler CL_API_CALL
> +clCreateSampler(cl_context /* context */,
> + cl_bool /* normalized_coords */,
> + cl_addressing_mode /* addressing_mode */,
> + cl_filter_mode /* filter_mode */,
> + cl_int * /* errcode_ret */) CL_EXT_SUFFIX__VERSION_1_2_DEPRECATED;
> +
> +extern CL_API_ENTRY CL_EXT_PREFIX__VERSION_1_2_DEPRECATED cl_int CL_API_CALL
> +clEnqueueTask(cl_command_queue /* command_queue */,
> + cl_kernel /* kernel */,
> + cl_uint /* num_events_in_wait_list */,
> + const cl_event * /* event_wait_list */,
> + cl_event * /* event */) CL_EXT_SUFFIX__VERSION_1_2_DEPRECATED;
> +
> #ifdef __cplusplus
> }
> #endif
> diff --git a/include/CL/cl_d3d10.h b/include/CL/cl_d3d10.h
> index b6c90b328d..d5960a43f7 100644
> --- a/include/CL/cl_d3d10.h
> +++ b/include/CL/cl_d3d10.h
> @@ -1,5 +1,5 @@
> /**********************************************************************************
> - * Copyright (c) 2008-2012 The Khronos Group Inc.
> + * Copyright (c) 2008-2015 The Khronos Group Inc.
> *
> * Permission is hereby granted, free of charge, to any person obtaining a
> * copy of this software and/or associated documentation files (the
> @@ -12,6 +12,11 @@
> * The above copyright notice and this permission notice shall be included
> * in all copies or substantial portions of the Materials.
> *
> + * MODIFICATIONS TO THIS FILE MAY MEAN IT NO LONGER ACCURATELY REFLECTS
> + * KHRONOS STANDARDS. THE UNMODIFIED, NORMATIVE VERSIONS OF KHRONOS
> + * SPECIFICATIONS AND HEADER INFORMATION ARE LOCATED AT
> + * https://www.khronos.org/registry/
> + *
> * THE MATERIALS ARE PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND,
> * EXPRESS OR IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF
> * MERCHANTABILITY, FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT.
> diff --git a/include/CL/cl_d3d11.h b/include/CL/cl_d3d11.h
> index 2e0a63fd3e..39f9072398 100644
> --- a/include/CL/cl_d3d11.h
> +++ b/include/CL/cl_d3d11.h
> @@ -1,5 +1,5 @@
> /**********************************************************************************
> - * Copyright (c) 2008-2012 The Khronos Group Inc.
> + * Copyright (c) 2008-2015 The Khronos Group Inc.
> *
> * Permission is hereby granted, free of charge, to any person obtaining a
> * copy of this software and/or associated documentation files (the
> @@ -12,6 +12,11 @@
> * The above copyright notice and this permission notice shall be included
> * in all copies or substantial portions of the Materials.
> *
> + * MODIFICATIONS TO THIS FILE MAY MEAN IT NO LONGER ACCURATELY REFLECTS
> + * KHRONOS STANDARDS. THE UNMODIFIED, NORMATIVE VERSIONS OF KHRONOS
> + * SPECIFICATIONS AND HEADER INFORMATION ARE LOCATED AT
> + * https://www.khronos.org/registry/
> + *
> * THE MATERIALS ARE PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND,
> * EXPRESS OR IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF
> * MERCHANTABILITY, FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT.
> diff --git a/include/CL/cl_dx9_media_sharing.h b/include/CL/cl_dx9_media_sharing.h
> index 23f1631786..2729e8b9e8 100644
> --- a/include/CL/cl_dx9_media_sharing.h
> +++ b/include/CL/cl_dx9_media_sharing.h
> @@ -1,5 +1,5 @@
> /**********************************************************************************
> - * Copyright (c) 2008-2012 The Khronos Group Inc.
> + * Copyright (c) 2008-2015 The Khronos Group Inc.
> *
> * Permission is hereby granted, free of charge, to any person obtaining a
> * copy of this software and/or associated documentation files (the
> @@ -12,6 +12,11 @@
> * The above copyright notice and this permission notice shall be included
> * in all copies or substantial portions of the Materials.
> *
> + * MODIFICATIONS TO THIS FILE MAY MEAN IT NO LONGER ACCURATELY REFLECTS
> + * KHRONOS STANDARDS. THE UNMODIFIED, NORMATIVE VERSIONS OF KHRONOS
> + * SPECIFICATIONS AND HEADER INFORMATION ARE LOCATED AT
> + * https://www.khronos.org/registry/
> + *
> * THE MATERIALS ARE PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND,
> * EXPRESS OR IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF
> * MERCHANTABILITY, FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT.
> @@ -33,7 +38,7 @@
> extern "C" {
> #endif
>
> -/******************************************************************************
> +/******************************************************************************/
> /* cl_khr_dx9_media_sharing */
> #define cl_khr_dx9_media_sharing 1
>
> diff --git a/include/CL/cl_dx9_media_sharing_intel.h b/include/CL/cl_dx9_media_sharing_intel.h
> new file mode 100644
> index 0000000000..331bab97c7
> --- /dev/null
> +++ b/include/CL/cl_dx9_media_sharing_intel.h
> @@ -0,0 +1,182 @@
> +/**********************************************************************************
> + * Copyright (c) 2008-2016 The Khronos Group Inc.
> + *
> + * Permission is hereby granted, free of charge, to any person obtaining a
> + * copy of this software and/or associated documentation files (the
> + * "Materials"), to deal in the Materials without restriction, including
> + * without limitation the rights to use, copy, modify, merge, publish,
> + * distribute, sublicense, and/or sell copies of the Materials, and to
> + * permit persons to whom the Materials are furnished to do so, subject to
> + * the following conditions:
> + *
> + * The above copyright notice and this permission notice shall be included
> + * in all copies or substantial portions of the Materials.
> + *
> + * MODIFICATIONS TO THIS FILE MAY MEAN IT NO LONGER ACCURATELY REFLECTS
> + * KHRONOS STANDARDS. THE UNMODIFIED, NORMATIVE VERSIONS OF KHRONOS
> + * SPECIFICATIONS AND HEADER INFORMATION ARE LOCATED AT
> + * https://www.khronos.org/registry/
> + *
> + * THE MATERIALS ARE PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND,
> + * EXPRESS OR IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF
> + * MERCHANTABILITY, FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT.
> + * IN NO EVENT SHALL THE AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY
> + * CLAIM, DAMAGES OR OTHER LIABILITY, WHETHER IN AN ACTION OF CONTRACT,
> + * TORT OR OTHERWISE, ARISING FROM, OUT OF OR IN CONNECTION WITH THE
> + * MATERIALS OR THE USE OR OTHER DEALINGS IN THE MATERIALS.
> + **********************************************************************************/
> +/*****************************************************************************\
> +
> +Copyright (c) 2013-2016 Intel Corporation All Rights Reserved.
> +
> +THESE MATERIALS ARE PROVIDED BY THE COPYRIGHT HOLDERS AND CONTRIBUTORS
> +"AS IS" AND ANY EXPRESS OR IMPLIED WARRANTIES, INCLUDING, BUT NOT
> +LIMITED TO, THE IMPLIED WARRANTIES OF MERCHANTABILITY AND FITNESS FOR
> +A PARTICULAR PURPOSE ARE DISCLAIMED. IN NO EVENT SHALL INTEL OR ITS
> +CONTRIBUTORS BE LIABLE FOR ANY DIRECT, INDIRECT, INCIDENTAL, SPECIAL,
> +EXEMPLARY, OR CONSEQUENTIAL DAMAGES (INCLUDING, BUT NOT LIMITED TO,
> +PROCUREMENT OF SUBSTITUTE GOODS OR SERVICES; LOSS OF USE, DATA, OR
> +PROFITS; OR BUSINESS INTERRUPTION) HOWEVER CAUSED AND ON ANY THEORY
> +OF LIABILITY, WHETHER IN CONTRACT, STRICT LIABILITY OR TORT (INCLUDING
> +NEGLIGENCE OR OTHERWISE) ARISING IN ANY WAY OUT OF THE USE OF THESE
> +MATERIALS, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE.
> +
> +File Name: cl_dx9_media_sharing_intel.h
> +
> +Abstract:
> +
> +Notes:
> +
> +\*****************************************************************************/
> +
> +#ifndef __OPENCL_CL_DX9_MEDIA_SHARING_INTEL_H
> +#define __OPENCL_CL_DX9_MEDIA_SHARING_INTEL_H
> +
> +#include <CL/cl.h>
> +#include <CL/cl_platform.h>
> +#include <d3d9.h>
> +#include <dxvahd.h>
> +#include <wtypes.h>
> +#include <d3d9types.h>
> +
> +#ifdef __cplusplus
> +extern "C" {
> +#endif
> +
> +/***************************************
> +* cl_intel_dx9_media_sharing extension *
> +****************************************/
> +
> +#define cl_intel_dx9_media_sharing 1
> +
> +typedef cl_uint cl_dx9_device_source_intel;
> +typedef cl_uint cl_dx9_device_set_intel;
> +
> +/* error codes */
> +#define CL_INVALID_DX9_DEVICE_INTEL -1010
> +#define CL_INVALID_DX9_RESOURCE_INTEL -1011
> +#define CL_DX9_RESOURCE_ALREADY_ACQUIRED_INTEL -1012
> +#define CL_DX9_RESOURCE_NOT_ACQUIRED_INTEL -1013
> +
> +/* cl_dx9_device_source_intel */
> +#define CL_D3D9_DEVICE_INTEL 0x4022
> +#define CL_D3D9EX_DEVICE_INTEL 0x4070
> +#define CL_DXVA_DEVICE_INTEL 0x4071
> +
> +/* cl_dx9_device_set_intel */
> +#define CL_PREFERRED_DEVICES_FOR_DX9_INTEL 0x4024
> +#define CL_ALL_DEVICES_FOR_DX9_INTEL 0x4025
> +
> +/* cl_context_info */
> +#define CL_CONTEXT_D3D9_DEVICE_INTEL 0x4026
> +#define CL_CONTEXT_D3D9EX_DEVICE_INTEL 0x4072
> +#define CL_CONTEXT_DXVA_DEVICE_INTEL 0x4073
> +
> +/* cl_mem_info */
> +#define CL_MEM_DX9_RESOURCE_INTEL 0x4027
> +#define CL_MEM_DX9_SHARED_HANDLE_INTEL 0x4074
> +
> +/* cl_image_info */
> +#define CL_IMAGE_DX9_PLANE_INTEL 0x4075
> +
> +/* cl_command_type */
> +#define CL_COMMAND_ACQUIRE_DX9_OBJECTS_INTEL 0x402A
> +#define CL_COMMAND_RELEASE_DX9_OBJECTS_INTEL 0x402B
> +/******************************************************************************/
> +
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clGetDeviceIDsFromDX9INTEL(
> + cl_platform_id /* platform */,
> + cl_dx9_device_source_intel /* dx9_device_source */,
> + void* /* dx9_object */,
> + cl_dx9_device_set_intel /* dx9_device_set */,
> + cl_uint /* num_entries */,
> + cl_device_id* /* devices */,
> + cl_uint* /* num_devices */) CL_EXT_SUFFIX__VERSION_1_1;
> +
> +typedef CL_API_ENTRY cl_int (CL_API_CALL* clGetDeviceIDsFromDX9INTEL_fn)(
> + cl_platform_id /* platform */,
> + cl_dx9_device_source_intel /* dx9_device_source */,
> + void* /* dx9_object */,
> + cl_dx9_device_set_intel /* dx9_device_set */,
> + cl_uint /* num_entries */,
> + cl_device_id* /* devices */,
> + cl_uint* /* num_devices */) CL_EXT_SUFFIX__VERSION_1_1;
> +
> +extern CL_API_ENTRY cl_mem CL_API_CALL
> +clCreateFromDX9MediaSurfaceINTEL(
> + cl_context /* context */,
> + cl_mem_flags /* flags */,
> + IDirect3DSurface9* /* resource */,
> + HANDLE /* sharedHandle */,
> + UINT /* plane */,
> + cl_int* /* errcode_ret */) CL_EXT_SUFFIX__VERSION_1_1;
> +
> +typedef CL_API_ENTRY cl_mem (CL_API_CALL *clCreateFromDX9MediaSurfaceINTEL_fn)(
> + cl_context /* context */,
> + cl_mem_flags /* flags */,
> + IDirect3DSurface9* /* resource */,
> + HANDLE /* sharedHandle */,
> + UINT /* plane */,
> + cl_int* /* errcode_ret */) CL_EXT_SUFFIX__VERSION_1_1;
> +
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clEnqueueAcquireDX9ObjectsINTEL(
> + cl_command_queue /* command_queue */,
> + cl_uint /* num_objects */,
> + const cl_mem* /* mem_objects */,
> + cl_uint /* num_events_in_wait_list */,
> + const cl_event* /* event_wait_list */,
> + cl_event* /* event */) CL_EXT_SUFFIX__VERSION_1_1;
> +
> +typedef CL_API_ENTRY cl_int (CL_API_CALL *clEnqueueAcquireDX9ObjectsINTEL_fn)(
> + cl_command_queue /* command_queue */,
> + cl_uint /* num_objects */,
> + const cl_mem* /* mem_objects */,
> + cl_uint /* num_events_in_wait_list */,
> + const cl_event* /* event_wait_list */,
> + cl_event* /* event */) CL_EXT_SUFFIX__VERSION_1_1;
> +
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clEnqueueReleaseDX9ObjectsINTEL(
> + cl_command_queue /* command_queue */,
> + cl_uint /* num_objects */,
> + cl_mem* /* mem_objects */,
> + cl_uint /* num_events_in_wait_list */,
> + const cl_event* /* event_wait_list */,
> + cl_event* /* event */) CL_EXT_SUFFIX__VERSION_1_1;
> +
> +typedef CL_API_ENTRY cl_int (CL_API_CALL *clEnqueueReleaseDX9ObjectsINTEL_fn)(
> + cl_command_queue /* command_queue */,
> + cl_uint /* num_objects */,
> + cl_mem* /* mem_objects */,
> + cl_uint /* num_events_in_wait_list */,
> + const cl_event* /* event_wait_list */,
> + cl_event* /* event */) CL_EXT_SUFFIX__VERSION_1_1;
> +
> +#ifdef __cplusplus
> +}
> +#endif
> +
> +#endif /* __OPENCL_CL_DX9_MEDIA_SHARING_INTEL_H */
> +
> diff --git a/include/CL/cl_egl.h b/include/CL/cl_egl.h
> index 93e6c9cfba..a765bd5266 100644
> --- a/include/CL/cl_egl.h
> +++ b/include/CL/cl_egl.h
> @@ -1,5 +1,5 @@
> /*******************************************************************************
> - * Copyright (c) 2008-2010 The Khronos Group Inc.
> + * Copyright (c) 2008-2015 The Khronos Group Inc.
> *
> * Permission is hereby granted, free of charge, to any person obtaining a
> * copy of this software and/or associated documentation files (the
> @@ -12,6 +12,11 @@
> * The above copyright notice and this permission notice shall be included
> * in all copies or substantial portions of the Materials.
> *
> + * MODIFICATIONS TO THIS FILE MAY MEAN IT NO LONGER ACCURATELY REFLECTS
> + * KHRONOS STANDARDS. THE UNMODIFIED, NORMATIVE VERSIONS OF KHRONOS
> + * SPECIFICATIONS AND HEADER INFORMATION ARE LOCATED AT
> + * https://www.khronos.org/registry/
> + *
> * THE MATERIALS ARE PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND,
> * EXPRESS OR IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF
> * MERCHANTABILITY, FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT.
> @@ -28,8 +33,6 @@
>
> #else
> #include <CL/cl.h>
> -#include <EGL/egl.h>
> -#include <EGL/eglext.h>
> #endif
>
> #ifdef __cplusplus
> diff --git a/include/CL/cl_ext.h b/include/CL/cl_ext.h
> index 710bea8837..5078e8f45f 100644
> --- a/include/CL/cl_ext.h
> +++ b/include/CL/cl_ext.h
> @@ -1,5 +1,5 @@
> /*******************************************************************************
> - * Copyright (c) 2008-2013 The Khronos Group Inc.
> + * Copyright (c) 2008-2015 The Khronos Group Inc.
> *
> * Permission is hereby granted, free of charge, to any person obtaining a
> * copy of this software and/or associated documentation files (the
> @@ -12,6 +12,11 @@
> * The above copyright notice and this permission notice shall be included
> * in all copies or substantial portions of the Materials.
> *
> + * MODIFICATIONS TO THIS FILE MAY MEAN IT NO LONGER ACCURATELY REFLECTS
> + * KHRONOS STANDARDS. THE UNMODIFIED, NORMATIVE VERSIONS OF KHRONOS
> + * SPECIFICATIONS AND HEADER INFORMATION ARE LOCATED AT
> + * https://www.khronos.org/registry/
> + *
> * THE MATERIALS ARE PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND,
> * EXPRESS OR IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF
> * MERCHANTABILITY, FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT.
> @@ -134,15 +139,15 @@ typedef CL_API_ENTRY cl_int (CL_API_CALL *clIcdGetPlatformIDsKHR_fn)(
> * cl_khr_initalize_memory extension *
> *************************************/
>
> -#define CL_CONTEXT_MEMORY_INITIALIZE_KHR 0x200E
> +#define CL_CONTEXT_MEMORY_INITIALIZE_KHR 0x2030
>
>
> /**************************************
> * cl_khr_terminate_context extension *
> **************************************/
>
> -#define CL_DEVICE_TERMINATE_CAPABILITY_KHR 0x200F
> -#define CL_CONTEXT_TERMINATE_KHR 0x2010
> +#define CL_DEVICE_TERMINATE_CAPABILITY_KHR 0x2031
> +#define CL_CONTEXT_TERMINATE_KHR 0x2032
>
> #define cl_khr_terminate_context 1
> extern CL_API_ENTRY cl_int CL_API_CALL clTerminateContextKHR(cl_context /* context */) CL_EXT_SUFFIX__VERSION_1_2;
> @@ -281,7 +286,7 @@ typedef struct _cl_mem_ext_host_ptr
> /* Legal values will be defined in layered extensions. */
> cl_uint allocation_type;
>
> - /* Host cache policy for this external memory allocation. */
> + /* Host cache policy for this external memory allocation. */
> cl_uint host_cache_policy;
>
> } cl_mem_ext_host_ptr;
> @@ -308,6 +313,292 @@ typedef struct _cl_mem_ion_host_ptr
>
> #endif /* CL_VERSION_1_1 */
>
> +#if defined(CL_VERSION_1_2)
> +
> +/******************************************
> + * cl_img_yuv_image extension *
> + ******************************************/
> +
> +/* Image formats used in clCreateImage */
> +#define CL_NV21_IMG 0x40D0
> +#define CL_YV12_IMG 0x40D1
> +
> +/******************************************
> + * cl_img_cached_allocations extension *
> + ******************************************/
> +
> +/* Flag values used by clCreteBuffer */
> +#define CL_MEM_USE_UNCACHED_CPU_MEMORY_IMG (1 << 26)
> +#define CL_MEM_USE_CACHED_CPU_MEMORY_IMG (1 << 27)
> +
> +/******************************************
> + * cl_img_use_gralloc_ptr extension *
> + ******************************************/
> +
> +/* Flag values used by clCreteBuffer */
> +#define CL_MEM_USE_GRALLOC_PTR_IMG (1 << 28)
> +
> +/* To be used by clGetEventInfo: */
> +#define CL_COMMAND_ACQUIRE_GRALLOC_OBJECTS_IMG 0x40D2
> +#define CL_COMMAND_RELEASE_GRALLOC_OBJECTS_IMG 0x40D3
> +
> +/* Error code from clEnqueueReleaseGrallocObjectsIMG */
> +#define CL_GRALLOC_RESOURCE_NOT_ACQUIRED_IMG 0x40D4
> +
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clEnqueueAcquireGrallocObjectsIMG(cl_command_queue /* command_queue */,
> + cl_uint /* num_objects */,
> + const cl_mem * /* mem_objects */,
> + cl_uint /* num_events_in_wait_list */,
> + const cl_event * /* event_wait_list */,
> + cl_event * /* event */) CL_EXT_SUFFIX__VERSION_1_2;
> +
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clEnqueueReleaseGrallocObjectsIMG(cl_command_queue /* command_queue */,
> + cl_uint /* num_objects */,
> + const cl_mem * /* mem_objects */,
> + cl_uint /* num_events_in_wait_list */,
> + const cl_event * /* event_wait_list */,
> + cl_event * /* event */) CL_EXT_SUFFIX__VERSION_1_2;
> +
> +#endif /* CL_VERSION_1_2 */
> +
> +#ifdef CL_VERSION_2_0
> +/*********************************
> +* cl_khr_subgroups extension
> +*********************************/
> +#define cl_khr_subgroups 1
> +
> +/* cl_kernel_sub_group_info is declared in CL.h. */
> +
> +/* cl_kernel_sub_group_info */
> +#define CL_KERNEL_MAX_SUB_GROUP_SIZE_FOR_NDRANGE_KHR 0x2033
> +#define CL_KERNEL_SUB_GROUP_COUNT_FOR_NDRANGE_KHR 0x2034
> +
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clGetKernelSubGroupInfoKHR(cl_kernel /* in_kernel */,
> + cl_device_id /*in_device*/,
> + cl_kernel_sub_group_info /* param_name */,
> + size_t /*input_value_size*/,
> + const void * /*input_value*/,
> + size_t /*param_value_size*/,
> + void* /*param_value*/,
> + size_t* /*param_value_size_ret*/ ) CL_EXT_SUFFIX__VERSION_2_0_DEPRECATED;
> +
> +typedef CL_API_ENTRY cl_int
> + ( CL_API_CALL * clGetKernelSubGroupInfoKHR_fn)(cl_kernel /* in_kernel */,
> + cl_device_id /*in_device*/,
> + cl_kernel_sub_group_info /* param_name */,
> + size_t /*input_value_size*/,
> + const void * /*input_value*/,
> + size_t /*param_value_size*/,
> + void* /*param_value*/,
> + size_t* /*param_value_size_ret*/ ) CL_EXT_SUFFIX__VERSION_2_0_DEPRECATED;
> +#endif /* CL_VERSION_2_0 */
> +
> +#ifdef CL_VERSION_2_1
> +/*********************************
> +* cl_khr_priority_hints extension
> +*********************************/
> +#define cl_khr_priority_hints 1
> +
> +typedef cl_uint cl_queue_priority_khr;
> +
> +/* cl_command_queue_properties */
> +#define CL_QUEUE_PRIORITY_KHR 0x1096
> +
> +/* cl_queue_priority_khr */
> +#define CL_QUEUE_PRIORITY_HIGH_KHR (1<<0)
> +#define CL_QUEUE_PRIORITY_MED_KHR (1<<1)
> +#define CL_QUEUE_PRIORITY_LOW_KHR (1<<2)
> +
> +#endif /* CL_VERSION_2_1 */
> +
> +#ifdef CL_VERSION_2_1
> +/*********************************
> +* cl_khr_throttle_hints extension
> +*********************************/
> +#define cl_khr_throttle_hints 1
> +
> +typedef cl_uint cl_queue_throttle_khr;
> +
> +/* cl_command_queue_properties */
> +#define CL_QUEUE_THROTTLE_KHR 0x1097
> +
> +/* cl_queue_throttle_khr */
> +#define CL_QUEUE_THROTTLE_HIGH_KHR (1<<0)
> +#define CL_QUEUE_THROTTLE_MED_KHR (1<<1)
> +#define CL_QUEUE_THROTTLE_LOW_KHR (1<<2)
> +
> +#endif /* CL_VERSION_2_1 */
> +
> +#ifdef CL_VERSION_2_2
> +/*********************************
> +* cl_khr_subgroup_named_barrier
> +*********************************/
> +#define cl_khr_subgroup_named_barrier 1
> +
> +/* cl_device_info */
> +#define CL_DEVICE_MAX_NAMED_BARRIER_COUNT_KHR 0x2035
> +
> +#endif /* CL_VERSION_2_2 */
> +
> +/**********************************
> + * cl_arm_import_memory extension *
> + **********************************/
> +
> +#ifdef CL_VERSION_1_0
> +
> +typedef intptr_t cl_import_properties_arm;
> +
> +/* Default and valid proporties name for cl_arm_import_memory */
> +#define CL_IMPORT_TYPE_ARM 0x40B2
> +
> +/* Host process memory type default value for CL_IMPORT_TYPE_ARM property */
> +#define CL_IMPORT_TYPE_HOST_ARM 0x40B3
> +
> +/* DMA BUF memory type value for CL_IMPORT_TYPE_ARM property */
> +#define CL_IMPORT_TYPE_DMA_BUF_ARM 0x40B4
> +
> +/* Secure DMA BUF memory type value for CL_IMPORT_TYPE_ARM property */
> +#define CL_IMPORT_TYPE_SECURE_ARM 0x40B5
> +
> +/* This extension adds a new function that allows for direct memory import into
> + * OpenCL via the clImportMemoryARM function.
> + *
> + * Memory imported through this interface will be mapped into the device's page
> + * tables directly, providing zero copy access. It will never fall back to copy
> + * operations and aliased buffers.
> + *
> + * Types of memory supported for import are specified as additional extension
> + * strings.
> + *
> + * This extension produces cl_mem allocations which are compatible with all other
> + * users of cl_mem in the standard API.
> + *
> + * This extension maps pages with the same properties as the normal buffer creation
> + * function clCreateBuffer.
> + */
> +extern CL_API_ENTRY cl_mem CL_API_CALL
> +clImportMemoryARM( cl_context context,
> + cl_mem_flags flags,
> + const cl_import_properties_arm *properties,
> + void *memory,
> + size_t size,
> + cl_int *errcode_ret) CL_EXT_SUFFIX__VERSION_1_0;
> +
> +
> +#endif /* CL_VERSION_1_0 */
> +
> +/******************************************
> + * cl_arm_shared_virtual_memory extension *
> + ******************************************/
> +
> +#ifdef CL_VERSION_1_2
> +
> +/* Used by clGetDeviceInfo */
> +#define CL_DEVICE_SVM_CAPABILITIES_ARM 0x40B6
> +
> +/* Used by clGetMemObjectInfo */
> +#define CL_MEM_USES_SVM_POINTER_ARM 0x40B7
> +
> +/* Used by clSetKernelExecInfoARM: */
> +#define CL_KERNEL_EXEC_INFO_SVM_PTRS_ARM 0x40B8
> +#define CL_KERNEL_EXEC_INFO_SVM_FINE_GRAIN_SYSTEM_ARM 0x40B9
> +
> +/* To be used by clGetEventInfo: */
> +#define CL_COMMAND_SVM_FREE_ARM 0x40BA
> +#define CL_COMMAND_SVM_MEMCPY_ARM 0x40BB
> +#define CL_COMMAND_SVM_MEMFILL_ARM 0x40BC
> +#define CL_COMMAND_SVM_MAP_ARM 0x40BD
> +#define CL_COMMAND_SVM_UNMAP_ARM 0x40BE
> +
> +/* Flag values returned by clGetDeviceInfo with CL_DEVICE_SVM_CAPABILITIES_ARM as the param_name. */
> +#define CL_DEVICE_SVM_COARSE_GRAIN_BUFFER_ARM (1 << 0)
> +#define CL_DEVICE_SVM_FINE_GRAIN_BUFFER_ARM (1 << 1)
> +#define CL_DEVICE_SVM_FINE_GRAIN_SYSTEM_ARM (1 << 2)
> +#define CL_DEVICE_SVM_ATOMICS_ARM (1 << 3)
> +
> +/* Flag values used by clSVMAllocARM: */
> +#define CL_MEM_SVM_FINE_GRAIN_BUFFER_ARM (1 << 10)
> +#define CL_MEM_SVM_ATOMICS_ARM (1 << 11)
> +
> +typedef cl_bitfield cl_svm_mem_flags_arm;
> +typedef cl_uint cl_kernel_exec_info_arm;
> +typedef cl_bitfield cl_device_svm_capabilities_arm;
> +
> +extern CL_API_ENTRY void * CL_API_CALL
> +clSVMAllocARM(cl_context /* context */,
> + cl_svm_mem_flags_arm /* flags */,
> + size_t /* size */,
> + cl_uint /* alignment */) CL_EXT_SUFFIX__VERSION_1_2;
> +
> +extern CL_API_ENTRY void CL_API_CALL
> +clSVMFreeARM(cl_context /* context */,
> + void * /* svm_pointer */) CL_EXT_SUFFIX__VERSION_1_2;
> +
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clEnqueueSVMFreeARM(cl_command_queue /* command_queue */,
> + cl_uint /* num_svm_pointers */,
> + void *[] /* svm_pointers[] */,
> + void (CL_CALLBACK * /*pfn_free_func*/)(cl_command_queue /* queue */,
> + cl_uint /* num_svm_pointers */,
> + void *[] /* svm_pointers[] */,
> + void * /* user_data */),
> + void * /* user_data */,
> + cl_uint /* num_events_in_wait_list */,
> + const cl_event * /* event_wait_list */,
> + cl_event * /* event */) CL_EXT_SUFFIX__VERSION_1_2;
> +
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clEnqueueSVMMemcpyARM(cl_command_queue /* command_queue */,
> + cl_bool /* blocking_copy */,
> + void * /* dst_ptr */,
> + const void * /* src_ptr */,
> + size_t /* size */,
> + cl_uint /* num_events_in_wait_list */,
> + const cl_event * /* event_wait_list */,
> + cl_event * /* event */) CL_EXT_SUFFIX__VERSION_1_2;
> +
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clEnqueueSVMMemFillARM(cl_command_queue /* command_queue */,
> + void * /* svm_ptr */,
> + const void * /* pattern */,
> + size_t /* pattern_size */,
> + size_t /* size */,
> + cl_uint /* num_events_in_wait_list */,
> + const cl_event * /* event_wait_list */,
> + cl_event * /* event */) CL_EXT_SUFFIX__VERSION_1_2;
> +
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clEnqueueSVMMapARM(cl_command_queue /* command_queue */,
> + cl_bool /* blocking_map */,
> + cl_map_flags /* flags */,
> + void * /* svm_ptr */,
> + size_t /* size */,
> + cl_uint /* num_events_in_wait_list */,
> + const cl_event * /* event_wait_list */,
> + cl_event * /* event */) CL_EXT_SUFFIX__VERSION_1_2;
> +
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clEnqueueSVMUnmapARM(cl_command_queue /* command_queue */,
> + void * /* svm_ptr */,
> + cl_uint /* num_events_in_wait_list */,
> + const cl_event * /* event_wait_list */,
> + cl_event * /* event */) CL_EXT_SUFFIX__VERSION_1_2;
> +
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clSetKernelArgSVMPointerARM(cl_kernel /* kernel */,
> + cl_uint /* arg_index */,
> + const void * /* arg_value */) CL_EXT_SUFFIX__VERSION_1_2;
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clSetKernelExecInfoARM(cl_kernel /* kernel */,
> + cl_kernel_exec_info_arm /* param_name */,
> + size_t /* param_value_size */,
> + const void * /* param_value */) CL_EXT_SUFFIX__VERSION_1_2;
> +
> +#endif /* CL_VERSION_1_2 */
> +
> #ifdef __cplusplus
> }
> #endif
> diff --git a/include/CL/cl_ext_intel.h b/include/CL/cl_ext_intel.h
> new file mode 100644
> index 0000000000..1c358cfc10
> --- /dev/null
> +++ b/include/CL/cl_ext_intel.h
> @@ -0,0 +1,429 @@
> +/*******************************************************************************
> + * Copyright (c) 2008-2017 The Khronos Group Inc.
> + *
> + * Permission is hereby granted, free of charge, to any person obtaining a
> + * copy of this software and/or associated documentation files (the
> + * "Materials"), to deal in the Materials without restriction, including
> + * without limitation the rights to use, copy, modify, merge, publish,
> + * distribute, sublicense, and/or sell copies of the Materials, and to
> + * permit persons to whom the Materials are furnished to do so, subject to
> + * the following conditions:
> + *
> + * The above copyright notice and this permission notice shall be included
> + * in all copies or substantial portions of the Materials.
> + *
> + * MODIFICATIONS TO THIS FILE MAY MEAN IT NO LONGER ACCURATELY REFLECTS
> + * KHRONOS STANDARDS. THE UNMODIFIED, NORMATIVE VERSIONS OF KHRONOS
> + * SPECIFICATIONS AND HEADER INFORMATION ARE LOCATED AT
> + * https://www.khronos.org/registry/
> + *
> + * THE MATERIALS ARE PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND,
> + * EXPRESS OR IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF
> + * MERCHANTABILITY, FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT.
> + * IN NO EVENT SHALL THE AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY
> + * CLAIM, DAMAGES OR OTHER LIABILITY, WHETHER IN AN ACTION OF CONTRACT,
> + * TORT OR OTHERWISE, ARISING FROM, OUT OF OR IN CONNECTION WITH THE
> + * MATERIALS OR THE USE OR OTHER DEALINGS IN THE MATERIALS.
> + ******************************************************************************/
> +/*****************************************************************************\
> +
> +Copyright (c) 2013-2017 Intel Corporation All Rights Reserved.
> +
> +THESE MATERIALS ARE PROVIDED BY THE COPYRIGHT HOLDERS AND CONTRIBUTORS
> +"AS IS" AND ANY EXPRESS OR IMPLIED WARRANTIES, INCLUDING, BUT NOT
> +LIMITED TO, THE IMPLIED WARRANTIES OF MERCHANTABILITY AND FITNESS FOR
> +A PARTICULAR PURPOSE ARE DISCLAIMED. IN NO EVENT SHALL INTEL OR ITS
> +CONTRIBUTORS BE LIABLE FOR ANY DIRECT, INDIRECT, INCIDENTAL, SPECIAL,
> +EXEMPLARY, OR CONSEQUENTIAL DAMAGES (INCLUDING, BUT NOT LIMITED TO,
> +PROCUREMENT OF SUBSTITUTE GOODS OR SERVICES; LOSS OF USE, DATA, OR
> +PROFITS; OR BUSINESS INTERRUPTION) HOWEVER CAUSED AND ON ANY THEORY
> +OF LIABILITY, WHETHER IN CONTRACT, STRICT LIABILITY OR TORT (INCLUDING
> +NEGLIGENCE OR OTHERWISE) ARISING IN ANY WAY OUT OF THE USE OF THESE
> +MATERIALS, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE.
> +
> +File Name: cl_ext_intel.h
> +
> +Abstract:
> +
> +Notes:
> +
> +\*****************************************************************************/
> +
> +#ifndef __CL_EXT_INTEL_H
> +#define __CL_EXT_INTEL_H
> +
> +#ifdef __APPLE__
> + #include <OpenCL/cl.h>
> + #include <OpenCL/cl_platform.h>
> +#else
> + #include <CL/cl.h>
> + #include <CL/cl_platform.h>
> +#endif
> +
> +#ifdef __cplusplus
> +extern "C" {
> +#endif
> +
> +/***************************************
> +* cl_intel_thread_local_exec extension *
> +****************************************/
> +
> +#define cl_intel_thread_local_exec 1
> +
> +#define CL_QUEUE_THREAD_LOCAL_EXEC_ENABLE_INTEL (((cl_bitfield)1) << 31)
> +
> +/***********************************************
> +* cl_intel_device_partition_by_names extension *
> +************************************************/
> +
> +#define cl_intel_device_partition_by_names 1
> +
> +#define CL_DEVICE_PARTITION_BY_NAMES_INTEL 0x4052
> +#define CL_PARTITION_BY_NAMES_LIST_END_INTEL -1
> +
> +/************************************************
> +* cl_intel_accelerator extension *
> +* cl_intel_motion_estimation extension *
> +* cl_intel_advanced_motion_estimation extension *
> +*************************************************/
> +
> +#define cl_intel_accelerator 1
> +#define cl_intel_motion_estimation 1
> +#define cl_intel_advanced_motion_estimation 1
> +
> +typedef struct _cl_accelerator_intel* cl_accelerator_intel;
> +typedef cl_uint cl_accelerator_type_intel;
> +typedef cl_uint cl_accelerator_info_intel;
> +
> +typedef struct _cl_motion_estimation_desc_intel {
> + cl_uint mb_block_type;
> + cl_uint subpixel_mode;
> + cl_uint sad_adjust_mode;
> + cl_uint search_path_type;
> +} cl_motion_estimation_desc_intel;
> +
> +/* error codes */
> +#define CL_INVALID_ACCELERATOR_INTEL -1094
> +#define CL_INVALID_ACCELERATOR_TYPE_INTEL -1095
> +#define CL_INVALID_ACCELERATOR_DESCRIPTOR_INTEL -1096
> +#define CL_ACCELERATOR_TYPE_NOT_SUPPORTED_INTEL -1097
> +
> +/* cl_accelerator_type_intel */
> +#define CL_ACCELERATOR_TYPE_MOTION_ESTIMATION_INTEL 0x0
> +
> +/* cl_accelerator_info_intel */
> +#define CL_ACCELERATOR_DESCRIPTOR_INTEL 0x4090
> +#define CL_ACCELERATOR_REFERENCE_COUNT_INTEL 0x4091
> +#define CL_ACCELERATOR_CONTEXT_INTEL 0x4092
> +#define CL_ACCELERATOR_TYPE_INTEL 0x4093
> +
> +/* cl_motion_detect_desc_intel flags */
> +#define CL_ME_MB_TYPE_16x16_INTEL 0x0
> +#define CL_ME_MB_TYPE_8x8_INTEL 0x1
> +#define CL_ME_MB_TYPE_4x4_INTEL 0x2
> +
> +#define CL_ME_SUBPIXEL_MODE_INTEGER_INTEL 0x0
> +#define CL_ME_SUBPIXEL_MODE_HPEL_INTEL 0x1
> +#define CL_ME_SUBPIXEL_MODE_QPEL_INTEL 0x2
> +
> +#define CL_ME_SAD_ADJUST_MODE_NONE_INTEL 0x0
> +#define CL_ME_SAD_ADJUST_MODE_HAAR_INTEL 0x1
> +
> +#define CL_ME_SEARCH_PATH_RADIUS_2_2_INTEL 0x0
> +#define CL_ME_SEARCH_PATH_RADIUS_4_4_INTEL 0x1
> +#define CL_ME_SEARCH_PATH_RADIUS_16_12_INTEL 0x5
> +
> +#define CL_ME_SKIP_BLOCK_TYPE_16x16_INTEL 0x0
> +#define CL_ME_CHROMA_INTRA_PREDICT_ENABLED_INTEL 0x1
> +#define CL_ME_LUMA_INTRA_PREDICT_ENABLED_INTEL 0x2
> +#define CL_ME_SKIP_BLOCK_TYPE_8x8_INTEL 0x4
> +
> +#define CL_ME_FORWARD_INPUT_MODE_INTEL 0x1
> +#define CL_ME_BACKWARD_INPUT_MODE_INTEL 0x2
> +#define CL_ME_BIDIRECTION_INPUT_MODE_INTEL 0x3
> +
> +#define CL_ME_BIDIR_WEIGHT_QUARTER_INTEL 16
> +#define CL_ME_BIDIR_WEIGHT_THIRD_INTEL 21
> +#define CL_ME_BIDIR_WEIGHT_HALF_INTEL 32
> +#define CL_ME_BIDIR_WEIGHT_TWO_THIRD_INTEL 43
> +#define CL_ME_BIDIR_WEIGHT_THREE_QUARTER_INTEL 48
> +
> +#define CL_ME_COST_PENALTY_NONE_INTEL 0x0
> +#define CL_ME_COST_PENALTY_LOW_INTEL 0x1
> +#define CL_ME_COST_PENALTY_NORMAL_INTEL 0x2
> +#define CL_ME_COST_PENALTY_HIGH_INTEL 0x3
> +
> +#define CL_ME_COST_PRECISION_QPEL_INTEL 0x0
> +#define CL_ME_COST_PRECISION_HPEL_INTEL 0x1
> +#define CL_ME_COST_PRECISION_PEL_INTEL 0x2
> +#define CL_ME_COST_PRECISION_DPEL_INTEL 0x3
> +
> +#define CL_ME_LUMA_PREDICTOR_MODE_VERTICAL_INTEL 0x0
> +#define CL_ME_LUMA_PREDICTOR_MODE_HORIZONTAL_INTEL 0x1
> +#define CL_ME_LUMA_PREDICTOR_MODE_DC_INTEL 0x2
> +#define CL_ME_LUMA_PREDICTOR_MODE_DIAGONAL_DOWN_LEFT_INTEL 0x3
> +
> +#define CL_ME_LUMA_PREDICTOR_MODE_DIAGONAL_DOWN_RIGHT_INTEL 0x4
> +#define CL_ME_LUMA_PREDICTOR_MODE_PLANE_INTEL 0x4
> +#define CL_ME_LUMA_PREDICTOR_MODE_VERTICAL_RIGHT_INTEL 0x5
> +#define CL_ME_LUMA_PREDICTOR_MODE_HORIZONTAL_DOWN_INTEL 0x6
> +#define CL_ME_LUMA_PREDICTOR_MODE_VERTICAL_LEFT_INTEL 0x7
> +#define CL_ME_LUMA_PREDICTOR_MODE_HORIZONTAL_UP_INTEL 0x8
> +
> +#define CL_ME_CHROMA_PREDICTOR_MODE_DC_INTEL 0x0
> +#define CL_ME_CHROMA_PREDICTOR_MODE_HORIZONTAL_INTEL 0x1
> +#define CL_ME_CHROMA_PREDICTOR_MODE_VERTICAL_INTEL 0x2
> +#define CL_ME_CHROMA_PREDICTOR_MODE_PLANE_INTEL 0x3
> +
> +/* cl_device_info */
> +#define CL_DEVICE_ME_VERSION_INTEL 0x407E
> +
> +#define CL_ME_VERSION_LEGACY_INTEL 0x0
> +#define CL_ME_VERSION_ADVANCED_VER_1_INTEL 0x1
> +#define CL_ME_VERSION_ADVANCED_VER_2_INTEL 0x2
> +
> +extern CL_API_ENTRY cl_accelerator_intel CL_API_CALL
> +clCreateAcceleratorINTEL(
> + cl_context /* context */,
> + cl_accelerator_type_intel /* accelerator_type */,
> + size_t /* descriptor_size */,
> + const void* /* descriptor */,
> + cl_int* /* errcode_ret */) CL_EXT_SUFFIX__VERSION_1_2;
> +
> +typedef CL_API_ENTRY cl_accelerator_intel (CL_API_CALL *clCreateAcceleratorINTEL_fn)(
> + cl_context /* context */,
> + cl_accelerator_type_intel /* accelerator_type */,
> + size_t /* descriptor_size */,
> + const void* /* descriptor */,
> + cl_int* /* errcode_ret */) CL_EXT_SUFFIX__VERSION_1_2;
> +
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clGetAcceleratorInfoINTEL(
> + cl_accelerator_intel /* accelerator */,
> + cl_accelerator_info_intel /* param_name */,
> + size_t /* param_value_size */,
> + void* /* param_value */,
> + size_t* /* param_value_size_ret */) CL_EXT_SUFFIX__VERSION_1_2;
> +
> +typedef CL_API_ENTRY cl_int (CL_API_CALL *clGetAcceleratorInfoINTEL_fn)(
> + cl_accelerator_intel /* accelerator */,
> + cl_accelerator_info_intel /* param_name */,
> + size_t /* param_value_size */,
> + void* /* param_value */,
> + size_t* /* param_value_size_ret */) CL_EXT_SUFFIX__VERSION_1_2;
> +
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clRetainAcceleratorINTEL(
> + cl_accelerator_intel /* accelerator */) CL_EXT_SUFFIX__VERSION_1_2;
> +
> +typedef CL_API_ENTRY cl_int (CL_API_CALL *clRetainAcceleratorINTEL_fn)(
> + cl_accelerator_intel /* accelerator */) CL_EXT_SUFFIX__VERSION_1_2;
> +
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clReleaseAcceleratorINTEL(
> + cl_accelerator_intel /* accelerator */) CL_EXT_SUFFIX__VERSION_1_2;
> +
> +typedef CL_API_ENTRY cl_int (CL_API_CALL *clReleaseAcceleratorINTEL_fn)(
> + cl_accelerator_intel /* accelerator */) CL_EXT_SUFFIX__VERSION_1_2;
> +
> +/******************************************
> +* cl_intel_simultaneous_sharing extension *
> +*******************************************/
> +
> +#define cl_intel_simultaneous_sharing 1
> +
> +#define CL_DEVICE_SIMULTANEOUS_INTEROPS_INTEL 0x4104
> +#define CL_DEVICE_NUM_SIMULTANEOUS_INTEROPS_INTEL 0x4105
> +
> +/***********************************
> +* cl_intel_egl_image_yuv extension *
> +************************************/
> +
> +#define cl_intel_egl_image_yuv 1
> +
> +#define CL_EGL_YUV_PLANE_INTEL 0x4107
> +
> +/********************************
> +* cl_intel_packed_yuv extension *
> +*********************************/
> +
> +#define cl_intel_packed_yuv 1
> +
> +#define CL_YUYV_INTEL 0x4076
> +#define CL_UYVY_INTEL 0x4077
> +#define CL_YVYU_INTEL 0x4078
> +#define CL_VYUY_INTEL 0x4079
> +
> +/********************************************
> +* cl_intel_required_subgroup_size extension *
> +*********************************************/
> +
> +#define cl_intel_required_subgroup_size 1
> +
> +#define CL_DEVICE_SUB_GROUP_SIZES_INTEL 0x4108
> +#define CL_KERNEL_SPILL_MEM_SIZE_INTEL 0x4109
> +#define CL_KERNEL_COMPILE_SUB_GROUP_SIZE_INTEL 0x410A
> +
> +/****************************************
> +* cl_intel_driver_diagnostics extension *
> +*****************************************/
> +
> +#define cl_intel_driver_diagnostics 1
> +
> +typedef cl_uint cl_diagnostics_verbose_level;
> +
> +#define CL_CONTEXT_SHOW_DIAGNOSTICS_INTEL 0x4106
> +
> +#define CL_CONTEXT_DIAGNOSTICS_LEVEL_ALL_INTEL ( 0xff )
> +#define CL_CONTEXT_DIAGNOSTICS_LEVEL_GOOD_INTEL ( 1 )
> +#define CL_CONTEXT_DIAGNOSTICS_LEVEL_BAD_INTEL ( 1 << 1 )
> +#define CL_CONTEXT_DIAGNOSTICS_LEVEL_NEUTRAL_INTEL ( 1 << 2 )
> +
> +/********************************
> +* cl_intel_planar_yuv extension *
> +*********************************/
> +
> +#define CL_NV12_INTEL 0x410E
> +
> +#define CL_MEM_NO_ACCESS_INTEL ( 1 << 24 )
> +#define CL_MEM_ACCESS_FLAGS_UNRESTRICTED_INTEL ( 1 << 25 )
> +
> +#define CL_DEVICE_PLANAR_YUV_MAX_WIDTH_INTEL 0x417E
> +#define CL_DEVICE_PLANAR_YUV_MAX_HEIGHT_INTEL 0x417F
> +
> +/*******************************************************
> +* cl_intel_device_side_avc_motion_estimation extension *
> +********************************************************/
> +
> +#define CL_DEVICE_AVC_ME_VERSION_INTEL 0x410B
> +#define CL_DEVICE_AVC_ME_SUPPORTS_TEXTURE_SAMPLER_USE_INTEL 0x410C
> +#define CL_DEVICE_AVC_ME_SUPPORTS_PREEMPTION_INTEL 0x410D
> +
> +#define CL_AVC_ME_VERSION_0_INTEL 0x0; // No support.
> +#define CL_AVC_ME_VERSION_1_INTEL 0x1; // First supported version.
> +
> +#define CL_AVC_ME_MAJOR_16x16_INTEL 0x0
> +#define CL_AVC_ME_MAJOR_16x8_INTEL 0x1
> +#define CL_AVC_ME_MAJOR_8x16_INTEL 0x2
> +#define CL_AVC_ME_MAJOR_8x8_INTEL 0x3
> +
> +#define CL_AVC_ME_MINOR_8x8_INTEL 0x0
> +#define CL_AVC_ME_MINOR_8x4_INTEL 0x1
> +#define CL_AVC_ME_MINOR_4x8_INTEL 0x2
> +#define CL_AVC_ME_MINOR_4x4_INTEL 0x3
> +
> +#define CL_AVC_ME_MAJOR_FORWARD_INTEL 0x0
> +#define CL_AVC_ME_MAJOR_BACKWARD_INTEL 0x1
> +#define CL_AVC_ME_MAJOR_BIDIRECTIONAL_INTEL 0x2
> +
> +#define CL_AVC_ME_PARTITION_MASK_ALL_INTEL 0x0
> +#define CL_AVC_ME_PARTITION_MASK_16x16_INTEL 0x7E
> +#define CL_AVC_ME_PARTITION_MASK_16x8_INTEL 0x7D
> +#define CL_AVC_ME_PARTITION_MASK_8x16_INTEL 0x7B
> +#define CL_AVC_ME_PARTITION_MASK_8x8_INTEL 0x77
> +#define CL_AVC_ME_PARTITION_MASK_8x4_INTEL 0x6F
> +#define CL_AVC_ME_PARTITION_MASK_4x8_INTEL 0x5F
> +#define CL_AVC_ME_PARTITION_MASK_4x4_INTEL 0x3F
> +
> +#define CL_AVC_ME_SEARCH_WINDOW_EXHAUSTIVE_INTEL 0x0
> +#define CL_AVC_ME_SEARCH_WINDOW_SMALL_INTEL 0x1
> +#define CL_AVC_ME_SEARCH_WINDOW_TINY_INTEL 0x2
> +#define CL_AVC_ME_SEARCH_WINDOW_EXTRA_TINY_INTEL 0x3
> +#define CL_AVC_ME_SEARCH_WINDOW_DIAMOND_INTEL 0x4
> +#define CL_AVC_ME_SEARCH_WINDOW_LARGE_DIAMOND_INTEL 0x5
> +#define CL_AVC_ME_SEARCH_WINDOW_RESERVED0_INTEL 0x6
> +#define CL_AVC_ME_SEARCH_WINDOW_RESERVED1_INTEL 0x7
> +#define CL_AVC_ME_SEARCH_WINDOW_CUSTOM_INTEL 0x8
> +#define CL_AVC_ME_SEARCH_WINDOW_16x12_RADIUS_INTEL 0x9
> +#define CL_AVC_ME_SEARCH_WINDOW_4x4_RADIUS_INTEL 0x2
> +#define CL_AVC_ME_SEARCH_WINDOW_2x2_RADIUS_INTEL 0xa
> +
> +#define CL_AVC_ME_SAD_ADJUST_MODE_NONE_INTEL 0x0
> +#define CL_AVC_ME_SAD_ADJUST_MODE_HAAR_INTEL 0x2
> +
> +#define CL_AVC_ME_SUBPIXEL_MODE_INTEGER_INTEL 0x0
> +#define CL_AVC_ME_SUBPIXEL_MODE_HPEL_INTEL 0x1
> +#define CL_AVC_ME_SUBPIXEL_MODE_QPEL_INTEL 0x3
> +
> +#define CL_AVC_ME_COST_PRECISION_QPEL_INTEL 0x0
> +#define CL_AVC_ME_COST_PRECISION_HPEL_INTEL 0x1
> +#define CL_AVC_ME_COST_PRECISION_PEL_INTEL 0x2
> +#define CL_AVC_ME_COST_PRECISION_DPEL_INTEL 0x3
> +
> +#define CL_AVC_ME_BIDIR_WEIGHT_QUARTER_INTEL 0x10
> +#define CL_AVC_ME_BIDIR_WEIGHT_THIRD_INTEL 0x15
> +#define CL_AVC_ME_BIDIR_WEIGHT_HALF_INTEL 0x20
> +#define CL_AVC_ME_BIDIR_WEIGHT_TWO_THIRD_INTEL 0x2B
> +#define CL_AVC_ME_BIDIR_WEIGHT_THREE_QUARTER_INTEL 0x30
> +
> +#define CL_AVC_ME_BORDER_REACHED_LEFT_INTEL 0x0
> +#define CL_AVC_ME_BORDER_REACHED_RIGHT_INTEL 0x2
> +#define CL_AVC_ME_BORDER_REACHED_TOP_INTEL 0x4
> +#define CL_AVC_ME_BORDER_REACHED_BOTTOM_INTEL 0x8
> +
> +#define CL_AVC_ME_SKIP_BLOCK_PARTITION_16x16_INTEL 0x0
> +#define CL_AVC_ME_SKIP_BLOCK_PARTITION_8x8_INTEL 0x4000
> +
> +#define CL_AVC_ME_SKIP_BLOCK_16x16_FORWARD_ENABLE_INTEL ( 0x1 << 24 )
> +#define CL_AVC_ME_SKIP_BLOCK_16x16_BACKWARD_ENABLE_INTEL ( 0x2 << 24 )
> +#define CL_AVC_ME_SKIP_BLOCK_16x16_DUAL_ENABLE_INTEL ( 0x3 << 24 )
> +#define CL_AVC_ME_SKIP_BLOCK_8x8_FORWARD_ENABLE_INTEL ( 0x55 << 24 )
> +#define CL_AVC_ME_SKIP_BLOCK_8x8_BACKWARD_ENABLE_INTEL ( 0xAA << 24 )
> +#define CL_AVC_ME_SKIP_BLOCK_8x8_DUAL_ENABLE_INTEL ( 0xFF << 24 )
> +#define CL_AVC_ME_SKIP_BLOCK_8x8_0_FORWARD_ENABLE_INTEL ( 0x1 << 24 )
> +#define CL_AVC_ME_SKIP_BLOCK_8x8_0_BACKWARD_ENABLE_INTEL ( 0x2 << 24 )
> +#define CL_AVC_ME_SKIP_BLOCK_8x8_1_FORWARD_ENABLE_INTEL ( 0x1 << 26 )
> +#define CL_AVC_ME_SKIP_BLOCK_8x8_1_BACKWARD_ENABLE_INTEL ( 0x2 << 26 )
> +#define CL_AVC_ME_SKIP_BLOCK_8x8_2_FORWARD_ENABLE_INTEL ( 0x1 << 28 )
> +#define CL_AVC_ME_SKIP_BLOCK_8x8_2_BACKWARD_ENABLE_INTEL ( 0x2 << 28 )
> +#define CL_AVC_ME_SKIP_BLOCK_8x8_3_FORWARD_ENABLE_INTEL ( 0x1 << 30 )
> +#define CL_AVC_ME_SKIP_BLOCK_8x8_3_BACKWARD_ENABLE_INTEL ( 0x2 << 30 )
> +
> +#define CL_AVC_ME_BLOCK_BASED_SKIP_4x4_INTEL 0x00
> +#define CL_AVC_ME_BLOCK_BASED_SKIP_8x8_INTEL 0x80
> +
> +#define CL_AVC_ME_INTRA_16x16_INTEL 0x0
> +#define CL_AVC_ME_INTRA_8x8_INTEL 0x1
> +#define CL_AVC_ME_INTRA_4x4_INTEL 0x2
> +
> +#define CL_AVC_ME_INTRA_LUMA_PARTITION_MASK_16x16_INTEL 0x6
> +#define CL_AVC_ME_INTRA_LUMA_PARTITION_MASK_8x8_INTEL 0x5
> +#define CL_AVC_ME_INTRA_LUMA_PARTITION_MASK_4x4_INTEL 0x3
> +
> +#define CL_AVC_ME_INTRA_NEIGHBOR_LEFT_MASK_ENABLE_INTEL 0x60
> +#define CL_AVC_ME_INTRA_NEIGHBOR_UPPER_MASK_ENABLE_INTEL 0x10
> +#define CL_AVC_ME_INTRA_NEIGHBOR_UPPER_RIGHT_MASK_ENABLE_INTEL 0x8
> +#define CL_AVC_ME_INTRA_NEIGHBOR_UPPER_LEFT_MASK_ENABLE_INTEL 0x4
> +
> +#define CL_AVC_ME_LUMA_PREDICTOR_MODE_VERTICAL_INTEL 0x0
> +#define CL_AVC_ME_LUMA_PREDICTOR_MODE_HORIZONTAL_INTEL 0x1
> +#define CL_AVC_ME_LUMA_PREDICTOR_MODE_DC_INTEL 0x2
> +#define CL_AVC_ME_LUMA_PREDICTOR_MODE_DIAGONAL_DOWN_LEFT_INTEL 0x3
> +#define CL_AVC_ME_LUMA_PREDICTOR_MODE_DIAGONAL_DOWN_RIGHT_INTEL 0x4
> +#define CL_AVC_ME_LUMA_PREDICTOR_MODE_PLANE_INTEL 0x4
> +#define CL_AVC_ME_LUMA_PREDICTOR_MODE_VERTICAL_RIGHT_INTEL 0x5
> +#define CL_AVC_ME_LUMA_PREDICTOR_MODE_HORIZONTAL_DOWN_INTEL 0x6
> +#define CL_AVC_ME_LUMA_PREDICTOR_MODE_VERTICAL_LEFT_INTEL 0x7
> +#define CL_AVC_ME_LUMA_PREDICTOR_MODE_HORIZONTAL_UP_INTEL 0x8
> +#define CL_AVC_ME_CHROMA_PREDICTOR_MODE_DC_INTEL 0x0
> +#define CL_AVC_ME_CHROMA_PREDICTOR_MODE_HORIZONTAL_INTEL 0x1
> +#define CL_AVC_ME_CHROMA_PREDICTOR_MODE_VERTICAL_INTEL 0x2
> +#define CL_AVC_ME_CHROMA_PREDICTOR_MODE_PLANE_INTEL 0x3
> +
> +#define CL_AVC_ME_FRAME_FORWARD_INTEL 0x1
> +#define CL_AVC_ME_FRAME_BACKWARD_INTEL 0x2
> +#define CL_AVC_ME_FRAME_DUAL_INTEL 0x3
> +
> +#define CL_AVC_ME_SLICE_TYPE_PRED_INTEL 0x0
> +#define CL_AVC_ME_SLICE_TYPE_BPRED_INTEL 0x1
> +#define CL_AVC_ME_SLICE_TYPE_INTRA_INTEL 0x2
> +
> +#define CL_AVC_ME_INTERLACED_SCAN_TOP_FIELD_INTEL 0x0
> +#define CL_AVC_ME_INTERLACED_SCAN_BOTTOM_FIELD_INTEL 0x1
> +
> +#ifdef __cplusplus
> +}
> +#endif
> +
> +#endif /* __CL_EXT_INTEL_H */
> +
> diff --git a/include/CL/cl_gl.h b/include/CL/cl_gl.h
> index e52c1b693d..945daa83d7 100644
> --- a/include/CL/cl_gl.h
> +++ b/include/CL/cl_gl.h
> @@ -1,5 +1,5 @@
> /**********************************************************************************
> - * Copyright (c) 2008 - 2012 The Khronos Group Inc.
> + * Copyright (c) 2008-2015 The Khronos Group Inc.
> *
> * Permission is hereby granted, free of charge, to any person obtaining a
> * copy of this software and/or associated documentation files (the
> @@ -12,6 +12,11 @@
> * The above copyright notice and this permission notice shall be included
> * in all copies or substantial portions of the Materials.
> *
> + * MODIFICATIONS TO THIS FILE MAY MEAN IT NO LONGER ACCURATELY REFLECTS
> + * KHRONOS STANDARDS. THE UNMODIFIED, NORMATIVE VERSIONS OF KHRONOS
> + * SPECIFICATIONS AND HEADER INFORMATION ARE LOCATED AT
> + * https://www.khronos.org/registry/
> + *
> * THE MATERIALS ARE PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND,
> * EXPRESS OR IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF
> * MERCHANTABILITY, FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT.
> diff --git a/include/CL/cl_gl_ext.h b/include/CL/cl_gl_ext.h
> index 77d53536f6..e3c14c6408 100644
> --- a/include/CL/cl_gl_ext.h
> +++ b/include/CL/cl_gl_ext.h
> @@ -1,5 +1,5 @@
> /**********************************************************************************
> - * Copyright (c) 2008-2012 The Khronos Group Inc.
> + * Copyright (c) 2008-2015 The Khronos Group Inc.
> *
> * Permission is hereby granted, free of charge, to any person obtaining a
> * copy of this software and/or associated documentation files (the
> @@ -12,6 +12,11 @@
> * The above copyright notice and this permission notice shall be included
> * in all copies or substantial portions of the Materials.
> *
> + * MODIFICATIONS TO THIS FILE MAY MEAN IT NO LONGER ACCURATELY REFLECTS
> + * KHRONOS STANDARDS. THE UNMODIFIED, NORMATIVE VERSIONS OF KHRONOS
> + * SPECIFICATIONS AND HEADER INFORMATION ARE LOCATED AT
> + * https://www.khronos.org/registry/
> + *
> * THE MATERIALS ARE PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND,
> * EXPRESS OR IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF
> * MERCHANTABILITY, FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT.
> diff --git a/include/CL/cl_platform.h b/include/CL/cl_platform.h
> index 7f6f5e8a74..15702d2f72 100644
> --- a/include/CL/cl_platform.h
> +++ b/include/CL/cl_platform.h
> @@ -1,5 +1,5 @@
> /**********************************************************************************
> - * Copyright (c) 2008-2012 The Khronos Group Inc.
> + * Copyright (c) 2008-2015 The Khronos Group Inc.
> *
> * Permission is hereby granted, free of charge, to any person obtaining a
> * copy of this software and/or associated documentation files (the
> @@ -12,6 +12,11 @@
> * The above copyright notice and this permission notice shall be included
> * in all copies or substantial portions of the Materials.
> *
> + * MODIFICATIONS TO THIS FILE MAY MEAN IT NO LONGER ACCURATELY REFLECTS
> + * KHRONOS STANDARDS. THE UNMODIFIED, NORMATIVE VERSIONS OF KHRONOS
> + * SPECIFICATIONS AND HEADER INFORMATION ARE LOCATED AT
> + * https://www.khronos.org/registry/
> + *
> * THE MATERIALS ARE PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND,
> * EXPRESS OR IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF
> * MERCHANTABILITY, FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT.
> @@ -45,6 +50,14 @@ extern "C" {
> #define CL_CALLBACK
> #endif
>
> +/*
> + * Deprecation flags refer to the last version of the header in which the
> + * feature was not deprecated.
> + *
> + * E.g. VERSION_1_1_DEPRECATED means the feature is present in 1.1 without
> + * deprecation but is deprecated in versions later than 1.1.
> + */
> +
> #ifdef __APPLE__
> #define CL_EXTENSION_WEAK_LINK __attribute__((weak_import))
> #define CL_API_SUFFIX__VERSION_1_0 AVAILABLE_MAC_OS_X_VERSION_10_6_AND_LATER
> @@ -75,6 +88,12 @@ extern "C" {
> #define CL_EXT_SUFFIX__VERSION_1_1
> #define CL_API_SUFFIX__VERSION_1_2
> #define CL_EXT_SUFFIX__VERSION_1_2
> + #define CL_API_SUFFIX__VERSION_2_0
> + #define CL_EXT_SUFFIX__VERSION_2_0
> + #define CL_API_SUFFIX__VERSION_2_1
> + #define CL_EXT_SUFFIX__VERSION_2_1
> + #define CL_API_SUFFIX__VERSION_2_2
> + #define CL_EXT_SUFFIX__VERSION_2_2
>
> #ifdef __GNUC__
> #ifdef CL_USE_DEPRECATED_OPENCL_1_0_APIS
> @@ -92,9 +111,33 @@ extern "C" {
> #define CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED __attribute__((deprecated))
> #define CL_EXT_PREFIX__VERSION_1_1_DEPRECATED
> #endif
> - #elif _WIN32
> +
> + #ifdef CL_USE_DEPRECATED_OPENCL_1_2_APIS
> + #define CL_EXT_SUFFIX__VERSION_1_2_DEPRECATED
> + #define CL_EXT_PREFIX__VERSION_1_2_DEPRECATED
> + #else
> + #define CL_EXT_SUFFIX__VERSION_1_2_DEPRECATED __attribute__((deprecated))
> + #define CL_EXT_PREFIX__VERSION_1_2_DEPRECATED
> + #endif
> +
> + #ifdef CL_USE_DEPRECATED_OPENCL_2_0_APIS
> + #define CL_EXT_SUFFIX__VERSION_2_0_DEPRECATED
> + #define CL_EXT_PREFIX__VERSION_2_0_DEPRECATED
> + #else
> + #define CL_EXT_SUFFIX__VERSION_2_0_DEPRECATED __attribute__((deprecated))
> + #define CL_EXT_PREFIX__VERSION_2_0_DEPRECATED
> + #endif
> +
> + #ifdef CL_USE_DEPRECATED_OPENCL_2_1_APIS
> + #define CL_EXT_SUFFIX__VERSION_2_1_DEPRECATED
> + #define CL_EXT_PREFIX__VERSION_2_1_DEPRECATED
> + #else
> + #define CL_EXT_SUFFIX__VERSION_2_1_DEPRECATED __attribute__((deprecated))
> + #define CL_EXT_PREFIX__VERSION_2_1_DEPRECATED
> + #endif
> + #elif defined(_WIN32)
> #ifdef CL_USE_DEPRECATED_OPENCL_1_0_APIS
> - #define CL_EXT_SUFFIX__VERSION_1_0_DEPRECATED
> + #define CL_EXT_SUFFIX__VERSION_1_0_DEPRECATED
> #define CL_EXT_PREFIX__VERSION_1_0_DEPRECATED
> #else
> #define CL_EXT_SUFFIX__VERSION_1_0_DEPRECATED
> @@ -108,12 +151,45 @@ extern "C" {
> #define CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED
> #define CL_EXT_PREFIX__VERSION_1_1_DEPRECATED __declspec(deprecated)
> #endif
> +
> + #ifdef CL_USE_DEPRECATED_OPENCL_1_2_APIS
> + #define CL_EXT_SUFFIX__VERSION_1_2_DEPRECATED
> + #define CL_EXT_PREFIX__VERSION_1_2_DEPRECATED
> + #else
> + #define CL_EXT_SUFFIX__VERSION_1_2_DEPRECATED
> + #define CL_EXT_PREFIX__VERSION_1_2_DEPRECATED __declspec(deprecated)
> + #endif
> +
> + #ifdef CL_USE_DEPRECATED_OPENCL_2_0_APIS
> + #define CL_EXT_SUFFIX__VERSION_2_0_DEPRECATED
> + #define CL_EXT_PREFIX__VERSION_2_0_DEPRECATED
> + #else
> + #define CL_EXT_SUFFIX__VERSION_2_0_DEPRECATED
> + #define CL_EXT_PREFIX__VERSION_2_0_DEPRECATED __declspec(deprecated)
> + #endif
> +
> + #ifdef CL_USE_DEPRECATED_OPENCL_2_1_APIS
> + #define CL_EXT_SUFFIX__VERSION_2_1_DEPRECATED
> + #define CL_EXT_PREFIX__VERSION_2_1_DEPRECATED
> + #else
> + #define CL_EXT_SUFFIX__VERSION_2_1_DEPRECATED
> + #define CL_EXT_PREFIX__VERSION_2_1_DEPRECATED __declspec(deprecated)
> + #endif
> #else
> #define CL_EXT_SUFFIX__VERSION_1_0_DEPRECATED
> #define CL_EXT_PREFIX__VERSION_1_0_DEPRECATED
>
> #define CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED
> #define CL_EXT_PREFIX__VERSION_1_1_DEPRECATED
> +
> + #define CL_EXT_SUFFIX__VERSION_1_2_DEPRECATED
> + #define CL_EXT_PREFIX__VERSION_1_2_DEPRECATED
> +
> + #define CL_EXT_SUFFIX__VERSION_2_0_DEPRECATED
> + #define CL_EXT_PREFIX__VERSION_2_0_DEPRECATED
> +
> + #define CL_EXT_SUFFIX__VERSION_2_1_DEPRECATED
> + #define CL_EXT_PREFIX__VERSION_2_1_DEPRECATED
> #endif
> #endif
>
> @@ -159,7 +235,18 @@ typedef double cl_double;
> #define CL_FLT_RADIX 2
> #define CL_FLT_MAX 340282346638528859811704183484516925440.0f
> #define CL_FLT_MIN 1.175494350822287507969e-38f
> -#define CL_FLT_EPSILON 0x1.0p-23f
> +#define CL_FLT_EPSILON 1.1920928955078125e-7f
> +
> +#define CL_HALF_DIG 3
> +#define CL_HALF_MANT_DIG 11
> +#define CL_HALF_MAX_10_EXP +4
> +#define CL_HALF_MAX_EXP +16
> +#define CL_HALF_MIN_10_EXP -4
> +#define CL_HALF_MIN_EXP -13
> +#define CL_HALF_RADIX 2
> +#define CL_HALF_MAX 65504.0f
> +#define CL_HALF_MIN 6.103515625e-05f
> +#define CL_HALF_EPSILON 9.765625e-04f
>
> #define CL_DBL_DIG 15
> #define CL_DBL_MANT_DIG 53
> @@ -168,37 +255,37 @@ typedef double cl_double;
> #define CL_DBL_MIN_10_EXP -307
> #define CL_DBL_MIN_EXP -1021
> #define CL_DBL_RADIX 2
> -#define CL_DBL_MAX 179769313486231570814527423731704356798070567525844996598917476803157260780028538760589558632766878171540458953514382464234321326889464182768467546703537516986049910576551282076245490090389328944075868508455133942304583236903222948165808559332123348274797826204144723168738177180919299881250404026184124858368.0
> +#define CL_DBL_MAX 1.7976931348623158e+308
> #define CL_DBL_MIN 2.225073858507201383090e-308
> #define CL_DBL_EPSILON 2.220446049250313080847e-16
>
> -#define CL_M_E 2.718281828459045090796
> -#define CL_M_LOG2E 1.442695040888963387005
> -#define CL_M_LOG10E 0.434294481903251816668
> -#define CL_M_LN2 0.693147180559945286227
> -#define CL_M_LN10 2.302585092994045901094
> -#define CL_M_PI 3.141592653589793115998
> -#define CL_M_PI_2 1.570796326794896557999
> -#define CL_M_PI_4 0.785398163397448278999
> -#define CL_M_1_PI 0.318309886183790691216
> -#define CL_M_2_PI 0.636619772367581382433
> -#define CL_M_2_SQRTPI 1.128379167095512558561
> -#define CL_M_SQRT2 1.414213562373095145475
> -#define CL_M_SQRT1_2 0.707106781186547572737
> -
> -#define CL_M_E_F 2.71828174591064f
> -#define CL_M_LOG2E_F 1.44269502162933f
> -#define CL_M_LOG10E_F 0.43429449200630f
> -#define CL_M_LN2_F 0.69314718246460f
> -#define CL_M_LN10_F 2.30258512496948f
> -#define CL_M_PI_F 3.14159274101257f
> -#define CL_M_PI_2_F 1.57079637050629f
> -#define CL_M_PI_4_F 0.78539818525314f
> -#define CL_M_1_PI_F 0.31830987334251f
> -#define CL_M_2_PI_F 0.63661974668503f
> -#define CL_M_2_SQRTPI_F 1.12837922573090f
> -#define CL_M_SQRT2_F 1.41421353816986f
> -#define CL_M_SQRT1_2_F 0.70710676908493f
> +#define CL_M_E 2.7182818284590452354
> +#define CL_M_LOG2E 1.4426950408889634074
> +#define CL_M_LOG10E 0.43429448190325182765
> +#define CL_M_LN2 0.69314718055994530942
> +#define CL_M_LN10 2.30258509299404568402
> +#define CL_M_PI 3.14159265358979323846
> +#define CL_M_PI_2 1.57079632679489661923
> +#define CL_M_PI_4 0.78539816339744830962
> +#define CL_M_1_PI 0.31830988618379067154
> +#define CL_M_2_PI 0.63661977236758134308
> +#define CL_M_2_SQRTPI 1.12837916709551257390
> +#define CL_M_SQRT2 1.41421356237309504880
> +#define CL_M_SQRT1_2 0.70710678118654752440
> +
> +#define CL_M_E_F 2.718281828f
> +#define CL_M_LOG2E_F 1.442695041f
> +#define CL_M_LOG10E_F 0.434294482f
> +#define CL_M_LN2_F 0.693147181f
> +#define CL_M_LN10_F 2.302585093f
> +#define CL_M_PI_F 3.141592654f
> +#define CL_M_PI_2_F 1.570796327f
> +#define CL_M_PI_4_F 0.785398163f
> +#define CL_M_1_PI_F 0.318309886f
> +#define CL_M_2_PI_F 0.636619772f
> +#define CL_M_2_SQRTPI_F 1.128379167f
> +#define CL_M_SQRT2_F 1.414213562f
> +#define CL_M_SQRT1_2_F 0.707106781f
>
> #define CL_NAN (CL_INFINITY - CL_INFINITY)
> #define CL_HUGE_VALF ((cl_float) 1e50)
> @@ -248,9 +335,20 @@ typedef double cl_double __attribute__((aligned(8)));
> #define CL_FLT_MIN_10_EXP -37
> #define CL_FLT_MIN_EXP -125
> #define CL_FLT_RADIX 2
> -#define CL_FLT_MAX 0x1.fffffep127f
> -#define CL_FLT_MIN 0x1.0p-126f
> -#define CL_FLT_EPSILON 0x1.0p-23f
> +#define CL_FLT_MAX 340282346638528859811704183484516925440.0f
> +#define CL_FLT_MIN 1.175494350822287507969e-38f
> +#define CL_FLT_EPSILON 1.1920928955078125e-7f
> +
> +#define CL_HALF_DIG 3
> +#define CL_HALF_MANT_DIG 11
> +#define CL_HALF_MAX_10_EXP +4
> +#define CL_HALF_MAX_EXP +16
> +#define CL_HALF_MIN_10_EXP -4
> +#define CL_HALF_MIN_EXP -13
> +#define CL_HALF_RADIX 2
> +#define CL_HALF_MAX 65504.0f
> +#define CL_HALF_MIN 6.103515625e-05f
> +#define CL_HALF_EPSILON 9.765625e-04f
>
> #define CL_DBL_DIG 15
> #define CL_DBL_MANT_DIG 53
> @@ -259,37 +357,37 @@ typedef double cl_double __attribute__((aligned(8)));
> #define CL_DBL_MIN_10_EXP -307
> #define CL_DBL_MIN_EXP -1021
> #define CL_DBL_RADIX 2
> -#define CL_DBL_MAX 0x1.fffffffffffffp1023
> -#define CL_DBL_MIN 0x1.0p-1022
> -#define CL_DBL_EPSILON 0x1.0p-52
> -
> -#define CL_M_E 2.718281828459045090796
> -#define CL_M_LOG2E 1.442695040888963387005
> -#define CL_M_LOG10E 0.434294481903251816668
> -#define CL_M_LN2 0.693147180559945286227
> -#define CL_M_LN10 2.302585092994045901094
> -#define CL_M_PI 3.141592653589793115998
> -#define CL_M_PI_2 1.570796326794896557999
> -#define CL_M_PI_4 0.785398163397448278999
> -#define CL_M_1_PI 0.318309886183790691216
> -#define CL_M_2_PI 0.636619772367581382433
> -#define CL_M_2_SQRTPI 1.128379167095512558561
> -#define CL_M_SQRT2 1.414213562373095145475
> -#define CL_M_SQRT1_2 0.707106781186547572737
> -
> -#define CL_M_E_F 2.71828174591064f
> -#define CL_M_LOG2E_F 1.44269502162933f
> -#define CL_M_LOG10E_F 0.43429449200630f
> -#define CL_M_LN2_F 0.69314718246460f
> -#define CL_M_LN10_F 2.30258512496948f
> -#define CL_M_PI_F 3.14159274101257f
> -#define CL_M_PI_2_F 1.57079637050629f
> -#define CL_M_PI_4_F 0.78539818525314f
> -#define CL_M_1_PI_F 0.31830987334251f
> -#define CL_M_2_PI_F 0.63661974668503f
> -#define CL_M_2_SQRTPI_F 1.12837922573090f
> -#define CL_M_SQRT2_F 1.41421353816986f
> -#define CL_M_SQRT1_2_F 0.70710676908493f
> +#define CL_DBL_MAX 179769313486231570814527423731704356798070567525844996598917476803157260780028538760589558632766878171540458953514382464234321326889464182768467546703537516986049910576551282076245490090389328944075868508455133942304583236903222948165808559332123348274797826204144723168738177180919299881250404026184124858368.0
> +#define CL_DBL_MIN 2.225073858507201383090e-308
> +#define CL_DBL_EPSILON 2.220446049250313080847e-16
> +
> +#define CL_M_E 2.7182818284590452354
> +#define CL_M_LOG2E 1.4426950408889634074
> +#define CL_M_LOG10E 0.43429448190325182765
> +#define CL_M_LN2 0.69314718055994530942
> +#define CL_M_LN10 2.30258509299404568402
> +#define CL_M_PI 3.14159265358979323846
> +#define CL_M_PI_2 1.57079632679489661923
> +#define CL_M_PI_4 0.78539816339744830962
> +#define CL_M_1_PI 0.31830988618379067154
> +#define CL_M_2_PI 0.63661977236758134308
> +#define CL_M_2_SQRTPI 1.12837916709551257390
> +#define CL_M_SQRT2 1.41421356237309504880
> +#define CL_M_SQRT1_2 0.70710678118654752440
> +
> +#define CL_M_E_F 2.718281828f
> +#define CL_M_LOG2E_F 1.442695041f
> +#define CL_M_LOG10E_F 0.434294482f
> +#define CL_M_LN2_F 0.693147181f
> +#define CL_M_LN10_F 2.302585093f
> +#define CL_M_PI_F 3.141592654f
> +#define CL_M_PI_2_F 1.570796327f
> +#define CL_M_PI_4_F 0.785398163f
> +#define CL_M_1_PI_F 0.318309886f
> +#define CL_M_2_PI_F 0.636619772f
> +#define CL_M_2_SQRTPI_F 1.128379167f
> +#define CL_M_SQRT2_F 1.414213562f
> +#define CL_M_SQRT1_2_F 0.707106781f
>
> #if defined( __GNUC__ )
> #define CL_HUGE_VALF __builtin_huge_valf()
> @@ -452,18 +550,23 @@ typedef unsigned int cl_GLenum;
> #endif
>
> /* Define capabilities for anonymous struct members. */
> -#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
> +#if !defined(__cplusplus) && defined(__STDC_VERSION__) && __STDC_VERSION__ >= 201112L
> +#define __CL_HAS_ANON_STRUCT__ 1
> +#define __CL_ANON_STRUCT__
> +#elif defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
> #define __CL_HAS_ANON_STRUCT__ 1
> #define __CL_ANON_STRUCT__ __extension__
> -#elif defined( _WIN32) && (_MSC_VER >= 1500)
> +#elif defined( _WIN32) && defined(_MSC_VER)
> + #if _MSC_VER >= 1500
> /* Microsoft Developer Studio 2008 supports anonymous structs, but
> * complains by default. */
> -#define __CL_HAS_ANON_STRUCT__ 1
> -#define __CL_ANON_STRUCT__
> + #define __CL_HAS_ANON_STRUCT__ 1
> + #define __CL_ANON_STRUCT__
> /* Disable warning C4201: nonstandard extension used : nameless
> * struct/union */
> -#pragma warning( push )
> -#pragma warning( disable : 4201 )
> + #pragma warning( push )
> + #pragma warning( disable : 4201 )
> + #endif
> #else
> #define __CL_HAS_ANON_STRUCT__ 0
> #define __CL_ANON_STRUCT__
> @@ -792,6 +895,81 @@ typedef union
> #endif
> }cl_ushort16;
>
> +
> +/* ---- cl_halfn ---- */
> +typedef union
> +{
> + cl_half CL_ALIGNED(4) s[2];
> +#if __CL_HAS_ANON_STRUCT__
> + __CL_ANON_STRUCT__ struct{ cl_half x, y; };
> + __CL_ANON_STRUCT__ struct{ cl_half s0, s1; };
> + __CL_ANON_STRUCT__ struct{ cl_half lo, hi; };
> +#endif
> +#if defined( __CL_HALF2__)
> + __cl_half2 v2;
> +#endif
> +}cl_half2;
> +
> +typedef union
> +{
> + cl_half CL_ALIGNED(8) s[4];
> +#if __CL_HAS_ANON_STRUCT__
> + __CL_ANON_STRUCT__ struct{ cl_half x, y, z, w; };
> + __CL_ANON_STRUCT__ struct{ cl_half s0, s1, s2, s3; };
> + __CL_ANON_STRUCT__ struct{ cl_half2 lo, hi; };
> +#endif
> +#if defined( __CL_HALF2__)
> + __cl_half2 v2[2];
> +#endif
> +#if defined( __CL_HALF4__)
> + __cl_half4 v4;
> +#endif
> +}cl_half4;
> +
> +/* cl_half3 is identical in size, alignment and behavior to cl_half4. See section 6.1.5. */
> +typedef cl_half4 cl_half3;
> +
> +typedef union
> +{
> + cl_half CL_ALIGNED(16) s[8];
> +#if __CL_HAS_ANON_STRUCT__
> + __CL_ANON_STRUCT__ struct{ cl_half x, y, z, w; };
> + __CL_ANON_STRUCT__ struct{ cl_half s0, s1, s2, s3, s4, s5, s6, s7; };
> + __CL_ANON_STRUCT__ struct{ cl_half4 lo, hi; };
> +#endif
> +#if defined( __CL_HALF2__)
> + __cl_half2 v2[4];
> +#endif
> +#if defined( __CL_HALF4__)
> + __cl_half4 v4[2];
> +#endif
> +#if defined( __CL_HALF8__ )
> + __cl_half8 v8;
> +#endif
> +}cl_half8;
> +
> +typedef union
> +{
> + cl_half CL_ALIGNED(32) s[16];
> +#if __CL_HAS_ANON_STRUCT__
> + __CL_ANON_STRUCT__ struct{ cl_half x, y, z, w, __spacer4, __spacer5, __spacer6, __spacer7, __spacer8, __spacer9, sa, sb, sc, sd, se, sf; };
> + __CL_ANON_STRUCT__ struct{ cl_half s0, s1, s2, s3, s4, s5, s6, s7, s8, s9, sA, sB, sC, sD, sE, sF; };
> + __CL_ANON_STRUCT__ struct{ cl_half8 lo, hi; };
> +#endif
> +#if defined( __CL_HALF2__)
> + __cl_half2 v2[8];
> +#endif
> +#if defined( __CL_HALF4__)
> + __cl_half4 v4[4];
> +#endif
> +#if defined( __CL_HALF8__ )
> + __cl_half8 v8[2];
> +#endif
> +#if defined( __CL_HALF16__ )
> + __cl_half16 v16;
> +#endif
> +}cl_half16;
> +
> /* ---- cl_intn ---- */
> typedef union
> {
> @@ -1271,8 +1449,10 @@ typedef union
>
> #undef __CL_HAS_ANON_STRUCT__
> #undef __CL_ANON_STRUCT__
> -#if defined( _WIN32) && (_MSC_VER >= 1500)
> -#pragma warning( pop )
> +#if defined( _WIN32) && defined(_MSC_VER)
> + #if _MSC_VER >=1500
> + #pragma warning( pop )
> + #endif
> #endif
>
> #endif /* __CL_PLATFORM_H */
> diff --git a/include/CL/cl_va_api_media_sharing_intel.h b/include/CL/cl_va_api_media_sharing_intel.h
> new file mode 100644
> index 0000000000..2844428857
> --- /dev/null
> +++ b/include/CL/cl_va_api_media_sharing_intel.h
> @@ -0,0 +1,172 @@
> +/**********************************************************************************
> + * Copyright (c) 2008-2016 The Khronos Group Inc.
> + *
> + * Permission is hereby granted, free of charge, to any person obtaining a
> + * copy of this software and/or associated documentation files (the
> + * "Materials"), to deal in the Materials without restriction, including
> + * without limitation the rights to use, copy, modify, merge, publish,
> + * distribute, sublicense, and/or sell copies of the Materials, and to
> + * permit persons to whom the Materials are furnished to do so, subject to
> + * the following conditions:
> + *
> + * The above copyright notice and this permission notice shall be included
> + * in all copies or substantial portions of the Materials.
> + *
> + * MODIFICATIONS TO THIS FILE MAY MEAN IT NO LONGER ACCURATELY REFLECTS
> + * KHRONOS STANDARDS. THE UNMODIFIED, NORMATIVE VERSIONS OF KHRONOS
> + * SPECIFICATIONS AND HEADER INFORMATION ARE LOCATED AT
> + * https://www.khronos.org/registry/
> + *
> + * THE MATERIALS ARE PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND,
> + * EXPRESS OR IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF
> + * MERCHANTABILITY, FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT.
> + * IN NO EVENT SHALL THE AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY
> + * CLAIM, DAMAGES OR OTHER LIABILITY, WHETHER IN AN ACTION OF CONTRACT,
> + * TORT OR OTHERWISE, ARISING FROM, OUT OF OR IN CONNECTION WITH THE
> + * MATERIALS OR THE USE OR OTHER DEALINGS IN THE MATERIALS.
> + **********************************************************************************/
> +/*****************************************************************************\
> +
> +Copyright (c) 2013-2016 Intel Corporation All Rights Reserved.
> +
> +THESE MATERIALS ARE PROVIDED BY THE COPYRIGHT HOLDERS AND CONTRIBUTORS
> +"AS IS" AND ANY EXPRESS OR IMPLIED WARRANTIES, INCLUDING, BUT NOT
> +LIMITED TO, THE IMPLIED WARRANTIES OF MERCHANTABILITY AND FITNESS FOR
> +A PARTICULAR PURPOSE ARE DISCLAIMED. IN NO EVENT SHALL INTEL OR ITS
> +CONTRIBUTORS BE LIABLE FOR ANY DIRECT, INDIRECT, INCIDENTAL, SPECIAL,
> +EXEMPLARY, OR CONSEQUENTIAL DAMAGES (INCLUDING, BUT NOT LIMITED TO,
> +PROCUREMENT OF SUBSTITUTE GOODS OR SERVICES; LOSS OF USE, DATA, OR
> +PROFITS; OR BUSINESS INTERRUPTION) HOWEVER CAUSED AND ON ANY THEORY
> +OF LIABILITY, WHETHER IN CONTRACT, STRICT LIABILITY OR TORT (INCLUDING
> +NEGLIGENCE OR OTHERWISE) ARISING IN ANY WAY OUT OF THE USE OF THESE
> +MATERIALS, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE.
> +
> +File Name: cl_va_api_media_sharing_intel.h
> +
> +Abstract:
> +
> +Notes:
> +
> +\*****************************************************************************/
> +
> +
> +#ifndef __OPENCL_CL_VA_API_MEDIA_SHARING_INTEL_H
> +#define __OPENCL_CL_VA_API_MEDIA_SHARING_INTEL_H
> +
> +#include <CL/cl.h>
> +#include <CL/cl_platform.h>
> +#include <va/va.h>
> +
> +#ifdef __cplusplus
> +extern "C" {
> +#endif
> +
> +/******************************************
> +* cl_intel_va_api_media_sharing extension *
> +*******************************************/
> +
> +#define cl_intel_va_api_media_sharing 1
> +
> +/* error codes */
> +#define CL_INVALID_VA_API_MEDIA_ADAPTER_INTEL -1098
> +#define CL_INVALID_VA_API_MEDIA_SURFACE_INTEL -1099
> +#define CL_VA_API_MEDIA_SURFACE_ALREADY_ACQUIRED_INTEL -1100
> +#define CL_VA_API_MEDIA_SURFACE_NOT_ACQUIRED_INTEL -1101
> +
> +/* cl_va_api_device_source_intel */
> +#define CL_VA_API_DISPLAY_INTEL 0x4094
> +
> +/* cl_va_api_device_set_intel */
> +#define CL_PREFERRED_DEVICES_FOR_VA_API_INTEL 0x4095
> +#define CL_ALL_DEVICES_FOR_VA_API_INTEL 0x4096
> +
> +/* cl_context_info */
> +#define CL_CONTEXT_VA_API_DISPLAY_INTEL 0x4097
> +
> +/* cl_mem_info */
> +#define CL_MEM_VA_API_MEDIA_SURFACE_INTEL 0x4098
> +
> +/* cl_image_info */
> +#define CL_IMAGE_VA_API_PLANE_INTEL 0x4099
> +
> +/* cl_command_type */
> +#define CL_COMMAND_ACQUIRE_VA_API_MEDIA_SURFACES_INTEL 0x409A
> +#define CL_COMMAND_RELEASE_VA_API_MEDIA_SURFACES_INTEL 0x409B
> +
> +typedef cl_uint cl_va_api_device_source_intel;
> +typedef cl_uint cl_va_api_device_set_intel;
> +
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clGetDeviceIDsFromVA_APIMediaAdapterINTEL(
> + cl_platform_id /* platform */,
> + cl_va_api_device_source_intel /* media_adapter_type */,
> + void* /* media_adapter */,
> + cl_va_api_device_set_intel /* media_adapter_set */,
> + cl_uint /* num_entries */,
> + cl_device_id* /* devices */,
> + cl_uint* /* num_devices */) CL_EXT_SUFFIX__VERSION_1_2;
> +
> +typedef CL_API_ENTRY cl_int (CL_API_CALL * clGetDeviceIDsFromVA_APIMediaAdapterINTEL_fn)(
> + cl_platform_id /* platform */,
> + cl_va_api_device_source_intel /* media_adapter_type */,
> + void* /* media_adapter */,
> + cl_va_api_device_set_intel /* media_adapter_set */,
> + cl_uint /* num_entries */,
> + cl_device_id* /* devices */,
> + cl_uint* /* num_devices */) CL_EXT_SUFFIX__VERSION_1_2;
> +
> +extern CL_API_ENTRY cl_mem CL_API_CALL
> +clCreateFromVA_APIMediaSurfaceINTEL(
> + cl_context /* context */,
> + cl_mem_flags /* flags */,
> + VASurfaceID* /* surface */,
> + cl_uint /* plane */,
> + cl_int* /* errcode_ret */) CL_EXT_SUFFIX__VERSION_1_2;
> +
> +typedef CL_API_ENTRY cl_mem (CL_API_CALL * clCreateFromVA_APIMediaSurfaceINTEL_fn)(
> + cl_context /* context */,
> + cl_mem_flags /* flags */,
> + VASurfaceID* /* surface */,
> + cl_uint /* plane */,
> + cl_int* /* errcode_ret */) CL_EXT_SUFFIX__VERSION_1_2;
> +
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clEnqueueAcquireVA_APIMediaSurfacesINTEL(
> + cl_command_queue /* command_queue */,
> + cl_uint /* num_objects */,
> + const cl_mem* /* mem_objects */,
> + cl_uint /* num_events_in_wait_list */,
> + const cl_event* /* event_wait_list */,
> + cl_event* /* event */) CL_EXT_SUFFIX__VERSION_1_2;
> +
> +typedef CL_API_ENTRY cl_int (CL_API_CALL *clEnqueueAcquireVA_APIMediaSurfacesINTEL_fn)(
> + cl_command_queue /* command_queue */,
> + cl_uint /* num_objects */,
> + const cl_mem* /* mem_objects */,
> + cl_uint /* num_events_in_wait_list */,
> + const cl_event* /* event_wait_list */,
> + cl_event* /* event */) CL_EXT_SUFFIX__VERSION_1_2;
> +
> +extern CL_API_ENTRY cl_int CL_API_CALL
> +clEnqueueReleaseVA_APIMediaSurfacesINTEL(
> + cl_command_queue /* command_queue */,
> + cl_uint /* num_objects */,
> + const cl_mem* /* mem_objects */,
> + cl_uint /* num_events_in_wait_list */,
> + const cl_event* /* event_wait_list */,
> + cl_event* /* event */) CL_EXT_SUFFIX__VERSION_1_2;
> +
> +typedef CL_API_ENTRY cl_int (CL_API_CALL *clEnqueueReleaseVA_APIMediaSurfacesINTEL_fn)(
> + cl_command_queue /* command_queue */,
> + cl_uint /* num_objects */,
> + const cl_mem* /* mem_objects */,
> + cl_uint /* num_events_in_wait_list */,
> + const cl_event* /* event_wait_list */,
> + cl_event* /* event */) CL_EXT_SUFFIX__VERSION_1_2;
> +
> +#ifdef __cplusplus
> +}
> +#endif
> +
> +#endif /* __OPENCL_CL_VA_API_MEDIA_SHARING_INTEL_H */
> +
> diff --git a/include/CL/opencl.h b/include/CL/opencl.h
> index 3f00524719..9855cd75e7 100644
> --- a/include/CL/opencl.h
> +++ b/include/CL/opencl.h
> @@ -1,5 +1,5 @@
> /*******************************************************************************
> - * Copyright (c) 2008-2012 The Khronos Group Inc.
> + * Copyright (c) 2008-2015 The Khronos Group Inc.
> *
> * Permission is hereby granted, free of charge, to any person obtaining a
> * copy of this software and/or associated documentation files (the
> @@ -12,6 +12,11 @@
> * The above copyright notice and this permission notice shall be included
> * in all copies or substantial portions of the Materials.
> *
> + * MODIFICATIONS TO THIS FILE MAY MEAN IT NO LONGER ACCURATELY REFLECTS
> + * KHRONOS STANDARDS. THE UNMODIFIED, NORMATIVE VERSIONS OF KHRONOS
> + * SPECIFICATIONS AND HEADER INFORMATION ARE LOCATED AT
> + * https://www.khronos.org/registry/
> + *
> * THE MATERIALS ARE PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND,
> * EXPRESS OR IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF
> * MERCHANTABILITY, FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT.
> --
> 2.16.2
>
More information about the mesa-dev
mailing list