Namespaces
namespace	__cuda_tex

Macros
#define	__nv_tex_surf_handler(__op, __ptr, ...)
#define	__ID(__op)
#define	__IDV(__op, __variant)
#define	__OP_TYPE_SURFACE(__op)
#define	__Args(...)
#define	__STRIP_PARENS(__X)
#define	__L(__X)
#define	__ASM_OUT(__t)
#define	__ASM_OUTP(__t)
#define	__IMPL_F1(__rt, __dt, __args, __asm_op, __asm_outs, __asm_args)
#define	__IMPL_F3(__args, __asm_op, __ctype, __asm_op_args, __asm_args)
#define	__IMPL_F3S(__args, __asm_op, __ctype, __asm_op_args, __asm_args)
#define	__IMPL_F3N(__args, __asm_op, __ctype, __asm_op_args, __asm_args)
#define	__IMPL_S3I(__op, __args, __asm_op, __ctype, __asm_op_args, __asm_args)
#define	__IMPL_S3SI(__op, __args, __asm_op, __ctype, __asm_op_args, __asm_args)
#define	__IMPL_S3NI(__op, __args, __asm_op, __ctype, __asm_op_args, __asm_args)
#define	__IMPL_SI(__op, __opn, __args, __asm_op, __ctype, __asm_op_args, __asm_args)
#define	__IMPL_S3(__op, __args, __asm_op, __ctype, __asm_op_args, __asm_args)
#define	__IMPL_S3S(__op, __args, __asm_op, __ctype, __asm_op_args, __asm_args)
#define	__IMPL_S3N(__op, __args, __asm_op, __ctype, __asm_op_args, __asm_args)
#define	__IMPL_S(__op, __opn, __args, __asm_op, __ctype, __asm_op_args, __asm_args)
#define	__IMPL_ALIASI(__op, __opn)
#define	__IMPL_ALIAS(__op, __opn)
#define	__IMPL_2DGATHER(variant, instr)
#define	__SURF_WRITE_V2(__op, __asm_dim, __asmtype, __type, __index_op_args, __index_args, __index_asm_args, __asm_op_args, __asm_args)
#define	__SURF_READ_V2(__op, __asm_dim, __asmtype, __type, __asm_op_args, __asm_args, __index_args, __index_asm_args)
#define	__SW_ASM_ARGS(__type)
#define	__SW_ASM_ARGS1(__type)
#define	__SW_ASM_ARGS2(__type)
#define	__SW_ASM_ARGS4(__type)
#define	__SURF_READ1D(__asmtype, __type, __asm_op_args, __asm_args)
#define	__SURF_READ2D(__asmtype, __type, __asm_op_args, __asm_args)
#define	__SURF_READ3D(__asmtype, __type, __asm_op_args, __asm_args)
#define	__SURF_READ1DLAYERED(__asmtype, __type, __asm_op_args, __asm_args)
#define	__SURF_READ2DLAYERED(__asmtype, __type, __asm_op_args, __asm_args)
#define	__SURF_READCUBEMAP(__asmtype, __type, __asm_op_args, __asm_args)
#define	__SURF_READCUBEMAPLAYERED(__asmtype, __type, __asm_op_args, __asm_args)
#define	__1DV1 "{%0}, [%1, {%2}]"
#define	__1DV2 "{%0, %1}, [%2, {%3}]"
#define	__1DV4 "{%0, %1, %2, %3}, [%4, {%5}]"
#define	__2DV1 "{%0}, [%1, {%2, %3}]"
#define	__2DV2 "{%0, %1}, [%2, {%3, %4}]"
#define	__2DV4 "{%0, %1, %2, %3}, [%4, {%5, %6}]"
#define	__1DLAYERV1 "{%0}, [%1, {%3, %2}]"
#define	__1DLAYERV2 "{%0, %1}, [%2, {%4, %3}]"
#define	__1DLAYERV4 "{%0, %1, %2, %3}, [%4, {%6, %5}]"
#define	__3DV1 "{%0}, [%1, {%2, %3, %4, %4}]"
#define	__3DV2 "{%0, %1}, [%2, {%3, %4, %5, %5}]"
#define	__3DV4 "{%0, %1, %2, %3}, [%4, {%5, %6, %7, %7}]"
#define	__2DLAYERV1 "{%0}, [%1, {%4, %2, %3, %3}]"
#define	__2DLAYERV2 "{%0, %1}, [%2, {%5, %3, %4, %4}]"
#define	__2DLAYERV4 "{%0, %1, %2, %3}, [%4, {%7, %5, %6, %6}]"
#define	__CUBEMAPV1 "{%0}, [%1, {%4, %2, %3, %3}]"
#define	__CUBEMAPV2 "{%0, %1}, [%2, {%5, %3, %4, %4}]"
#define	__CUBEMAPV4 "{%0, %1, %2, %3}, [%4, {%7, %5, %6, %6}]"
#define	__CUBEMAPLAYERV1 "{%0}, [%1, {%4, %2, %3, %3}]"
#define	__CUBEMAPLAYERV2 "{%0, %1}, [%2, {%5, %3, %4, %4}]"
#define	__CUBEMAPLAYERV4 "{%0, %1, %2, %3}, [%4, {%7, %5, %6, %6}]"
#define	__SURF_READXD_ALL(__xdv1, __xdv2, __xdv4, __surf_readxd_v2)
#define	__SURF_WRITE1D_V2(__asmtype, __type, __asm_op_args, __asm_args)
#define	__SURF_WRITE1DLAYERED_V2(__asmtype, __type, __asm_op_args, __asm_args)
#define	__SURF_WRITE2D_V2(__asmtype, __type, __asm_op_args, __asm_args)
#define	__SURF_WRITE2DLAYERED_V2(__asmtype, __type, __asm_op_args, __asm_args)
#define	__SURF_WRITE3D_V2(__asmtype, __type, __asm_op_args, __asm_args)
#define	__SURF_CUBEMAPWRITE_V2(__asmtype, __type, __asm_op_args, __asm_args)
#define	__SURF_CUBEMAPLAYEREDWRITE_V2(__asmtype, __type, __asm_op_args, __asm_args)
#define	__SURF_WRITEXD_V2_ALL(__xdv1, __xdv2, __xdv4, __surf_writexd_v2)
#define	__1DV1 "{%2}"
#define	__1DV2 "{%2, %3}"
#define	__1DV4 "{%2, %3, %4, %5}"
#define	__2DV1 "{%3}"
#define	__2DV2 "{%3, %4}"
#define	__2DV4 "{%3, %4, %5, %6}"
#define	__3DV1 "{%4}"
#define	__3DV2 "{%4, %5}"
#define	__3DV4 "{%4, %5, %6, %7}"

