opencl-c-base.h Source File (original) (raw)

9#ifndef _OPENCL_BASE_H_

10#define _OPENCL_BASE_H_

12#if !defined(__opencl_c_generic_address_space)

15#define __opencl_c_named_address_space_builtins 1

16#endif

18#if defined(cl_intel_subgroups) || defined(cl_khr_subgroups) || defined(__opencl_c_subgroups)

20#define __opencl_subgroup_builtins 1

21#endif

28typedef unsigned char uchar;

38typedef unsigned int uint;

43typedef unsigned long ulong;

51typedef __SIZE_TYPE__ size_t;

59typedef __PTRDIFF_TYPE__ ptrdiff_t;

77typedef char char3 __attribute__((ext_vector_type(3)));

78typedef char char4 __attribute__((ext_vector_type(4)));

79typedef char char8 __attribute__((ext_vector_type(8)));

80typedef char char16 __attribute__((ext_vector_type(16)));

86typedef short short2 __attribute__((ext_vector_type(2)));

87typedef short short3 __attribute__((ext_vector_type(3)));

88typedef short short4 __attribute__((ext_vector_type(4)));

89typedef short short8 __attribute__((ext_vector_type(8)));

90typedef short short16 __attribute__((ext_vector_type(16)));

96typedef int int2 __attribute__((ext_vector_type(2)));

97typedef int int3 __attribute__((ext_vector_type(3)));

98typedef int int4 __attribute__((ext_vector_type(4)));

99typedef int int8 __attribute__((ext_vector_type(8)));

100typedef int int16 __attribute__((ext_vector_type(16)));

101typedef uint uint2 __attribute__((ext_vector_type(2)));

102typedef uint uint3 __attribute__((ext_vector_type(3)));

103typedef uint uint4 __attribute__((ext_vector_type(4)));

104typedef uint uint8 __attribute__((ext_vector_type(8)));

105typedef uint uint16 __attribute__((ext_vector_type(16)));

106typedef long long2 __attribute__((ext_vector_type(2)));

107typedef long long3 __attribute__((ext_vector_type(3)));

108typedef long long4 __attribute__((ext_vector_type(4)));

109typedef long long8 __attribute__((ext_vector_type(8)));

110typedef long long16 __attribute__((ext_vector_type(16)));

116typedef float float2 __attribute__((ext_vector_type(2)));

117typedef float float3 __attribute__((ext_vector_type(3)));

118typedef float float4 __attribute__((ext_vector_type(4)));

119typedef float float8 __attribute__((ext_vector_type(8)));

120typedef float float16 __attribute__((ext_vector_type(16)));

121#ifdef cl_khr_fp16

122#pragma OPENCL EXTENSION cl_khr_fp16 : enable

123typedef half half2 __attribute__((ext_vector_type(2)));

124typedef half half3 __attribute__((ext_vector_type(3)));

125typedef half half4 __attribute__((ext_vector_type(4)));

126typedef half half8 __attribute__((ext_vector_type(8)));

127typedef half half16 __attribute__((ext_vector_type(16)));

128#endif

129#ifdef cl_khr_fp64

130#if __OPENCL_C_VERSION__ < CL_VERSION_1_2

131#pragma OPENCL EXTENSION cl_khr_fp64 : enable

132#endif

133typedef double double2 __attribute__((ext_vector_type(2)));

134typedef double double3 __attribute__((ext_vector_type(3)));

135typedef double double4 __attribute__((ext_vector_type(4)));

136typedef double double8 __attribute__((ext_vector_type(8)));

137typedef double double16 __attribute__((ext_vector_type(16)));

138#endif

139

140

141#define __half half

142

143#if defined(__OPENCL_CPP_VERSION__)

144#define NULL nullptr

145#elif defined(__OPENCL_C_VERSION__)

146#define NULL ((void*)0)

147#endif

148

149

150

151

152

153#define MAXFLOAT 0x1.fffffep127f

154

155

156

157

158

159

160#define HUGE_VALF (__builtin_huge_valf())

161

162

163

164

165

166

167#define HUGE_VAL (__builtin_huge_val())

168

169

170

171

172

173#define INFINITY (__builtin_inff())

174

175

176

177

178#define NAN as_float(INT_MAX)

179

180#define FP_ILOGB0 INT_MIN

181#define FP_ILOGBNAN INT_MAX

182

183#define FLT_DIG 6

184#define FLT_MANT_DIG 24

185#define FLT_MAX_10_EXP +38

186#define FLT_MAX_EXP +128

187#define FLT_MIN_10_EXP -37

188#define FLT_MIN_EXP -125

