Home
last modified time | relevance | path

Searched refs:__device__ (Results 1 – 25 of 69) sorted by relevance

123

/external/clang/test/SemaCUDA/
Dfunction-overload.cu40 __device__ DeviceReturnTy dh() { return DeviceReturnTy(); } in dh()
43 __host__ __device__ int hdh() { return 0; } // expected-note {{previous definition is here}} in hdh()
47 __host__ __device__ int hhd() { return 0; } // expected-error {{redefinition of 'hhd'}} in hhd()
51 __host__ __device__ int hdd() { return 0; } // expected-note {{previous definition is here}} in hdd()
52 __device__ int hdd() { return 0; } // expected-error {{redefinition of 'hdd'}} in hdd()
54 __device__ int dhd() { return 0; } // expected-note {{previous definition is here}} in dhd()
55 __host__ __device__ int dhd() { return 0; } // expected-error {{redefinition of 'dhd'}} in dhd()
64 extern "C" __device__ DeviceReturnTy cdh() { return DeviceReturnTy(); } in cdh()
68 extern "C" __host__ __device__ int chhd1() { return 0; } // expected-note {{previous definition is … in chhd1()
72 extern "C" __host__ __device__ int chhd2() { return 0; } // expected-error {{redefinition of 'chhd2… in chhd2()
[all …]
Ddevice-var-init.cu18 __device__ int d_v_f = f();
28 __device__ EC d_ec_i(3);
35 __device__ EC d_ec_i2 = {3};
42 __device__ ETC d_etc_i(3);
49 __device__ ETC d_etc_i2 = {3};
56 __device__ UC d_uc;
63 __device__ UD d_ud;
70 __device__ ECI d_eci;
77 __device__ NEC d_nec;
84 __device__ NED d_ned;
[all …]
Dbad-attributes.cu14 __device__ int a1;
15 __device__ void a2();
28 __device__ __host__ void z1();
29 __device__ __constant__ int z2;
30 __device__ __shared__ int z3;
31 __device__ __global__ void z4(); // expected-error {{attributes are not compatible}}
34 __host__ __device__ void z5();
38 __constant__ __device__ int z7;
42 __shared__ __device__ int z9;
46 __global__ __device__ void z11(); // expected-error {{attributes are not compatible}}
Dimplicit-member-target.cu27 __device__ void devicefoo() { in devicefoo()
35 __device__ A2_with_device_ctor() {} in A2_with_device_ctor()
49 __device__ void devicefoo2() { in devicefoo2()
58 __device__ A3_with_device_ctors(const A3_with_device_ctors&) {} in A3_with_device_ctors()
93 __device__ void devicefoo4() { in devicefoo4()
115 __device__ void devicefoo5(B5_copy_ctor_constness& b_arg) { in devicefoo5()
124 __device__ A6_with_device_ctor() {} in A6_with_device_ctor()
135 __device__ void devicefoo6() { in devicefoo6()
144 __device__ A7_with_copy_assign& operator=(const A7_with_copy_assign&) {} in operator =()
174 __device__ A8_with_move_assign& operator=(A8_with_move_assign&&) {} in operator =()
[all …]
Dvararg.cu13 __device__ void foo() { in foo()
26 __device__ void baz() { in baz()
33 __device__ void vararg(const char* x, ...) {} in vararg()
39 __device__ void vararg(T t, ...) {} in vararg()
44 extern "C" __device__ int printf(const char* fmt, ...); // OK, special case.
47 extern "C" __device__ int printf(const char* fmt, ...) { return 0; } in printf()
53 __device__ int printf(const char* fmt, ...);
Dmethod-target.cu12 __device__ void foo1(S1& s) { in foo1()
24 __device__ void foo2(S2& s, int i, float f) { in foo2()
32 __device__ void method() {} in method()
43 __device__ void method() {} in method()
46 __host__ __device__ void foo4(S4& s) { in foo4()
58 __device__ void foo5(S5& s, S5& t) { in foo5()
69 __device__ void foo6(S6* s) { in foo6()
Dfunction-target.cu7 __device__ void h1d(void); // expected-note {{candidate function not viable: call to __device__ fun…
8 __host__ __device__ void h1hd(void);
12 …__device__ h1ds(); // expected-note {{candidate constructor not viable: call to __device__ functio…
24 __device__ void d1d(void);
25 __host__ __device__ void d1hd(void);
28 __device__ void d1(void) { in d1()
Doverloaded-delete.cu10 __device__ static void operator delete(void*, size_t) {} in operator delete()
13 __host__ __device__ void test(S* s) { in test()
20 __device__ void operator delete(void *ptr) {} in operator delete()
22 __host__ __device__ void test_global_delete(int *ptr) { in test_global_delete()
/external/clang/test/CodeGenCUDA/Inputs/
Dcuda-initializers.h14 __device__ EC() {} // -- allowed in EC()
15 __device__ EC(int) {} // -- not allowed in EC()
20 __device__ ~ED() {} // -- allowed in ~ED()
24 __device__ ECD() {} // -- allowed in ECD()
25 __device__ ~ECD() {} // -- allowed in ~ECD()
30 template <typename... T> __device__ ETC(T...) {} in ETC()
36 __device__ UC();
42 __device__ ~UD();
48 __device__ ECI() : eci(1) {} in ECI()
54 __device__ NEC() { nec = 1; } in NEC()
[all …]
/external/clang/test/SemaCUDA/Inputs/
Dcuda-initializers.h14 __device__ EC() {} // -- allowed in EC()
15 __device__ EC(int) {} // -- not allowed in EC()
20 __device__ ~ED() {} // -- allowed in ~ED()
24 __device__ ECD() {} // -- allowed in ECD()
25 __device__ ~ECD() {} // -- allowed in ~ECD()
30 template <typename... T> __device__ ETC(T...) {} in ETC()
36 __device__ UC();
42 __device__ ~UD();
48 __device__ ECI() : eci(1) {} in ECI()
54 __device__ NEC() { nec = 1; } in NEC()
[all …]
/external/clang/lib/Headers/
D__clang_cuda_intrinsics.h38 inline __device__ int __FnName(int __in, int __offset, \
43 inline __device__ float __FnName(float __in, int __offset, \
48 inline __device__ unsigned int __FnName(unsigned int __in, int __offset, \
53 inline __device__ long long __FnName(long long __in, int __offset, \
68 inline __device__ unsigned long long __FnName( \
73 inline __device__ double __FnName(double __in, int __offset, \
103 inline __device__ char __ldg(const char *ptr) { return __nvvm_ldg_c(ptr); } in __ldg()
104 inline __device__ short __ldg(const short *ptr) { return __nvvm_ldg_s(ptr); } in __ldg()
105 inline __device__ int __ldg(const int *ptr) { return __nvvm_ldg_i(ptr); } in __ldg()
106 inline __device__ long __ldg(const long *ptr) { return __nvvm_ldg_l(ptr); } in __ldg()
[all …]
D__clang_cuda_runtime_wrapper.h143 #define __forceinline__ __device__ __inline__ __attribute__((always_inline))
184 static inline __device__ void __brkpt(int __c) { __brkpt(); } in __brkpt()
242 __device__ int vprintf(const char *, const char *);
243 __device__ void free(void *) __attribute((nothrow));
244 __device__ void *malloc(size_t) __attribute((nothrow)) __attribute__((malloc));
245 __device__ void __assertfail(const char *__message, const char *__file,
251 __device__ static inline void __assert_fail(const char *__message, in __assert_fail()
259 __device__ int printf(const char *, ...);
264 __device__ static inline void free(void *__ptr) { ::free(__ptr); } in free()
265 __device__ static inline void *malloc(size_t __size) { in malloc()
[all …]
/external/tensorflow/tensorflow/core/util/
Dcuda_device_functions.h44 __device__ Iterator(T index, T delta) : index_(index), delta_(delta) {} in Iterator()
45 __device__ T operator*() const { return index_; }
46 __device__ Iterator& operator++() {
50 __device__ bool operator!=(const Iterator& other) const {
70 __device__ CudaGridRange(T begin, T delta, T end) in CudaGridRange()
73 __device__ Iterator begin() const { return Iterator{begin_, delta_}; } in begin()
74 __device__ Iterator end() const { return Iterator{end_, 0}; } in end()
89 __device__ detail::CudaGridRange<T> CudaGridRangeX(T count) { in CudaGridRangeX()
97 __device__ detail::CudaGridRange<T> CudaGridRangeY(T count) { in CudaGridRangeY()
105 __device__ detail::CudaGridRange<T> CudaGridRangeZ(T count) { in CudaGridRangeZ()
[all …]
Dtransform_output_iterator.h34 __host__ __device__ __forceinline__ Reference(StoreType* ptr, in Reference()
39 __host__ __device__ __forceinline__ InputType operator=(InputType val) {
68 __host__ __device__ __forceinline__ TransformOutputIterator( in TransformOutputIterator()
74 __host__ __device__ __forceinline__ self_type operator++(int) {
81 __host__ __device__ __forceinline__ self_type operator++() {
87 __host__ __device__ __forceinline__ reference operator*() const {
93 __host__ __device__ __forceinline__ self_type operator+(Distance n) const {
100 __host__ __device__ __forceinline__ self_type& operator+=(Distance n) {
107 __host__ __device__ __forceinline__ self_type operator-(Distance n) const {
114 __host__ __device__ __forceinline__ self_type& operator-=(Distance n) {
[all …]
Dpermutation_input_iterator.h48 __host__ __device__ __forceinline__ PermutationInputIterator( in PermutationInputIterator()
54 __host__ __device__ __forceinline__ self_type operator++(int) {
61 __host__ __device__ __forceinline__ self_type operator++() {
67 __host__ __device__ __forceinline__ reference operator*() const {
73 __host__ __device__ __forceinline__ self_type operator+(Distance n) const {
80 __host__ __device__ __forceinline__ self_type& operator+=(Distance n) {
87 __host__ __device__ __forceinline__ self_type operator-(Distance n) const {
94 __host__ __device__ __forceinline__ self_type& operator-=(Distance n) {
100 __host__ __device__ __forceinline__ difference_type
107 __host__ __device__ __forceinline__ reference operator[](Distance n) const {
[all …]
Dcuda_kernel_helper.h32 __host__ __device__ inline tensorflow::bfloat16 CudaLdg( in CudaLdg()
40 __host__ __device__ inline T ldg(const T* ptr) { in ldg()
45 __host__ __device__ inline const T& tf_min(const T& x, const T& y) { in tf_min()
50 __host__ __device__ inline const T& tf_max(const T& x, const T& y) { in tf_max()
55 __host__ __device__ inline float tf_min(float x, float y) { in tf_min()
58 __host__ __device__ inline double tf_min(double x, double y) { in tf_min()
61 __host__ __device__ inline float tf_max(float x, float y) { in tf_max()
64 __host__ __device__ inline double tf_max(double x, double y) { in tf_max()
68 __device__ inline Eigen::half CudaShuffleSync(unsigned mask, Eigen::half value,
75 __device__ EIGEN_ALWAYS_INLINE Eigen::half CudaShuffleUpSync(
[all …]
/external/clang/test/CodeGenCUDA/
Ddevice-var-init.cu16 __device__ int d_v;
23 __device__ int d_v_i = 1;
27 __device__ T d_t;
34 __device__ T d_t_i = {2};
40 __device__ EC d_ec;
48 __device__ ED d_ed;
55 __device__ ECD d_ecd;
63 __device__ ETC d_etc;
70 __device__ NCFS d_ncfs;
76 __device__ T_B_T d_t_b_t;
[all …]
Daddress-spaces.cu9 __device__ int i;
29 __device__ void foo() { in foo()
44 __device__ void func0() { in func0()
53 __device__ void callee(float *ap) { in callee()
57 __device__ void func1() { in func1()
64 __device__ void func2() { in func2()
72 __device__ void func3() { in func3()
80 __device__ void func4() { in func4()
90 __device__ float *func5() { in func5()
Dprintf.cu9 extern "C" __device__ int vprintf(const char*, const char*);
13 __device__ int CheckSimple() { in CheckSimple()
29 __device__ void CheckNoArgs() { in CheckNoArgs()
36 __device__ bool foo();
37 __device__ void CheckAllocaIsInEntryBlock() { in CheckAllocaIsInEntryBlock()
Dfunction-overload.cu18 __device__ s_cd_dh() { x = 12; } in s_cd_dh()
20 __device__ ~s_cd_dh() { x = 22; } in ~s_cd_dh()
24 __host__ __device__ s_cd_hd() { x = 31; } in s_cd_hd()
25 __host__ __device__ ~s_cd_hd() { x = 32; } in ~s_cd_hd()
30 __device__
Ddevice-vtable.cu24 __device__ virtual void method();
38 __device__ virtual void d_method();
52 void __device__ D::method() {} in method()
55 void __device__ HD::d_method() {} in d_method()
Dlink-device-bitcode.cu39 __device__ float device_mul_or_add(float a, float b);
40 extern "C" __device__ double __nv_sin(double x);
41 extern "C" __device__ double __nv_exp(double x);
45 __device__ void should_not_be_internalized(float *data) {} in should_not_be_internalized()
/external/clang/test/CodeGen/
Dbuiltins-nvptx.c7 #define __device__ __attribute__((device)) macro
12 __device__ int read_tid() { in read_tid()
28 __device__ int read_ntid() { in read_ntid()
44 __device__ int read_ctaid() { in read_ctaid()
60 __device__ int read_nctaid() { in read_nctaid()
76 __device__ int read_ids() { in read_ids()
96 __device__ int read_lanemasks() { in read_lanemasks()
114 __device__ long long read_clocks() { in read_clocks()
125 __device__ int read_pms() { in read_pms()
141 __device__ void sync() { in sync()
[all …]
/external/tensorflow/tensorflow/core/kernels/
Dtopk_op_gpu.cu.cc71 __device__ Entry& operator[](std::size_t index) const { return data[index]; } in operator []()
73 __device__ int get_index(int i) const { return data[i].index; } in get_index()
74 __device__ T get_value(int i) const { return data[i].value; } in get_value()
83 __device__ Entry& operator[](std::size_t index) const { return data[index]; } in operator []()
85 __device__ int get_index(int i) const { in get_index()
88 __device__ T get_value(int i) const { return data[i].value; } in get_value()
99 __device__ Entry& operator[](std::size_t index) const { in operator []()
103 __device__ int get_index(int i) const { return (*this)[i].index; } in get_index()
104 __device__ T get_value(int i) const { return (*this)[i].value; } in get_value()
117 __device__ bool is_above(int left, int right) { in is_above()
[all …]
Ddeterminant_op_gpu.cu.cc33 __device__ int PermutationOrder(int n, const int* pivots) { in PermutationOrder()
49 __device__ inline std::complex<T> complex_multiply(const std::complex<T>& a, in complex_multiply()
58 __device__ inline complex64 operator*(const complex64& a, const complex64& b) { in operator *()
61 __device__ inline complex64 operator*(const complex64& a, const float& b) { in operator *()
64 __device__ inline complex64 operator/(const complex64& a, const float& b) { in operator /()
68 __device__ inline complex128 operator*(const complex128& a, in operator *()
72 __device__ inline complex128 operator*(const complex128& a, const double& b) { in operator *()
75 __device__ inline complex128 operator/(const complex128& a, const double& b) { in operator /()

123