Macro Definition Documentation

◆ __1DLAYERV1

#define __1DLAYERV1 "{%0}, [%1, {%3, %2}]"

Definition at line 857 of file __clang_cuda_texture_intrinsics.h.

◆ __1DLAYERV2

#define __1DLAYERV2 "{%0, %1}, [%2, {%4, %3}]"

Definition at line 858 of file __clang_cuda_texture_intrinsics.h.

◆ __1DLAYERV4

#define __1DLAYERV4 "{%0, %1, %2, %3}, [%4, {%6, %5}]"

Definition at line 859 of file __clang_cuda_texture_intrinsics.h.

◆ __1DV1 [1/2]

#define __1DV1 "{%0}, [%1, {%2}]"

Definition at line 849 of file __clang_cuda_texture_intrinsics.h.

◆ __1DV1 [2/2]

#define __1DV1 "{%2}"

Definition at line 849 of file __clang_cuda_texture_intrinsics.h.

◆ __1DV2 [1/2]

#define __1DV2 "{%0, %1}, [%2, {%3}]"

Definition at line 850 of file __clang_cuda_texture_intrinsics.h.

◆ __1DV2 [2/2]

#define __1DV2 "{%2, %3}"

Definition at line 850 of file __clang_cuda_texture_intrinsics.h.

◆ __1DV4 [1/2]

#define __1DV4 "{%0, %1, %2, %3}, [%4, {%5}]"

Definition at line 851 of file __clang_cuda_texture_intrinsics.h.

◆ __1DV4 [2/2]

#define __1DV4 "{%2, %3, %4, %5}"

Definition at line 851 of file __clang_cuda_texture_intrinsics.h.

◆ __2DLAYERV1

#define __2DLAYERV1 "{%0}, [%1, {%4, %2, %3, %3}]"

Definition at line 865 of file __clang_cuda_texture_intrinsics.h.

◆ __2DLAYERV2

#define __2DLAYERV2 "{%0, %1}, [%2, {%5, %3, %4, %4}]"

Definition at line 866 of file __clang_cuda_texture_intrinsics.h.

◆ __2DLAYERV4

#define __2DLAYERV4 "{%0, %1, %2, %3}, [%4, {%7, %5, %6, %6}]"

Definition at line 867 of file __clang_cuda_texture_intrinsics.h.

◆ __2DV1 [1/2]

#define __2DV1 "{%0}, [%1, {%2, %3}]"

Definition at line 853 of file __clang_cuda_texture_intrinsics.h.

◆ __2DV1 [2/2]

#define __2DV1 "{%3}"

Definition at line 853 of file __clang_cuda_texture_intrinsics.h.

◆ __2DV2 [1/2]

#define __2DV2 "{%0, %1}, [%2, {%3, %4}]"

Definition at line 854 of file __clang_cuda_texture_intrinsics.h.

◆ __2DV2 [2/2]

#define __2DV2 "{%3, %4}"

Definition at line 854 of file __clang_cuda_texture_intrinsics.h.

◆ __2DV4 [1/2]