189#define FLT_RADIX 2

190#define FLT_MAX 0x1.fffffep127f

191#define FLT_MIN 0x1.0p-126f

192#define FLT_EPSILON 0x1.0p-23f

193

194#define M_E_F 2.71828182845904523536028747135266250f

195#define M_LOG2E_F 1.44269504088896340735992468100189214f

196#define M_LOG10E_F 0.434294481903251827651128918916605082f

197#define M_LN2_F 0.693147180559945309417232121458176568f

198#define M_LN10_F 2.30258509299404568401799145468436421f

199#define M_PI_F 3.14159265358979323846264338327950288f

200#define M_PI_2_F 1.57079632679489661923132169163975144f

201#define M_PI_4_F 0.785398163397448309615660845819875721f

202#define M_1_PI_F 0.318309886183790671537767526745028724f

203#define M_2_PI_F 0.636619772367581343075535053490057448f

204#define M_2_SQRTPI_F 1.12837916709551257389615890312154517f

205#define M_SQRT2_F 1.41421356237309504880168872420969808f

206#define M_SQRT1_2_F 0.707106781186547524400844362104849039f

207

208#define DBL_DIG 15

209#define DBL_MANT_DIG 53

210#define DBL_MAX_10_EXP +308

211#define DBL_MAX_EXP +1024

212#define DBL_MIN_10_EXP -307

213#define DBL_MIN_EXP -1021

214#define DBL_RADIX 2

215#define DBL_MAX 0x1.fffffffffffffp1023

216#define DBL_MIN 0x1.0p-1022

217#define DBL_EPSILON 0x1.0p-52

218

219#define M_E 0x1.5bf0a8b145769p+1

220#define M_LOG2E 0x1.71547652b82fep+0

221#define M_LOG10E 0x1.bcb7b1526e50ep-2

222#define M_LN2 0x1.62e42fefa39efp-1

223#define M_LN10 0x1.26bb1bbb55516p+1

224#define M_PI 0x1.921fb54442d18p+1

225#define M_PI_2 0x1.921fb54442d18p+0

226#define M_PI_4 0x1.921fb54442d18p-1

227#define M_1_PI 0x1.45f306dc9c883p-2

228#define M_2_PI 0x1.45f306dc9c883p-1

229#define M_2_SQRTPI 0x1.20dd750429b6dp+0

230#define M_SQRT2 0x1.6a09e667f3bcdp+0

231#define M_SQRT1_2 0x1.6a09e667f3bcdp-1

232

233#ifdef cl_khr_fp16

234

235#define HALF_DIG 3

236#define HALF_MANT_DIG 11

237#define HALF_MAX_10_EXP +4

238#define HALF_MAX_EXP +16

239#define HALF_MIN_10_EXP -4

240#define HALF_MIN_EXP -13

241#define HALF_RADIX 2

242#define HALF_MAX ((0x1.ffcp15h))

243#define HALF_MIN ((0x1.0p-14h))

244#define HALF_EPSILON ((0x1.0p-10h))

245

246#define M_E_H 2.71828182845904523536028747135266250h

247#define M_LOG2E_H 1.44269504088896340735992468100189214h

248#define M_LOG10E_H 0.434294481903251827651128918916605082h

249#define M_LN2_H 0.693147180559945309417232121458176568h

250#define M_LN10_H 2.30258509299404568401799145468436421h

251#define M_PI_H 3.14159265358979323846264338327950288h

252#define M_PI_2_H 1.57079632679489661923132169163975144h

253#define M_PI_4_H 0.785398163397448309615660845819875721h

254#define M_1_PI_H 0.318309886183790671537767526745028724h

255#define M_2_PI_H 0.636619772367581343075535053490057448h

256#define M_2_SQRTPI_H 1.12837916709551257389615890312154517h

257#define M_SQRT2_H 1.41421356237309504880168872420969808h

258#define M_SQRT1_2_H 0.707106781186547524400844362104849039h

259

260#endif

261

262#define CHAR_BIT 8

263#define SCHAR_MAX 127

264#define SCHAR_MIN (-128)

265#define UCHAR_MAX 255

266#define CHAR_MAX SCHAR_MAX

267#define CHAR_MIN SCHAR_MIN

268#define USHRT_MAX 65535

269#define SHRT_MAX 32767

270#define SHRT_MIN (-32768)

271#define UINT_MAX 0xffffffff

272#define INT_MAX 2147483647

273#define INT_MIN (-2147483647-1)

274#define ULONG_MAX 0xffffffffffffffffUL

275#define LONG_MAX 0x7fffffffffffffffL

