[clang] [CIR] Upstream CUDA mangling test with LLVM and OGCG verification (PR #184444)

[Akimasa Watanuki via cfe-commits]

================
@@ -0,0 +1,132 @@
+// REQUIRES: nvptx-registered-target
+
+// RUN: %if cir-enabled %{ %clang_cc1 -triple x86_64-unknown-linux-gnu -fclangir -x cuda -emit-cir -target-sdk-version=12.3 %s -o %t.cir %}
+// RUN: %if cir-enabled %{ FileCheck --check-prefix=CIR-HOST --input-file=%t.cir %s %}
+// RUN: %if cir-enabled %{ %clang_cc1 -triple nvptx64-nvidia-cuda -fclangir -fcuda-is-device -emit-cir -target-sdk-version=12.3 %s -o %t.cir %}
+// RUN: %if cir-enabled %{ FileCheck --check-prefix=CIR-DEVICE --input-file=%t.cir %s %}
+
+// RUN: %if cir-enabled %{ %clang_cc1 -triple x86_64-unknown-linux-gnu -fclangir -x cuda -emit-llvm -target-sdk-version=12.3 %s -o %t.ll %}
+// RUN: %if cir-enabled %{ FileCheck --check-prefix=LLVM-HOST --input-file=%t.ll %s %}
+// RUN: %if cir-enabled %{ %clang_cc1 -triple nvptx64-nvidia-cuda -fclangir -fcuda-is-device -emit-llvm -target-sdk-version=12.3 %s -o %t.ll %}
+// RUN: %if cir-enabled %{ FileCheck --check-prefix=LLVM-DEVICE --input-file=%t.ll %s %}
+
+// RUN: %clang_cc1 -triple x86_64-unknown-linux-gnu -x cuda -emit-llvm -target-sdk-version=12.3 %s -o %t.ll
+// RUN: FileCheck --check-prefix=OGCG-HOST --input-file=%t.ll %s
+// RUN: %clang_cc1 -triple nvptx64-nvidia-cuda -fcuda-is-device -emit-llvm -target-sdk-version=12.3 %s -o %t.ll
+// RUN: FileCheck --check-prefix=OGCG-DEVICE --input-file=%t.ll %s
+
+#include "Inputs/cuda.h"
+
+namespace ns {
+
+// CIR-HOST:   cir.func {{.*}} @_ZN2ns36__device_stub__cpp_global_function_1EiPif
+// CIR-DEVICE: cir.func {{.*}} @_ZN2ns21cpp_global_function_1EiPif
+// LLVM-HOST:  define {{.*}} @_ZN2ns36__device_stub__cpp_global_function_1EiPif
+// LLVM-DEVICE: define {{.*}} @_ZN2ns21cpp_global_function_1EiPif
+// OGCG-HOST:  define {{.*}} @_ZN2ns36__device_stub__cpp_global_function_1EiPif
+// OGCG-DEVICE: define {{.*}} @_ZN2ns21cpp_global_function_1EiPif
+    __global__ void cpp_global_function_1(int a, int* b, float c) {}
+
+// CIR-HOST:   cir.func {{.*}} @_ZN2ns36__device_stub__cpp_global_function_2EiPif
+// CIR-DEVICE: cir.func {{.*}} @_ZN2ns21cpp_global_function_2EiPif
+// LLVM-HOST:  define {{.*}} @_ZN2ns36__device_stub__cpp_global_function_2EiPif
+// LLVM-DEVICE: define {{.*}} @_ZN2ns21cpp_global_function_2EiPif
+// OGCG-HOST:  define {{.*}} @_ZN2ns36__device_stub__cpp_global_function_2EiPif
+// OGCG-DEVICE: define {{.*}} @_ZN2ns21cpp_global_function_2EiPif
+    __global__ void cpp_global_function_2(int a, int* b, float c) {}
+
+// CIR-HOST:  cir.func {{.*}} @_ZN2ns19cpp_host_function_1EiPif
+// LLVM-HOST: define {{.*}} @_ZN2ns19cpp_host_function_1EiPif
+// OGCG-HOST: define {{.*}} @_ZN2ns19cpp_host_function_1EiPif
+    __host__ void cpp_host_function_1(int a, int* b, float c) {}
+
+// CIR-HOST:  cir.func {{.*}} @_ZN2ns19cpp_host_function_2EiPif
+// LLVM-HOST: define {{.*}} @_ZN2ns19cpp_host_function_2EiPif
+// OGCG-HOST: define {{.*}} @_ZN2ns19cpp_host_function_2EiPif
+    __host__ void cpp_host_function_2(int a, int* b, float c) {}
+
+// CIR-DEVICE:  cir.func {{.*}} @_ZN2ns21cpp_device_function_1EiPif
+// LLVM-DEVICE: define {{.*}} @_ZN2ns21cpp_device_function_1EiPif
+// OGCG-DEVICE: define {{.*}} @_ZN2ns21cpp_device_function_1EiPif
+    __device__ void cpp_device_function_1(int a, int* b, float c) {}
+
+// CIR-DEVICE:  cir.func {{.*}} @_ZN2ns21cpp_device_function_2EiPif
+// LLVM-DEVICE: define {{.*}} @_ZN2ns21cpp_device_function_2EiPif
+// OGCG-DEVICE: define {{.*}} @_ZN2ns21cpp_device_function_2EiPif
+    __device__ void cpp_device_function_2(int a, int* b, float c) {}
+}
----------------
Men-cotton wrote:

ultra nit

```suggestion
} // namespace ns
```

https://github.com/llvm/llvm-project/pull/184444