#define __2DV4 "{%0, %1, %2, %3}, [%4, {%5, %6}]"

Definition at line 855 of file __clang_cuda_texture_intrinsics.h.

◆ __2DV4 [2/2]

#define __2DV4 "{%3, %4, %5, %6}"

Definition at line 855 of file __clang_cuda_texture_intrinsics.h.

◆ __3DV1 [1/2]

#define __3DV1 "{%0}, [%1, {%2, %3, %4, %4}]"

Definition at line 861 of file __clang_cuda_texture_intrinsics.h.

◆ __3DV1 [2/2]

#define __3DV1 "{%4}"

Definition at line 861 of file __clang_cuda_texture_intrinsics.h.

◆ __3DV2 [1/2]

#define __3DV2 "{%0, %1}, [%2, {%3, %4, %5, %5}]"

Definition at line 862 of file __clang_cuda_texture_intrinsics.h.

◆ __3DV2 [2/2]

#define __3DV2 "{%4, %5}"

Definition at line 862 of file __clang_cuda_texture_intrinsics.h.

◆ __3DV4 [1/2]

#define __3DV4 "{%0, %1, %2, %3}, [%4, {%5, %6, %7, %7}]"

Definition at line 863 of file __clang_cuda_texture_intrinsics.h.

◆ __3DV4 [2/2]

#define __3DV4 "{%4, %5, %6, %7}"

Definition at line 863 of file __clang_cuda_texture_intrinsics.h.

◆ __Args

#define __Args ( ... )

Value:

__VA_ARGS__

Definition at line 266 of file __clang_cuda_texture_intrinsics.h.

◆ __ASM_OUT

#define __ASM_OUT ( __t )

Value:

("=" __t(__r.x), "=" __t(__r.y), "=" __t(__r.z), "=" __t(__r.w))

Definition at line 274 of file __clang_cuda_texture_intrinsics.h.

◆ __ASM_OUTP

#define __ASM_OUTP ( __t )

Value:

(__L(__ASM_OUT(__t)), "=h"(*__ir))

__L

#define __L(__X)

Definition __clang_cuda_texture_intrinsics.h:268

__ASM_OUT

#define __ASM_OUT(__t)

Definition __clang_cuda_texture_intrinsics.h:274

Definition at line 277 of file __clang_cuda_texture_intrinsics.h.

◆ __CUBEMAPLAYERV1

#define __CUBEMAPLAYERV1 "{%0}, [%1, {%4, %2, %3, %3}]"

Definition at line 873 of file __clang_cuda_texture_intrinsics.h.

◆ __CUBEMAPLAYERV2

#define __CUBEMAPLAYERV2 "{%0, %1}, [%2, {%5, %3, %4, %4}]"

Definition at line 874 of file __clang_cuda_texture_intrinsics.h.

◆ __CUBEMAPLAYERV4

#define __CUBEMAPLAYERV4 "{%0, %1, %2, %3}, [%4, {%7, %5, %6, %6}]"

Definition at line 875 of file __clang_cuda_texture_intrinsics.h.

◆ __CUBEMAPV1

#define __CUBEMAPV1 "{%0}, [%1, {%4, %2, %3, %3}]"

Definition at line 869 of file __clang_cuda_texture_intrinsics.h.

◆ __CUBEMAPV2

#define __CUBEMAPV2 "{%0, %1}, [%2, {%5, %3, %4, %4}]"

Definition at line 870 of file __clang_cuda_texture_intrinsics.h.

◆ __CUBEMAPV4

#define __CUBEMAPV4 "{%0, %1, %2, %3}, [%4, {%7, %5, %6, %6}]"

Definition at line 871 of file __clang_cuda_texture_intrinsics.h.

◆ __ID

#define __ID ( __op )

Value:

__Tag<__tex_op_hash(__op)>

Definition at line 198 of file __clang_cuda_texture_intrinsics.h.

◆ __IDV

#define __IDV	(		__op,
			__variant )

Value:

__Tag<10000 + __tex_op_hash(__op) * 100 + __variant>

Definition at line 201 of file __clang_cuda_texture_intrinsics.h.

◆ __IMPL_2DGATHER

#define __IMPL_2DGATHER	(		variant,
			instr )

Value:

  __IMPL_SI(__IDV("__tex2Dgather_v2", variant),                                \
            __IDV("__tex2Dgather_rmnf_v2", variant),                           \
            (float __x, float __y, int __comp), instr, "f32",                  \
            "{%0, %1, %2, %3}, [%4, {%5, %6}];", ("f"(__x), "f"(__y)));        \
  __IMPL_ALIASI(__IDV("__itex2Dgather", variant),                              \
                __IDV("__tex2Dgather_v2", variant));                           \
  __IMPL_S3SI(__IDV("__itex2Dgather_sparse", variant),                         \
              (float __x, float __y, unsigned char *__ir, int __comp),         \
              "{.reg .pred %%p0;\n\t" instr, "f32",                            \
              "{%0, %1, %2, %3}|%%p0, [%5, {%6, %7}];\n\t"                     \
              "selp.u16 %4, 1, 0, %%p0; }",                                    \
              ("f"(__x), "f"(__y)));