276#define LONG_MIN (-0x7fffffffffffffffL-1)

277

278

279

280

282

283

284

285

286

287#define CLK_LOCAL_MEM_FENCE 0x01

288

289

290

291

292

293#define CLK_GLOBAL_MEM_FENCE 0x02

294

295#if defined(__OPENCL_CPP_VERSION__) || (__OPENCL_C_VERSION__ >= CL_VERSION_2_0)

296

301#if defined(__opencl_c_atomic_scope_all_devices)

302 memory_scope_all_svm_devices = __OPENCL_MEMORY_SCOPE_ALL_SVM_DEVICES,

303#if (__OPENCL_C_VERSION__ >= CL_VERSION_3_0 || __OPENCL_CPP_VERSION__ >= 202100)

304 memory_scope_all_devices = memory_scope_all_svm_devices,

305#endif

306#endif

307

308

309

310

311

312

313#if defined(cl_intel_subgroups) || defined(cl_khr_subgroups) || defined(__opencl_c_subgroups)

314 memory_scope_sub_group = __OPENCL_MEMORY_SCOPE_SUB_GROUP

315#endif

317

318

319

320

321

322

323#define CLK_IMAGE_MEM_FENCE 0x04

324

325#ifndef ATOMIC_VAR_INIT

326#define ATOMIC_VAR_INIT(x) (x)

327#endif

328#define ATOMIC_FLAG_INIT 0

329

330

