25#include <hip/hip_vector_types.h>
29#define ADDRESS_SPACE_CONSTANT __attribute__((address_space(4)))
31__device__ float4::Native_vec_ __ockl_image_load_1D(
unsigned int ADDRESS_SPACE_CONSTANT*i,
int c);
33__device__ float4::Native_vec_ __ockl_image_load_1Db(
unsigned int ADDRESS_SPACE_CONSTANT*i,
int c);
35__device__ float4::Native_vec_ __ockl_image_load_1Da(
unsigned int ADDRESS_SPACE_CONSTANT*i, int2::Native_vec_ c);
37__device__ float4::Native_vec_ __ockl_image_load_2D(
unsigned int ADDRESS_SPACE_CONSTANT*i, int2::Native_vec_ c);
39__device__ float4::Native_vec_ __ockl_image_load_2Da(
unsigned int ADDRESS_SPACE_CONSTANT*i, int4::Native_vec_ c);
41__device__ float4::Native_vec_ __ockl_image_load_3D(
unsigned int ADDRESS_SPACE_CONSTANT*i, int4::Native_vec_ c);
43__device__ float4::Native_vec_ __ockl_image_load_CM(
unsigned int ADDRESS_SPACE_CONSTANT*i, int2::Native_vec_ c,
int f);
45__device__ float4::Native_vec_ __ockl_image_load_CMa(
unsigned int ADDRESS_SPACE_CONSTANT*i, int4::Native_vec_ c,
int f);
47__device__ float4::Native_vec_ __ockl_image_load_lod_1D(
unsigned int ADDRESS_SPACE_CONSTANT*i,
int c,
int l);
49__device__ float4::Native_vec_ __ockl_image_load_lod_1Da(
unsigned int ADDRESS_SPACE_CONSTANT*i, int2::Native_vec_ c,
int l);
51__device__ float4::Native_vec_ __ockl_image_load_lod_2D(
unsigned int ADDRESS_SPACE_CONSTANT*i, int2::Native_vec_ c,
int l);
53__device__ float4::Native_vec_ __ockl_image_load_lod_2Da(
unsigned int ADDRESS_SPACE_CONSTANT*i, int4::Native_vec_ c,
int l);
55__device__ float4::Native_vec_ __ockl_image_load_lod_3D(
unsigned int ADDRESS_SPACE_CONSTANT*i, int4::Native_vec_ c,
int l);
57__device__ float4::Native_vec_ __ockl_image_load_lod_CM(
unsigned int ADDRESS_SPACE_CONSTANT*i, int2::Native_vec_ c,
int f,
int l);
59__device__ float4::Native_vec_ __ockl_image_load_lod_CMa(
unsigned int ADDRESS_SPACE_CONSTANT*i, int4::Native_vec_ c,
int f,
int l);
61__device__
void __ockl_image_store_1D(
unsigned int ADDRESS_SPACE_CONSTANT*i,
int c, float4::Native_vec_ p);
63__device__
void __ockl_image_store_1Da(
unsigned int ADDRESS_SPACE_CONSTANT*i, int2::Native_vec_ c, float4::Native_vec_ p);
65__device__
void __ockl_image_store_2D(
unsigned int ADDRESS_SPACE_CONSTANT*i, int2::Native_vec_ c, float4::Native_vec_ p);
67__device__
void __ockl_image_store_2Da(
unsigned int ADDRESS_SPACE_CONSTANT*i, int4::Native_vec_ c, float4::Native_vec_ p);
69__device__
void __ockl_image_store_3D(
unsigned int ADDRESS_SPACE_CONSTANT*i, int4::Native_vec_ c, float4::Native_vec_ p);
71__device__
void __ockl_image_store_CM(
unsigned int ADDRESS_SPACE_CONSTANT*i, int2::Native_vec_ c,
int f, float4::Native_vec_ p);
73__device__
void __ockl_image_store_CMa(
unsigned int ADDRESS_SPACE_CONSTANT*i, int4::Native_vec_ c,
int f, float4::Native_vec_ p);
75__device__
void __ockl_image_store_lod_1D(
unsigned int ADDRESS_SPACE_CONSTANT*i,
int c,
int l, float4::Native_vec_ p);
77__device__
void __ockl_image_store_lod_1Da(
unsigned int ADDRESS_SPACE_CONSTANT*i, int2::Native_vec_ c,
int l, float4::Native_vec_ p);
79__device__
void __ockl_image_store_lod_2D(
unsigned int ADDRESS_SPACE_CONSTANT*i, int2::Native_vec_ c,
int l, float4::Native_vec_ p);
81__device__
void __ockl_image_store_lod_2Da(
unsigned int ADDRESS_SPACE_CONSTANT*i, int4::Native_vec_ c,
int l, float4::Native_vec_ p);
83__device__
void __ockl_image_store_lod_3D(
unsigned int ADDRESS_SPACE_CONSTANT*i, int4::Native_vec_ c,
int l, float4::Native_vec_ p);
85__device__
void __ockl_image_store_lod_CM(
unsigned int ADDRESS_SPACE_CONSTANT*i, int2::Native_vec_ c,
int f,
int l, float4::Native_vec_ p);
87__device__
void __ockl_image_store_lod_CMa(
unsigned int ADDRESS_SPACE_CONSTANT*i, int4::Native_vec_ c,
int f,
int l, float4::Native_vec_ p);
89__device__ float4::Native_vec_ __ockl_image_sample_1D(
unsigned int ADDRESS_SPACE_CONSTANT*i,
unsigned int ADDRESS_SPACE_CONSTANT*s,
float c);
91__device__ float4::Native_vec_ __ockl_image_sample_1Da(
unsigned int ADDRESS_SPACE_CONSTANT*i,
unsigned int ADDRESS_SPACE_CONSTANT*s, float2::Native_vec_ c);
93__device__ float4::Native_vec_ __ockl_image_sample_2D(
unsigned int ADDRESS_SPACE_CONSTANT*i,
unsigned int ADDRESS_SPACE_CONSTANT*s, float2::Native_vec_ c);
95__device__ float4::Native_vec_ __ockl_image_sample_2Da(
unsigned int ADDRESS_SPACE_CONSTANT*i,
unsigned int ADDRESS_SPACE_CONSTANT*s, float4::Native_vec_ c);
97__device__ float4::Native_vec_ __ockl_image_sample_3D(
unsigned int ADDRESS_SPACE_CONSTANT*i,
unsigned int ADDRESS_SPACE_CONSTANT*s, float4::Native_vec_ c);
99__device__ float4::Native_vec_ __ockl_image_sample_CM(
unsigned int ADDRESS_SPACE_CONSTANT*i,
unsigned int ADDRESS_SPACE_CONSTANT*s, float4::Native_vec_ c);
101__device__ float4::Native_vec_ __ockl_image_sample_CMa(
unsigned int ADDRESS_SPACE_CONSTANT*i,
unsigned int ADDRESS_SPACE_CONSTANT*s, float4::Native_vec_ c);
103__device__ float4::Native_vec_ __ockl_image_sample_grad_1D(
unsigned int ADDRESS_SPACE_CONSTANT*i,
unsigned int ADDRESS_SPACE_CONSTANT*s,
float c,
float dx,
float dy);
105__device__ float4::Native_vec_ __ockl_image_sample_grad_1Da(
unsigned int ADDRESS_SPACE_CONSTANT*i,
unsigned int ADDRESS_SPACE_CONSTANT*s, float2::Native_vec_ c,
float dx,
float dy);
107__device__ float4::Native_vec_ __ockl_image_sample_grad_2D(
unsigned int ADDRESS_SPACE_CONSTANT*i,
unsigned int ADDRESS_SPACE_CONSTANT*s, float2::Native_vec_ c, float2::Native_vec_ dx, float2::Native_vec_ dy);
109__device__ float4::Native_vec_ __ockl_image_sample_grad_2Da(
unsigned int ADDRESS_SPACE_CONSTANT*i,
unsigned int ADDRESS_SPACE_CONSTANT*s, float4::Native_vec_ c, float2::Native_vec_ dx, float2::Native_vec_ dy);
111__device__ float4::Native_vec_ __ockl_image_sample_grad_3D(
unsigned int ADDRESS_SPACE_CONSTANT*i,
unsigned int ADDRESS_SPACE_CONSTANT*s, float4::Native_vec_ c, float4::Native_vec_ dx, float4::Native_vec_ dy);
113__device__ float4::Native_vec_ __ockl_image_sample_lod_1D(
unsigned int ADDRESS_SPACE_CONSTANT*i,
unsigned int ADDRESS_SPACE_CONSTANT*s,
float c,
float l);
115__device__ float4::Native_vec_ __ockl_image_sample_lod_1Da(
unsigned int ADDRESS_SPACE_CONSTANT*i,
unsigned int ADDRESS_SPACE_CONSTANT*s, float2::Native_vec_ c,
float l);
117__device__ float4::Native_vec_ __ockl_image_sample_lod_2D(
unsigned int ADDRESS_SPACE_CONSTANT*i,
unsigned int ADDRESS_SPACE_CONSTANT*s, float2::Native_vec_ c,
float l);
119__device__ float4::Native_vec_ __ockl_image_sample_lod_2Da(
unsigned int ADDRESS_SPACE_CONSTANT*i,
unsigned int ADDRESS_SPACE_CONSTANT*s, float4::Native_vec_ c,
float l);
121__device__ float4::Native_vec_ __ockl_image_sample_lod_3D(
unsigned int ADDRESS_SPACE_CONSTANT*i,
unsigned int ADDRESS_SPACE_CONSTANT*s, float4::Native_vec_ c,
float l);
123__device__ float4::Native_vec_ __ockl_image_sample_lod_CM(
unsigned int ADDRESS_SPACE_CONSTANT*i,
unsigned int ADDRESS_SPACE_CONSTANT*s, float4::Native_vec_ c,
float l);
125__device__ float4::Native_vec_ __ockl_image_sample_lod_CMa(
unsigned int ADDRESS_SPACE_CONSTANT*i,
unsigned int ADDRESS_SPACE_CONSTANT*s, float4::Native_vec_ c,
float l);
127__device__ float4::Native_vec_ __ockl_image_gather4r_2D(
unsigned int ADDRESS_SPACE_CONSTANT*i,
unsigned int ADDRESS_SPACE_CONSTANT*s, float2::Native_vec_ c);
129__device__ float4::Native_vec_ __ockl_image_gather4g_2D(
unsigned int ADDRESS_SPACE_CONSTANT*i,
unsigned int ADDRESS_SPACE_CONSTANT*s, float2::Native_vec_ c);
131__device__ float4::Native_vec_ __ockl_image_gather4b_2D(
unsigned int ADDRESS_SPACE_CONSTANT*i,
unsigned int ADDRESS_SPACE_CONSTANT*s, float2::Native_vec_ c);
133__device__ float4::Native_vec_ __ockl_image_gather4a_2D(
unsigned int ADDRESS_SPACE_CONSTANT*i,
unsigned int ADDRESS_SPACE_CONSTANT*s, float2::Native_vec_ c);
135__device__
int __ockl_image_channel_data_type_1D(
unsigned int ADDRESS_SPACE_CONSTANT* i);
137__device__
int __ockl_image_channel_data_type_1Da(
unsigned int ADDRESS_SPACE_CONSTANT* i);
139__device__
int __ockl_image_channel_data_type_1Db(
unsigned int ADDRESS_SPACE_CONSTANT* i);
141__device__
int __ockl_image_channel_data_type_2D(
unsigned int ADDRESS_SPACE_CONSTANT* i);
143__device__
int __ockl_image_channel_data_type_2Da(
unsigned int ADDRESS_SPACE_CONSTANT* i);
145__device__
int __ockl_image_channel_data_type_2Dad(
unsigned int ADDRESS_SPACE_CONSTANT* i);
147__device__
int __ockl_image_channel_data_type_2Dd(
unsigned int ADDRESS_SPACE_CONSTANT* i);
149__device__
int __ockl_image_channel_data_type_3D(
unsigned int ADDRESS_SPACE_CONSTANT* i);
151__device__
int __ockl_image_channel_data_type_CM(
unsigned int ADDRESS_SPACE_CONSTANT* i);
153__device__
int __ockl_image_channel_data_type_CMa(
unsigned int ADDRESS_SPACE_CONSTANT* i);
155__device__
int __ockl_image_channel_order_1D(
unsigned int ADDRESS_SPACE_CONSTANT* i);
157__device__
int __ockl_image_channel_order_1Da(
unsigned int ADDRESS_SPACE_CONSTANT* i);
159__device__
int __ockl_image_channel_order_1Db(
unsigned int ADDRESS_SPACE_CONSTANT* i);
161__device__
int __ockl_image_channel_order_2D(
unsigned int ADDRESS_SPACE_CONSTANT* i);
163__device__
int __ockl_image_channel_order_2Da(
unsigned int ADDRESS_SPACE_CONSTANT* i);
165__device__
int __ockl_image_channel_order_2Dad(
unsigned int ADDRESS_SPACE_CONSTANT* i);
167__device__
int __ockl_image_channel_order_2Dd(
unsigned int ADDRESS_SPACE_CONSTANT* i);
169__device__
int __ockl_image_channel_order_3D(
unsigned int ADDRESS_SPACE_CONSTANT* i);
171__device__
int __ockl_image_channel_order_CM(
unsigned int ADDRESS_SPACE_CONSTANT* i);
173__device__
int __ockl_image_channel_order_CMa(
unsigned int ADDRESS_SPACE_CONSTANT* i);