Definition at line 514 of file __clang_cuda_texture_intrinsics.h.

◆ __IMPL_ALIAS

#define __IMPL_ALIAS	(		__op,
			__opn )

Value:

__IMPL_ALIASI(__ID(__op), __ID(__opn))

__ID

#define __ID(__op)

Definition __clang_cuda_texture_intrinsics.h:198

__IMPL_ALIASI

#define __IMPL_ALIASI(__op, __opn)

Definition __clang_cuda_texture_intrinsics.h:369

Definition at line 371 of file __clang_cuda_texture_intrinsics.h.

◆ __IMPL_ALIASI

#define __IMPL_ALIASI	(		__op,
			__opn )

Value:

template <> struct __tex_fetch_v4<__op> : __tex_fetch_v4<__opn> {}

Definition at line 369 of file __clang_cuda_texture_intrinsics.h.

◆ __IMPL_F1

#define __IMPL_F1	(	__rt,
		__dt,
		__args,
		__asm_op,
		__asm_outs,
		__asm_args )

Value:

  template <>                                                                  \
  __device__ __rt __run<__dt>(cudaTextureObject_t __obj, __L(__args)) {        \
    __rt __r;                                                                  \
    asm(__asm_op : __L(__asm_outs) : "l"(__obj), __L(__asm_args));             \
    return __r;                                                                \
  }

Definition at line 280 of file __clang_cuda_texture_intrinsics.h.

◆ __IMPL_F3

#define __IMPL_F3	(	__args,
		__asm_op,
		__ctype,
		__asm_op_args,
		__asm_args )

Value:

  __IMPL_F1(int4, int4, __args, __asm_op ".s32." __ctype "\t" __asm_op_args,   \
            __ASM_OUT("r"), __asm_args)                                        \
  __IMPL_F1(uint4, uint4, __args, __asm_op ".u32." __ctype "\t" __asm_op_args, \
            __ASM_OUT("r"), __asm_args)                                        \
  __IMPL_F1(float4, float4, __args,                                            \
            __asm_op ".f32." __ctype "\t" __asm_op_args, __ASM_OUT("f"),       \
            __asm_args)

Definition at line 289 of file __clang_cuda_texture_intrinsics.h.

◆ __IMPL_F3N

#define __IMPL_F3N	(	__args,
		__asm_op,
		__ctype,
		__asm_op_args,
		__asm_args )

Value:

  __IMPL_F1(float4, int4, __args, __asm_op ".s32." __ctype "\t" __asm_op_args, \
            __ASM_OUT("r"), __asm_args)                                        \
  __IMPL_F1(float4, uint4, __args,                                             \
            __asm_op ".u32." __ctype "\t" __asm_op_args, __ASM_OUT("r"),       \
            __asm_args)

Definition at line 311 of file __clang_cuda_texture_intrinsics.h.

◆ __IMPL_F3S

#define __IMPL_F3S	(	__args,
		__asm_op,
		__ctype,
		__asm_op_args,
		__asm_args )

Value:

  __IMPL_F1(int4, int4, __args, __asm_op ".s32." __ctype "\t" __asm_op_args,   \
            __ASM_OUTP("r"), __asm_args)                                       \
  __IMPL_F1(uint4, uint4, __args, __asm_op ".u32." __ctype "\t" __asm_op_args, \
            __ASM_OUTP("r"), __asm_args)                                       \
  __IMPL_F1(float4, float4, __args,                                            \
            __asm_op ".f32." __ctype "\t" __asm_op_args, __ASM_OUTP("f"),      \
            __asm_args)

Definition at line 300 of file __clang_cuda_texture_intrinsics.h.

◆ __IMPL_S

#define __IMPL_S	(	__op,
		__opn,
		__args,
		__asm_op,
		__ctype,
		__asm_op_args,
		__asm_args )

Value:

__IMPL_SI(__ID(__op), __ID(__opn), __args, __asm_op, __ctype, __asm_op_args, \

__asm_args)

Definition at line 362 of file __clang_cuda_texture_intrinsics.h.

◆ __IMPL_S3

#define __IMPL_S3	(	__op,
		__args,
		__asm_op,
		__ctype,
		__asm_op_args,
		__asm_args )

Value:

__IMPL_S3I(__ID(__op), __args, __asm_op, __ctype, __asm_op_args, __asm_args)

__IMPL_S3I

#define __IMPL_S3I(__op, __args, __asm_op, __ctype, __asm_op_args, __asm_args)

Definition __clang_cuda_texture_intrinsics.h:319

Definition at line 356 of file __clang_cuda_texture_intrinsics.h.

◆ __IMPL_S3I