332{

337#if defined(__opencl_c_atomic_order_seq_cst)

339#endif

341

342#endif

343

344

345

346

347

348

349

350#define CLK_ADDRESS_NONE 0

351#define CLK_ADDRESS_CLAMP_TO_EDGE 2

352#define CLK_ADDRESS_CLAMP 4

353#define CLK_ADDRESS_REPEAT 6

354#define CLK_ADDRESS_MIRRORED_REPEAT 8

355

356

357

358

359#define CLK_NORMALIZED_COORDS_FALSE 0

360#define CLK_NORMALIZED_COORDS_TRUE 1

361

362

363

364

365#define CLK_FILTER_NEAREST 0x10

366#define CLK_FILTER_LINEAR 0x20

367

368#ifdef cl_khr_gl_msaa_sharing

369#pragma OPENCL EXTENSION cl_khr_gl_msaa_sharing : enable

370#endif

371

372

373

374

375#define CLK_SNORM_INT8 0x10D0

376#define CLK_SNORM_INT16 0x10D1

377#define CLK_UNORM_INT8 0x10D2

378#define CLK_UNORM_INT16 0x10D3

379#define CLK_UNORM_SHORT_565 0x10D4

380#define CLK_UNORM_SHORT_555 0x10D5

381#define CLK_UNORM_INT_101010 0x10D6

382#define CLK_SIGNED_INT8 0x10D7

383#define CLK_SIGNED_INT16 0x10D8

384#define CLK_SIGNED_INT32 0x10D9

385#define CLK_UNSIGNED_INT8 0x10DA

386#define CLK_UNSIGNED_INT16 0x10DB

387#define CLK_UNSIGNED_INT32 0x10DC

388#define CLK_HALF_FLOAT 0x10DD

389#define CLK_FLOAT 0x10DE

390#define CLK_UNORM_INT24 0x10DF

391#if __OPENCL_C_VERSION__ >= CL_VERSION_3_0

392#define CLK_UNORM_INT_101010_2 0x10E0

393#endif

394#ifdef __opencl_c_ext_image_raw10_raw12

395#define CLK_UNSIGNED_INT_RAW10_EXT 0x10E3

396#define CLK_UNSIGNED_INT_RAW12_EXT 0x10E4

397#endif

398#ifdef __opencl_c_ext_image_unorm_int_2_101010

399#define CLK_UNORM_INT_2_101010_EXT 0x10E5

400#endif

401#ifdef __opencl_c_ext_image_unsigned_10x6_12x4_14x2

402#define CLK_UNSIGNED_INT10X6_EXT 0x10E6

403#define CLK_UNSIGNED_INT12X4_EXT 0x10E7

404#define CLK_UNSIGNED_INT14X2_EXT 0x10E8

405#define CLK_UNORM_10X6_EXT 0x10E1

406#define CLK_UNORM_12X4_EXT 0x10E9

407#define CLK_UNORM_14X2_EXT 0x10EA

408#endif

409

410

411

412#define CLK_R 0x10B0

413#define CLK_A 0x10B1

414#define CLK_RG 0x10B2

415#define CLK_RA 0x10B3

416#define CLK_RGB 0x10B4

417#define CLK_RGBA 0x10B5

418#define CLK_BGRA 0x10B6

419#define CLK_ARGB 0x10B7

420#define CLK_INTENSITY 0x10B8

421#define CLK_LUMINANCE 0x10B9

422#define CLK_Rx 0x10BA

423#define CLK_RGx 0x10BB

424#define CLK_RGBx 0x10BC

425#define CLK_DEPTH 0x10BD

426#define CLK_DEPTH_STENCIL 0x10BE

427#if __OPENCL_C_VERSION__ >= CL_VERSION_2_0

428#define CLK_sRGB 0x10BF

429#define CLK_sRGBx 0x10C0

430#define CLK_sRGBA 0x10C1

431#define CLK_sBGRA 0x10C2

432#define CLK_ABGR 0x10C3

433#endif

434

435

436#if defined(__OPENCL_CPP_VERSION__) || (__OPENCL_C_VERSION__ >= CL_VERSION_2_0)

437#define CLK_NULL_RESERVE_ID (__builtin_astype(((void*)(__SIZE_MAX__)), reserve_id_t))

438

439

440#define CL_COMPLETE 0x0

441#define CL_RUNNING 0x1

442#define CL_SUBMITTED 0x2

443#define CL_QUEUED 0x3

444

445#define CLK_SUCCESS 0

446#define CLK_ENQUEUE_FAILURE -101

447#define CLK_INVALID_QUEUE -102

448#define CLK_INVALID_NDRANGE -160

449#define CLK_INVALID_EVENT_WAIT_LIST -57

450#define CLK_DEVICE_QUEUE_FULL -161

451#define CLK_INVALID_ARG_SIZE -51

452#define CLK_EVENT_ALLOCATION_FAILURE -100

453#define CLK_OUT_OF_RESOURCES -5

454

455#define CLK_NULL_QUEUE 0

456#define CLK_NULL_EVENT (__builtin_astype(((__SIZE_MAX__)), clk_event_t))

457

458

459#define CLK_ENQUEUE_FLAGS_NO_WAIT 0x0

460#define CLK_ENQUEUE_FLAGS_WAIT_KERNEL 0x1

461#define CLK_ENQUEUE_FLAGS_WAIT_WORK_GROUP 0x2

462

465

466

467#define CLK_PROFILING_COMMAND_EXEC_TIME 0x1

468

469#define MAX_WORK_DIM 3

470

471#ifdef __opencl_c_device_enqueue

472typedef struct {

473 unsigned int workDimension;

477} ndrange_t;

478#endif

479

480#endif

481

482

483

484

485

486#define as_char(x) __builtin_astype((x), char)

487#define as_char2(x) __builtin_astype((x), char2)

488#define as_char3(x) __builtin_astype((x), char3)

489#define as_char4(x) __builtin_astype((x), char4)

490#define as_char8(x) __builtin_astype((x), char8)

491#define as_char16(x) __builtin_astype((x), char16)

492

493#define as_uchar(x) __builtin_astype((x), uchar)

494#define as_uchar2(x) __builtin_astype((x), uchar2)

495#define as_uchar3(x) __builtin_astype((x), uchar3)

496#define as_uchar4(x) __builtin_astype((x), uchar4)

497#define as_uchar8(x) __builtin_astype((x), uchar8)

498#define as_uchar16(x) __builtin_astype((x), uchar16)

499

500#define as_short(x) __builtin_astype((x), short)

501#define as_short2(x) __builtin_astype((x), short2)

502#define as_short3(x) __builtin_astype((x), short3)

503#define as_short4(x) __builtin_astype((x), short4)

504#define as_short8(x) __builtin_astype((x), short8)

505#define as_short16(x) __builtin_astype((x), short16)

506

507#define as_ushort(x) __builtin_astype((x), ushort)

508#define as_ushort2(x) __builtin_astype((x), ushort2)

509#define as_ushort3(x) __builtin_astype((x), ushort3)

510#define as_ushort4(x) __builtin_astype((x), ushort4)

511#define as_ushort8(x) __builtin_astype((x), ushort8)

512#define as_ushort16(x) __builtin_astype((x), ushort16)

513

514#define as_int(x) __builtin_astype((x), int)

515#define as_int2(x) __builtin_astype((x), int2)

516#define as_int3(x) __builtin_astype((x), int3)

517#define as_int4(x) __builtin_astype((x), int4)

518#define as_int8(x) __builtin_astype((x), int8)

519#define as_int16(x) __builtin_astype((x), int16)

520

521#define as_uint(x) __builtin_astype((x), uint)

522#define as_uint2(x) __builtin_astype((x), uint2)

523#define as_uint3(x) __builtin_astype((x), uint3)

524#define as_uint4(x) __builtin_astype((x), uint4)

525#define as_uint8(x) __builtin_astype((x), uint8)

526#define as_uint16(x) __builtin_astype((x), uint16)

527

528#define as_long(x) __builtin_astype((x), long)

529#define as_long2(x) __builtin_astype((x), long2)

530#define as_long3(x) __builtin_astype((x), long3)

531#define as_long4(x) __builtin_astype((x), long4)

532#define as_long8(x) __builtin_astype((x), long8)

533#define as_long16(x) __builtin_astype((x), long16)

534

535#define as_ulong(x) __builtin_astype((x), ulong)

536#define as_ulong2(x) __builtin_astype((x), ulong2)

537#define as_ulong3(x) __builtin_astype((x), ulong3)

538#define as_ulong4(x) __builtin_astype((x), ulong4)

539#define as_ulong8(x) __builtin_astype((x), ulong8)

540#define as_ulong16(x) __builtin_astype((x), ulong16)

541

542#define as_float(x) __builtin_astype((x), float)

543#define as_float2(x) __builtin_astype((x), float2)

544#define as_float3(x) __builtin_astype((x), float3)

545#define as_float4(x) __builtin_astype((x), float4)

546#define as_float8(x) __builtin_astype((x), float8)

547#define as_float16(x) __builtin_astype((x), float16)

548

549#ifdef cl_khr_fp64

550#define as_double(x) __builtin_astype((x), double)

551#define as_double2(x) __builtin_astype((x), double2)

552#define as_double3(x) __builtin_astype((x), double3)

553#define as_double4(x) __builtin_astype((x), double4)

554#define as_double8(x) __builtin_astype((x), double8)

555#define as_double16(x) __builtin_astype((x), double16)

556#endif

557

558#ifdef cl_khr_fp16

559#define as_half(x) __builtin_astype((x), half)

560#define as_half2(x) __builtin_astype((x), half2)

561#define as_half3(x) __builtin_astype((x), half3)

562#define as_half4(x) __builtin_astype((x), half4)

563#define as_half8(x) __builtin_astype((x), half8)

564#define as_half16(x) __builtin_astype((x), half16)

565#endif

566

567#define as_size_t(x) __builtin_astype((x), size_t)

568#define as_ptrdiff_t(x) __builtin_astype((x), ptrdiff_t)

569#define as_intptr_t(x) __builtin_astype((x), intptr_t)

570#define as_uintptr_t(x) __builtin_astype((x), uintptr_t)

571

572

573#if defined(__OPENCL_CPP_VERSION__)

574template <typename _Tp> struct __remove_address_space { using type = _Tp; };

575#if defined(__opencl_c_generic_address_space)

576template <typename _Tp> struct __remove_address_space<__generic _Tp> {

577 using type = _Tp;

578};

579#endif

580template <typename _Tp> struct __remove_address_space<__global _Tp> {

581 using type = _Tp;

582};

583template <typename _Tp> struct __remove_address_space<__private _Tp> {

584 using type = _Tp;

585};

586template <typename _Tp> struct __remove_address_space<__local _Tp> {

587 using type = _Tp;

588};

589template <typename _Tp> struct __remove_address_space<__constant _Tp> {

590 using type = _Tp;

591};

592#endif

593

594

595

596#define __kernel_exec(X, typen) __kernel \

597 __attribute__((work_group_size_hint(X, 1, 1))) \

598 __attribute__((vec_type_hint(typen)))

599

600#define kernel_exec(X, typen) __kernel \

601 __attribute__((work_group_size_hint(X, 1, 1))) \

602 __attribute__((vec_type_hint(typen)))

603

604#if defined(__OPENCL_CPP_VERSION__) || (__OPENCL_C_VERSION__ >= CL_VERSION_1_2)

605

606

607#ifdef __OPENCL_CPP_VERSION__

608#define CLINKAGE extern "C"

609#else

610#define CLINKAGE

611#endif

612

615

616#undef CLINKAGE

617#endif

618

619#ifdef cl_intel_device_side_avc_motion_estimation

620

621#define CLK_AVC_ME_MAJOR_16x16_INTEL 0x0

622#define CLK_AVC_ME_MAJOR_16x8_INTEL 0x1

623#define CLK_AVC_ME_MAJOR_8x16_INTEL 0x2

624#define CLK_AVC_ME_MAJOR_8x8_INTEL 0x3

625

626#define CLK_AVC_ME_MINOR_8x8_INTEL 0x0

627#define CLK_AVC_ME_MINOR_8x4_INTEL 0x1

628#define CLK_AVC_ME_MINOR_4x8_INTEL 0x2

629#define CLK_AVC_ME_MINOR_4x4_INTEL 0x3

630

631#define CLK_AVC_ME_MAJOR_FORWARD_INTEL 0x0

632#define CLK_AVC_ME_MAJOR_BACKWARD_INTEL 0x1

633#define CLK_AVC_ME_MAJOR_BIDIRECTIONAL_INTEL 0x2

634

635#define CLK_AVC_ME_PARTITION_MASK_ALL_INTEL 0x0

636#define CLK_AVC_ME_PARTITION_MASK_16x16_INTEL 0x7E

637#define CLK_AVC_ME_PARTITION_MASK_16x8_INTEL 0x7D

638#define CLK_AVC_ME_PARTITION_MASK_8x16_INTEL 0x7B

639#define CLK_AVC_ME_PARTITION_MASK_8x8_INTEL 0x77

640#define CLK_AVC_ME_PARTITION_MASK_8x4_INTEL 0x6F

641#define CLK_AVC_ME_PARTITION_MASK_4x8_INTEL 0x5F

642#define CLK_AVC_ME_PARTITION_MASK_4x4_INTEL 0x3F

643

644#define CLK_AVC_ME_SLICE_TYPE_PRED_INTEL 0x0

645#define CLK_AVC_ME_SLICE_TYPE_BPRED_INTEL 0x1

646#define CLK_AVC_ME_SLICE_TYPE_INTRA_INTEL 0x2

647

648#define CLK_AVC_ME_SEARCH_WINDOW_EXHAUSTIVE_INTEL 0x0

649#define CLK_AVC_ME_SEARCH_WINDOW_SMALL_INTEL 0x1

650#define CLK_AVC_ME_SEARCH_WINDOW_TINY_INTEL 0x2

651#define CLK_AVC_ME_SEARCH_WINDOW_EXTRA_TINY_INTEL 0x3

652#define CLK_AVC_ME_SEARCH_WINDOW_DIAMOND_INTEL 0x4

653#define CLK_AVC_ME_SEARCH_WINDOW_LARGE_DIAMOND_INTEL 0x5

654#define CLK_AVC_ME_SEARCH_WINDOW_RESERVED0_INTEL 0x6

655#define CLK_AVC_ME_SEARCH_WINDOW_RESERVED1_INTEL 0x7

656#define CLK_AVC_ME_SEARCH_WINDOW_CUSTOM_INTEL 0x8

657

658#define CLK_AVC_ME_SAD_ADJUST_MODE_NONE_INTEL 0x0

659#define CLK_AVC_ME_SAD_ADJUST_MODE_HAAR_INTEL 0x2

660

661#define CLK_AVC_ME_SUBPIXEL_MODE_INTEGER_INTEL 0x0

662#define CLK_AVC_ME_SUBPIXEL_MODE_HPEL_INTEL 0x1

663#define CLK_AVC_ME_SUBPIXEL_MODE_QPEL_INTEL 0x3

664

665#define CLK_AVC_ME_COST_PRECISION_QPEL_INTEL 0x0

666#define CLK_AVC_ME_COST_PRECISION_HPEL_INTEL 0x1

667#define CLK_AVC_ME_COST_PRECISION_PEL_INTEL 0x2

668#define CLK_AVC_ME_COST_PRECISION_DPEL_INTEL 0x3

669

670#define CLK_AVC_ME_BIDIR_WEIGHT_QUARTER_INTEL 0x10

671#define CLK_AVC_ME_BIDIR_WEIGHT_THIRD_INTEL 0x15

672#define CLK_AVC_ME_BIDIR_WEIGHT_HALF_INTEL 0x20

673#define CLK_AVC_ME_BIDIR_WEIGHT_TWO_THIRD_INTEL 0x2B

674#define CLK_AVC_ME_BIDIR_WEIGHT_THREE_QUARTER_INTEL 0x30

675

676#define CLK_AVC_ME_BORDER_REACHED_LEFT_INTEL 0x0

677#define CLK_AVC_ME_BORDER_REACHED_RIGHT_INTEL 0x2

678#define CLK_AVC_ME_BORDER_REACHED_TOP_INTEL 0x4

679#define CLK_AVC_ME_BORDER_REACHED_BOTTOM_INTEL 0x8

680

681#define CLK_AVC_ME_INTRA_16x16_INTEL 0x0

682#define CLK_AVC_ME_INTRA_8x8_INTEL 0x1

683#define CLK_AVC_ME_INTRA_4x4_INTEL 0x2

684

685#define CLK_AVC_ME_SKIP_BLOCK_PARTITION_16x16_INTEL 0x0

686#define CLK_AVC_ME_SKIP_BLOCK_PARTITION_8x8_INTEL 0x4000

687

688#define CLK_AVC_ME_SKIP_BLOCK_16x16_FORWARD_ENABLE_INTEL (0x1 << 24)

689#define CLK_AVC_ME_SKIP_BLOCK_16x16_BACKWARD_ENABLE_INTEL (0x2 << 24)

690#define CLK_AVC_ME_SKIP_BLOCK_16x16_DUAL_ENABLE_INTEL (0x3 << 24)

691#define CLK_AVC_ME_SKIP_BLOCK_8x8_FORWARD_ENABLE_INTEL (0x55 << 24)

692#define CLK_AVC_ME_SKIP_BLOCK_8x8_BACKWARD_ENABLE_INTEL (0xAA << 24)

693#define CLK_AVC_ME_SKIP_BLOCK_8x8_DUAL_ENABLE_INTEL (0xFF << 24)

694#define CLK_AVC_ME_SKIP_BLOCK_8x8_0_FORWARD_ENABLE_INTEL (0x1 << 24)

695#define CLK_AVC_ME_SKIP_BLOCK_8x8_0_BACKWARD_ENABLE_INTEL (0x2 << 24)

696#define CLK_AVC_ME_SKIP_BLOCK_8x8_1_FORWARD_ENABLE_INTEL (0x1 << 26)

697#define CLK_AVC_ME_SKIP_BLOCK_8x8_1_BACKWARD_ENABLE_INTEL (0x2 << 26)

698#define CLK_AVC_ME_SKIP_BLOCK_8x8_2_FORWARD_ENABLE_INTEL (0x1 << 28)

699#define CLK_AVC_ME_SKIP_BLOCK_8x8_2_BACKWARD_ENABLE_INTEL (0x2 << 28)

700#define CLK_AVC_ME_SKIP_BLOCK_8x8_3_FORWARD_ENABLE_INTEL (0x1 << 30)

701#define CLK_AVC_ME_SKIP_BLOCK_8x8_3_BACKWARD_ENABLE_INTEL (0x2 << 30)

702

703#define CLK_AVC_ME_BLOCK_BASED_SKIP_4x4_INTEL 0x00

704#define CLK_AVC_ME_BLOCK_BASED_SKIP_8x8_INTEL 0x80

705

706#define CLK_AVC_ME_INTRA_LUMA_PARTITION_MASK_ALL_INTEL 0x0

707#define CLK_AVC_ME_INTRA_LUMA_PARTITION_MASK_16x16_INTEL 0x6

708#define CLK_AVC_ME_INTRA_LUMA_PARTITION_MASK_8x8_INTEL 0x5

709#define CLK_AVC_ME_INTRA_LUMA_PARTITION_MASK_4x4_INTEL 0x3

710

711#define CLK_AVC_ME_INTRA_NEIGHBOR_LEFT_MASK_ENABLE_INTEL 0x60

712#define CLK_AVC_ME_INTRA_NEIGHBOR_UPPER_MASK_ENABLE_INTEL 0x10

713#define CLK_AVC_ME_INTRA_NEIGHBOR_UPPER_RIGHT_MASK_ENABLE_INTEL 0x8

714#define CLK_AVC_ME_INTRA_NEIGHBOR_UPPER_LEFT_MASK_ENABLE_INTEL 0x4

715

716#define CLK_AVC_ME_LUMA_PREDICTOR_MODE_VERTICAL_INTEL 0x0

717#define CLK_AVC_ME_LUMA_PREDICTOR_MODE_HORIZONTAL_INTEL 0x1

718#define CLK_AVC_ME_LUMA_PREDICTOR_MODE_DC_INTEL 0x2

719#define CLK_AVC_ME_LUMA_PREDICTOR_MODE_DIAGONAL_DOWN_LEFT_INTEL 0x3

720#define CLK_AVC_ME_LUMA_PREDICTOR_MODE_DIAGONAL_DOWN_RIGHT_INTEL 0x4

721#define CLK_AVC_ME_LUMA_PREDICTOR_MODE_PLANE_INTEL 0x4

722#define CLK_AVC_ME_LUMA_PREDICTOR_MODE_VERTICAL_RIGHT_INTEL 0x5

723#define CLK_AVC_ME_LUMA_PREDICTOR_MODE_HORIZONTAL_DOWN_INTEL 0x6

724#define CLK_AVC_ME_LUMA_PREDICTOR_MODE_VERTICAL_LEFT_INTEL 0x7

725#define CLK_AVC_ME_LUMA_PREDICTOR_MODE_HORIZONTAL_UP_INTEL 0x8

726#define CLK_AVC_ME_CHROMA_PREDICTOR_MODE_DC_INTEL 0x0

727#define CLK_AVC_ME_CHROMA_PREDICTOR_MODE_HORIZONTAL_INTEL 0x1

728#define CLK_AVC_ME_CHROMA_PREDICTOR_MODE_VERTICAL_INTEL 0x2

729#define CLK_AVC_ME_CHROMA_PREDICTOR_MODE_PLANE_INTEL 0x3

730

731#define CLK_AVC_ME_FRAME_FORWARD_INTEL 0x1

732#define CLK_AVC_ME_FRAME_BACKWARD_INTEL 0x2

733#define CLK_AVC_ME_FRAME_DUAL_INTEL 0x3

734

735#define CLK_AVC_ME_INTERLACED_SCAN_TOP_FIELD_INTEL 0x0

736#define CLK_AVC_ME_INTERLACED_SCAN_BOTTOM_FIELD_INTEL 0x1

737

738#define CLK_AVC_ME_INITIALIZE_INTEL 0x0

739

740#define CLK_AVC_IME_PAYLOAD_INITIALIZE_INTEL 0x0

741#define CLK_AVC_REF_PAYLOAD_INITIALIZE_INTEL 0x0

742#define CLK_AVC_SIC_PAYLOAD_INITIALIZE_INTEL 0x0

743

744#define CLK_AVC_IME_RESULT_INITIALIZE_INTEL 0x0

745#define CLK_AVC_REF_RESULT_INITIALIZE_INTEL 0x0

746#define CLK_AVC_SIC_RESULT_INITIALIZE_INTEL 0x0

747

748#define CLK_AVC_IME_RESULT_SINGLE_REFERENCE_STREAMOUT_INITIALIZE_INTEL 0x0

749#define CLK_AVC_IME_RESULT_SINGLE_REFERENCE_STREAMIN_INITIALIZE_INTEL 0x0

750#define CLK_AVC_IME_RESULT_DUAL_REFERENCE_STREAMOUT_INITIALIZE_INTEL 0x0

751#define CLK_AVC_IME_RESULT_DUAL_REFERENCE_STREAMIN_INITIALIZE_INTEL 0x0

752

753#endif

754

755

756#pragma OPENCL EXTENSION all : disable

757

758#endif

_Float16 __2f16 __attribute__((ext_vector_type(2)))

Zeroes the upper 128 bits (bits 255:128) of all YMM registers.

__PTRDIFF_TYPE__ ptrdiff_t

A signed integer type that is the result of subtracting two pointers.

__SIZE_TYPE__ size_t

The unsigned integer type of the result of the sizeof operator.

const internal::VariadicAllOfMatcher< Type > type

Matches Types in the clang AST.

#define CLINKAGE

Definition opencl-c-base.h:610

__INTPTR_TYPE__ intptr_t

A signed integer type with the property that any valid pointer to void can be converted to this type,...

Definition opencl-c-base.h:66

int kernel_enqueue_flags_t

Definition opencl-c-base.h:463

memory_order

Definition opencl-c-base.h:332

@ memory_order_release

Definition opencl-c-base.h:335

@ memory_order_relaxed

Definition opencl-c-base.h:333

@ memory_order_acq_rel

Definition opencl-c-base.h:336

@ memory_order_acquire

Definition opencl-c-base.h:334

#define MAX_WORK_DIM

Definition opencl-c-base.h:469

__UINTPTR_TYPE__ uintptr_t

An unsigned integer type with the property that any valid pointer to void can be converted to this ty...

Definition opencl-c-base.h:73

char char2 __attribute__((ext_vector_type(2)))

Definition opencl-c-base.h:76

int clk_profiling_info

Definition opencl-c-base.h:464

uint cl_mem_fence_flags

Definition opencl-c-base.h:281

unsigned char uchar

An unsigned 8-bit integer.

Definition opencl-c-base.h:28

unsigned long ulong

An unsigned 64-bit integer.

Definition opencl-c-base.h:43

memory_scope

Definition opencl-c-base.h:297

@ memory_scope_work_item

Definition opencl-c-base.h:298

@ memory_scope_work_group

Definition opencl-c-base.h:299

@ memory_scope_device

Definition opencl-c-base.h:300

unsigned short ushort

An unsigned 16-bit integer.

Definition opencl-c-base.h:33

CLINKAGE int printf(__constant const char *st,...) __attribute__((format(printf