Mercurial > hg > CbC > CbC_llvm

annotate clang/test/CodeGenCUDA/function-overload.cu @ 236:c4bab56944e8 llvm-original

Find changesets by keywords (author, files, the commit message), revision number or hash, or revset expression.
LLVM 16
author kono
date Wed, 09 Nov 2022 17:45:10 +0900
parents 79ff65ed7e25
children
Ignore whitespace changes - Everywhere: Within whitespace: At end of lines:
rev   line source
150
anatofuz
parents:
diff changeset
1 // REQUIRES: x86-registered-target
anatofuz
parents:
diff changeset
2 // REQUIRES: nvptx-registered-target
anatofuz
parents:
diff changeset
3
anatofuz
parents:
diff changeset
4 // Make sure we handle target overloads correctly. Most of this is checked in
anatofuz
parents:
diff changeset
5 // sema, but special functions like constructors and destructors are here.
anatofuz
parents:
diff changeset
6 //
anatofuz
parents:
diff changeset
7 // RUN: %clang_cc1 -triple x86_64-unknown-linux-gnu -emit-llvm -o - %s \
anatofuz
parents:
diff changeset
8 // RUN: | FileCheck -check-prefix=CHECK-BOTH -check-prefix=CHECK-HOST %s
anatofuz
parents:
diff changeset
9 // RUN: %clang_cc1 -triple nvptx64-nvidia-cuda -fcuda-is-device -emit-llvm -o - %s \
anatofuz
parents:
diff changeset
10 // RUN: | FileCheck -check-prefix=CHECK-BOTH -check-prefix=CHECK-DEVICE %s
anatofuz
parents:
diff changeset
11
anatofuz
parents:
diff changeset
12 #include "Inputs/cuda.h"
anatofuz
parents:
diff changeset
13
anatofuz
parents:
diff changeset
14 // Check constructors/destructors for D/H functions
221
79ff65ed7e25 LLVM12 Original
Shinji KONO <kono@ie.u-ryukyu.ac.jp>
parents: 150
diff changeset
15 #ifdef __CUDA_ARCH__
79ff65ed7e25 LLVM12 Original
Shinji KONO <kono@ie.u-ryukyu.ac.jp>
parents: 150
diff changeset
16 __device__
79ff65ed7e25 LLVM12 Original
Shinji KONO <kono@ie.u-ryukyu.ac.jp>
parents: 150
diff changeset
17 #endif
150
anatofuz
parents:
diff changeset
18 int x;
anatofuz
parents:
diff changeset
19 struct s_cd_dh {
anatofuz
parents:
diff changeset
20 __host__ s_cd_dh() { x = 11; }
anatofuz
parents:
diff changeset
21 __device__ s_cd_dh() { x = 12; }
anatofuz
parents:
diff changeset
22 };
anatofuz
parents:
diff changeset
23
anatofuz
parents:
diff changeset
24 struct s_cd_hd {
anatofuz
parents:
diff changeset
25 __host__ __device__ s_cd_hd() { x = 31; }
anatofuz
parents:
diff changeset
26 __host__ __device__ ~s_cd_hd() { x = 32; }
anatofuz
parents:
diff changeset
27 };
anatofuz
parents:
diff changeset
28
221
79ff65ed7e25 LLVM12 Original
Shinji KONO <kono@ie.u-ryukyu.ac.jp>
parents: 150
diff changeset
29 // CHECK-BOTH: define{{.*}} void @_Z7wrapperv
150
anatofuz
parents:
diff changeset
30 #if defined(__CUDA_ARCH__)
anatofuz
parents:
diff changeset
31 __device__
anatofuz
parents:
diff changeset
32 #else
anatofuz
parents:
diff changeset
33 __host__
anatofuz
parents:
diff changeset
34 #endif
anatofuz
parents:
diff changeset
35 void wrapper() {
anatofuz
parents:
diff changeset
36 s_cd_dh scddh;
anatofuz
parents:
diff changeset
37 // CHECK-BOTH: call void @_ZN7s_cd_dhC1Ev(
anatofuz
parents:
diff changeset
38 s_cd_hd scdhd;
anatofuz
parents:
diff changeset
39 // CHECK-BOTH: call void @_ZN7s_cd_hdC1Ev
anatofuz
parents:
diff changeset
40
anatofuz
parents:
diff changeset
41 // CHECK-BOTH: call void @_ZN7s_cd_hdD1Ev(
anatofuz
parents:
diff changeset
42 }
anatofuz
parents:
diff changeset
43 // CHECK-BOTH: ret void
anatofuz
parents:
diff changeset
44
anatofuz
parents:
diff changeset
45 // Now it's time to check what's been generated for the methods we used.
anatofuz
parents:
diff changeset
46
anatofuz
parents:
diff changeset
47 // CHECK-BOTH: define linkonce_odr void @_ZN7s_cd_dhC2Ev(
anatofuz
parents:
diff changeset
48 // CHECK-HOST: store i32 11,
anatofuz
parents:
diff changeset
49 // CHECK-DEVICE: store i32 12,
anatofuz
parents:
diff changeset
50 // CHECK-BOTH: ret void
anatofuz
parents:
diff changeset
51
anatofuz
parents:
diff changeset
52 // CHECK-BOTH: define linkonce_odr void @_ZN7s_cd_hdC2Ev(
anatofuz
parents:
diff changeset
53 // CHECK-BOTH: store i32 31,
anatofuz
parents:
diff changeset
54 // CHECK-BOTH: ret void
anatofuz
parents:
diff changeset
55
anatofuz
parents:
diff changeset
56 // CHECK-BOTH: define linkonce_odr void @_ZN7s_cd_hdD2Ev(
anatofuz
parents:
diff changeset
57 // CHECK-BOTH: store i32 32,
anatofuz
parents:
diff changeset
58 // CHECK-BOTH: ret void