#define __IMPL_S3I	(	__op,
		__args,
		__asm_op,
		__ctype,
		__asm_op_args,
		__asm_args )

Value:

  template <> struct __tex_fetch_v4<__op> {                                    \
    template <class T>                                                         \
    __device__ static T __run(cudaTextureObject_t __obj, __L(__args));         \
    __IMPL_F3(__args, __asm_op, __ctype, __asm_op_args, __asm_args)            \
  }

Definition at line 319 of file __clang_cuda_texture_intrinsics.h.

◆ __IMPL_S3N

#define __IMPL_S3N	(	__op,
		__args,
		__asm_op,
		__ctype,
		__asm_op_args,
		__asm_args )

Value:

__IMPL_S3NI(__ID(__op), __args, __asm_op, __ctype, __asm_op_args, __asm_args)

__IMPL_S3NI

#define __IMPL_S3NI(__op, __args, __asm_op, __ctype, __asm_op_args, __asm_args)

Definition __clang_cuda_texture_intrinsics.h:340

Definition at line 360 of file __clang_cuda_texture_intrinsics.h.

◆ __IMPL_S3NI

#define __IMPL_S3NI	(	__op,
		__args,
		__asm_op,
		__ctype,
		__asm_op_args,
		__asm_args )

Value:

  template <> struct __tex_fetch_v4<__op> {                                    \
    template <class T>                                                         \
    __device__ static float4 __run(cudaTextureObject_t __obj, __L(__args));    \
    __IMPL_F3N(__args, __asm_op, __ctype, __asm_op_args, __asm_args)           \
  }

Definition at line 340 of file __clang_cuda_texture_intrinsics.h.

◆ __IMPL_S3S

#define __IMPL_S3S	(	__op,
		__args,
		__asm_op,
		__ctype,
		__asm_op_args,
		__asm_args )

Value:

__IMPL_S3SI(__ID(__op), __args, __asm_op, __ctype, __asm_op_args, __asm_args)

__IMPL_S3SI

#define __IMPL_S3SI(__op, __args, __asm_op, __ctype, __asm_op_args, __asm_args)

Definition __clang_cuda_texture_intrinsics.h:328

Definition at line 358 of file __clang_cuda_texture_intrinsics.h.

◆ __IMPL_S3SI

#define __IMPL_S3SI	(	__op,
		__args,
		__asm_op,
		__ctype,
		__asm_op_args,
		__asm_args )

Value:

  template <> struct __tex_fetch_v4<__op> {                                    \
    template <class T>                                                         \
    __device__ static T __run(cudaTextureObject_t __obj, __L(__args));         \
    __IMPL_F3S(__args, __asm_op, __ctype, __asm_op_args, __asm_args)           \
  }

Definition at line 328 of file __clang_cuda_texture_intrinsics.h.

◆ __IMPL_SI

#define __IMPL_SI	(	__op,
		__opn,
		__args,
		__asm_op,
		__ctype,
		__asm_op_args,
		__asm_args )

Value:

__IMPL_S3I(__op, __args, __asm_op, __ctype, __asm_op_args, __asm_args); \

__IMPL_S3NI(__opn, __args, __asm_op, __ctype, __asm_op_args, __asm_args)

Definition at line 350 of file __clang_cuda_texture_intrinsics.h.

◆ __L

#define __L ( __X )

Value:

__STRIP_PARENS(__Args __X)

__STRIP_PARENS

#define __STRIP_PARENS(__X)

Definition __clang_cuda_texture_intrinsics.h:267

__Args

#define __Args(...)

Definition __clang_cuda_texture_intrinsics.h:266

Definition at line 268 of file __clang_cuda_texture_intrinsics.h.

Referenced by _mm512_set_epi32(), _mm512_set_ps(), and return().

◆ __nv_tex_surf_handler

#define __nv_tex_surf_handler	(	__op,
		__ptr,
		... )

Value:

  ::__cuda_tex::__tex_fetch<                                                   \
      ::__cuda_tex::__Tag<::__cuda_tex::__tex_op_hash(__op)>>(__ptr,           \
                                                              __VA_ARGS__)

Definition at line 21 of file __clang_cuda_texture_intrinsics.h.

◆ __OP_TYPE_SURFACE

#define __OP_TYPE_SURFACE ( __op )

Value:

  template <> struct __op_type_traits<__op> {                                  \
    using type = __surface_op_tag;                                             \
  }

Definition at line 257 of file __clang_cuda_texture_intrinsics.h.

◆ __STRIP_PARENS

#define __STRIP_PARENS ( __X )

Value:

__X

Definition at line 267 of file __clang_cuda_texture_intrinsics.h.

◆ __SURF_CUBEMAPLAYEREDWRITE_V2

#define __SURF_CUBEMAPLAYEREDWRITE_V2	(	__asmtype,
		__type,
		__asm_op_args,
		__asm_args )

Value:

  __SURF_WRITE_V2(__ID("__isurfCubemapLayeredwrite_v2"), "a2d", __asmtype,     \
                  __type, "{%3, %1, %2, %2}", (int x, int y, int layerface),   \
                  ("r"(x), "r"(y), "r"(layerface)), __asm_op_args, __asm_args)

Definition at line 949 of file __clang_cuda_texture_intrinsics.h.

◆ __SURF_CUBEMAPWRITE_V2

#define __SURF_CUBEMAPWRITE_V2	(	__asmtype,
		__type,
		__asm_op_args,
		__asm_args )

Value:

  __SURF_WRITE_V2(__ID("__isurfCubemapwrite_v2"), "a2d", __asmtype, __type,    \
                  "{%3, %1, %2, %2}", (int x, int y, int face),                \
                  ("r"(x), "r"(y), "r"(face)), __asm_op_args, __asm_args)

Definition at line 945 of file __clang_cuda_texture_intrinsics.h.

◆ __SURF_READ1D

#define __SURF_READ1D	(	__asmtype,
		__type,
		__asm_op_args,
		__asm_args )

Value:

__SURF_READ_V2(__ID("__isurf1Dread"), "1d", __asmtype, __type, \

__asm_op_args, __asm_args, (int x), ("r"(x)))

__SURF_READ_V2

#define __SURF_READ_V2(__op, __asm_dim, __asmtype, __type, __asm_op_args, __asm_args, __index_args, __index_asm_args)

Definition __clang_cuda_texture_intrinsics.h:785

Definition at line 820 of file __clang_cuda_texture_intrinsics.h.

◆ __SURF_READ1DLAYERED

#define __SURF_READ1DLAYERED	(	__asmtype,
		__type,
		__asm_op_args,
		__asm_args )

Value:

  __SURF_READ_V2(__ID("__isurf1DLayeredread"), "a1d", __asmtype, __type,       \
                 __asm_op_args, __asm_args, (int x, int layer),                \
                 ("r"(x), "r"(layer)))

Definition at line 831 of file __clang_cuda_texture_intrinsics.h.

◆ __SURF_READ2D

#define __SURF_READ2D	(	__asmtype,
		__type,
		__asm_op_args,
		__asm_args )

Value:

__SURF_READ_V2(__ID("__isurf2Dread"), "2d", __asmtype, __type, \

__asm_op_args, __asm_args, (int x, int y), ("r"(x), "r"(y)))

Definition at line 823 of file __clang_cuda_texture_intrinsics.h.

◆ __SURF_READ2DLAYERED

#define __SURF_READ2DLAYERED	(	__asmtype,
		__type,
		__asm_op_args,
		__asm_args )

Value:

  __SURF_READ_V2(__ID("__isurf2DLayeredread"), "a2d", __asmtype, __type,       \
                 __asm_op_args, __asm_args, (int x, int y, int layer),         \
                 ("r"(x), "r"(y), "r"(layer)))

Definition at line 835 of file __clang_cuda_texture_intrinsics.h.

◆ __SURF_READ3D

#define __SURF_READ3D	(	__asmtype,
		__type,
		__asm_op_args,
		__asm_args )

Value:

  __SURF_READ_V2(__ID("__isurf3Dread"), "3d", __asmtype, __type,               \
                 __asm_op_args, __asm_args, (int x, int y, int z),             \
                 ("r"(x), "r"(y), "r"(z)))

Definition at line 826 of file __clang_cuda_texture_intrinsics.h.

◆ __SURF_READ_V2

#define __SURF_READ_V2	(	__op,
		__asm_dim,
		__asmtype,
		__type,
		__asm_op_args,
		__asm_args,
		__index_args,
		__index_asm_args )

Value:

  template <> struct __surf_read_write_v2<__op, __type> {                      \
    static __device__ void __run(__type *__ptr, cudaSurfaceObject_t obj,       \
                                 __L(__index_args),                            \
                                 cudaSurfaceBoundaryMode mode) {               \
      switch (mode) {                                                          \
      case cudaBoundaryModeZero:                                               \
        asm("suld.b." __asm_dim "." __asmtype ".zero " __asm_op_args ";"       \
            : __L(__asm_args)                                                  \
            : "l"(obj), __L(__index_asm_args));                                \
        break;                                                                 \
      case cudaBoundaryModeClamp:                                              \
        asm("suld.b." __asm_dim "." __asmtype ".clamp " __asm_op_args ";"      \
            : __L(__asm_args)                                                  \
            : "l"(obj), __L(__index_asm_args));                                \
        break;                                                                 \
      case cudaBoundaryModeTrap:                                               \
        asm("suld.b." __asm_dim "." __asmtype ".trap " __asm_op_args ";"       \
            : __L(__asm_args)                                                  \
            : "l"(obj), __L(__index_asm_args));                                \
        break;                                                                 \
      }                                                                        \
    }                                                                          \
  }

Definition at line 785 of file __clang_cuda_texture_intrinsics.h.

◆ __SURF_READCUBEMAP

#define __SURF_READCUBEMAP	(	__asmtype,
		__type,
		__asm_op_args,
		__asm_args )

Value:

  __SURF_READ_V2(__ID("__isurfCubemapread"), "a2d", __asmtype, __type,         \
                 __asm_op_args, __asm_args, (int x, int y, int face),          \
                 ("r"(x), "r"(y), "r"(face)))

Definition at line 839 of file __clang_cuda_texture_intrinsics.h.

◆ __SURF_READCUBEMAPLAYERED

#define __SURF_READCUBEMAPLAYERED	(	__asmtype,
		__type,
		__asm_op_args,
		__asm_args )

Value:

  __SURF_READ_V2(__ID("__isurfCubemapLayeredread"), "a2d", __asmtype, __type,  \
                 __asm_op_args, __asm_args, (int x, int y, int layerface),     \
                 ("r"(x), "r"(y), "r"(layerface)))

Definition at line 843 of file __clang_cuda_texture_intrinsics.h.

◆ __SURF_READXD_ALL

#define __SURF_READXD_ALL	(	__xdv1,
		__xdv2,
		__xdv4,
		__surf_readxd_v2 )

Definition at line 877 of file __clang_cuda_texture_intrinsics.h.

◆ __SURF_WRITE1D_V2

#define __SURF_WRITE1D_V2	(	__asmtype,
		__type,
		__asm_op_args,
		__asm_args )

Value:

__SURF_WRITE_V2(__ID("__isurf1Dwrite_v2"), "1d", __asmtype, __type, "{%1}", \

(int x), ("r"(x)), __asm_op_args, __asm_args)

Definition at line 925 of file __clang_cuda_texture_intrinsics.h.

◆ __SURF_WRITE1DLAYERED_V2

#define __SURF_WRITE1DLAYERED_V2	(	__asmtype,
		__type,
		__asm_op_args,
		__asm_args )

Value:

  __SURF_WRITE_V2(__ID("__isurf1DLayeredwrite_v2"), "a1d", __asmtype, __type,  \
                  "{%2, %1}", (int x, int layer), ("r"(x), "r"(layer)),        \
                  __asm_op_args, __asm_args)

Definition at line 928 of file __clang_cuda_texture_intrinsics.h.

◆ __SURF_WRITE2D_V2

#define __SURF_WRITE2D_V2	(	__asmtype,
		__type,
		__asm_op_args,
		__asm_args )

Value:

  __SURF_WRITE_V2(__ID("__isurf2Dwrite_v2"), "2d", __asmtype, __type,          \
                  "{%1, %2}", (int x, int y), ("r"(x), "r"(y)), __asm_op_args, \
                  __asm_args)

Definition at line 932 of file __clang_cuda_texture_intrinsics.h.

◆ __SURF_WRITE2DLAYERED_V2

#define __SURF_WRITE2DLAYERED_V2	(	__asmtype,
		__type,
		__asm_op_args,
		__asm_args )

Value:

  __SURF_WRITE_V2(__ID("__isurf2DLayeredwrite_v2"), "a2d", __asmtype, __type,  \
                  "{%3, %1, %2, %2}", (int x, int y, int layer),               \
                  ("r"(x), "r"(y), "r"(layer)), __asm_op_args, __asm_args)

Definition at line 936 of file __clang_cuda_texture_intrinsics.h.

◆ __SURF_WRITE3D_V2

#define __SURF_WRITE3D_V2	(	__asmtype,
		__type,
		__asm_op_args,
		__asm_args )

Value:

  __SURF_WRITE_V2(__ID("__isurf3Dwrite_v2"), "3d", __asmtype, __type,          \
                  "{%1, %2, %3, %3}", (int x, int y, int z),                   \
                  ("r"(x), "r"(y), "r"(z)), __asm_op_args, __asm_args)

Definition at line 940 of file __clang_cuda_texture_intrinsics.h.

◆ __SURF_WRITE_V2

#define __SURF_WRITE_V2	(	__op,
		__asm_dim,
		__asmtype,
		__type,
		__index_op_args,
		__index_args,
		__index_asm_args,
		__asm_op_args,
		__asm_args )

Value:

  template <> struct __surf_read_write_v2<__op, __type> {                      \
    static __device__ void __run(__type *__ptr, cudaSurfaceObject_t obj,       \
                                 __L(__index_args),                            \
                                 cudaSurfaceBoundaryMode mode) {               \
      switch (mode) {                                                          \
      case cudaBoundaryModeZero:                                               \
        asm volatile("sust.b." __asm_dim "." __asmtype                         \
                     ".zero [%0, " __index_op_args "], " __asm_op_args ";"     \
                     :                                                         \
                     : "l"(obj), __L(__index_asm_args), __L(__asm_args));      \
        break;                                                                 \
      case cudaBoundaryModeClamp:                                              \
        asm volatile("sust.b." __asm_dim "." __asmtype                         \
                     ".clamp [%0, " __index_op_args "], " __asm_op_args ";"    \
                     :                                                         \
                     : "l"(obj), __L(__index_asm_args), __L(__asm_args));      \
        break;                                                                 \
      case cudaBoundaryModeTrap:                                               \
        asm volatile("sust.b." __asm_dim "." __asmtype                         \
                     ".trap [%0, " __index_op_args "], " __asm_op_args ";"     \
                     :                                                         \
                     : "l"(obj), __L(__index_asm_args), __L(__asm_args));      \
        break;                                                                 \
      }                                                                        \
    }                                                                          \
  }

Definition at line 755 of file __clang_cuda_texture_intrinsics.h.

◆ __SURF_WRITEXD_V2_ALL

#define __SURF_WRITEXD_V2_ALL	(	__xdv1,
		__xdv2,
		__xdv4,
		__surf_writexd_v2 )

Definition at line 955 of file __clang_cuda_texture_intrinsics.h.

◆ __SW_ASM_ARGS

#define __SW_ASM_ARGS ( __type )

Value:

(__type(*__ptr))

Definition at line 814 of file __clang_cuda_texture_intrinsics.h.

◆ __SW_ASM_ARGS1

#define __SW_ASM_ARGS1 ( __type )

Value:

(__type(__ptr->x))

Definition at line 815 of file __clang_cuda_texture_intrinsics.h.

◆ __SW_ASM_ARGS2

#define __SW_ASM_ARGS2 ( __type )

Value:

(__type(__ptr->x), __type(__ptr->y))

Definition at line 816 of file __clang_cuda_texture_intrinsics.h.

◆ __SW_ASM_ARGS4

#define __SW_ASM_ARGS4 ( __type )

Value:

(__type(__ptr->x), __type(__ptr->y), __type(__ptr->z), __type(__ptr->w))

Definition at line 817 of file __clang_cuda_texture_intrinsics.h.

Namespaces

Macros

Macro Definition Documentation

◆ __1DLAYERV1

◆ __1DLAYERV2

◆ __1DLAYERV4

◆ __1DV1 [1/2]

◆ __1DV1 [2/2]

◆ __1DV2 [1/2]

◆ __1DV2 [2/2]

◆ __1DV4 [1/2]

◆ __1DV4 [2/2]

◆ __2DLAYERV1

◆ __2DLAYERV2

◆ __2DLAYERV4

◆ __2DV1 [1/2]

◆ __2DV1 [2/2]

◆ __2DV2 [1/2]

◆ __2DV2 [2/2]

◆ __2DV4 [1/2]

◆ __2DV4 [2/2]

◆ __3DV1 [1/2]

◆ __3DV1 [2/2]

◆ __3DV2 [1/2]

◆ __3DV2 [2/2]

◆ __3DV4 [1/2]

◆ __3DV4 [2/2]

◆ __Args

◆ __ASM_OUT

◆ __ASM_OUTP

◆ __CUBEMAPLAYERV1

◆ __CUBEMAPLAYERV2

◆ __CUBEMAPLAYERV4

◆ __CUBEMAPV1

◆ __CUBEMAPV2

◆ __CUBEMAPV4

◆ __ID

◆ __IDV

◆ __IMPL_2DGATHER

◆ __IMPL_ALIAS

◆ __IMPL_ALIASI

◆ __IMPL_F1

◆ __IMPL_F3

◆ __IMPL_F3N

◆ __IMPL_F3S

◆ __IMPL_S

◆ __IMPL_S3

◆ __IMPL_S3I

◆ __IMPL_S3N

◆ __IMPL_S3NI

◆ __IMPL_S3S

◆ __IMPL_S3SI

◆ __IMPL_SI

◆ __L

◆ __nv_tex_surf_handler

◆ __OP_TYPE_SURFACE

◆ __STRIP_PARENS

◆ __SURF_CUBEMAPLAYEREDWRITE_V2

◆ __SURF_CUBEMAPWRITE_V2

◆ __SURF_READ1D

◆ __SURF_READ1DLAYERED

◆ __SURF_READ2D

◆ __SURF_READ2DLAYERED

◆ __SURF_READ3D

◆ __SURF_READ_V2

◆ __SURF_READCUBEMAP

◆ __SURF_READCUBEMAPLAYERED

◆ __SURF_READXD_ALL

◆ __SURF_WRITE1D_V2

◆ __SURF_WRITE1DLAYERED_V2

◆ __SURF_WRITE2D_V2

◆ __SURF_WRITE2DLAYERED_V2

◆ __SURF_WRITE3D_V2

◆ __SURF_WRITE_V2

◆ __SURF_WRITEXD_V2_ALL

◆ __SW_ASM_ARGS

◆ __SW_ASM_ARGS1

◆ __SW_ASM_ARGS2

◆ __SW_ASM_ARGS4