Merge remote-tracking branch 'origin/SYCLomatic' into remove_exp

ShengchenJ · ShengchenJ · commit ce9e7bdd79a9 · 2025-06-30T15:44:11.000+08:00
diff --git a/clang/examples/DPCT/CUB/cub$$ArgIndexInputIterator.cu b/clang/examples/DPCT/CUB/cub$$ArgIndexInputIterator.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+void test(int *d_in) {
+  // Start
+  cub::ArgIndexInputIterator<int *> Iter(d_in);
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$BFE.cu b/clang/examples/DPCT/CUB/cub$$BFE.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+__device__ void test(int input, unsigned int bit_start, unsigned int num_bits) {
+  // Start
+  cub::BFE(input/*int*/, bit_start/*unsigned int*/, num_bits/*unsigned int*/);
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$BFI.cu b/clang/examples/DPCT/CUB/cub$$BFI.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+__device__ void test(unsigned int a, unsigned int b, unsigned int c, unsigned int bit_start, unsigned int num_bits) {
+  // Start
+  cub::BFI(a/*unsigned int*/, b/*unsigned int*/, c/*unsigned int*/, bit_start/*unsigned int*/, num_bits/*unsigned int*/);
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$ConstantInputIterator.cu b/clang/examples/DPCT/CUB/cub$$ConstantInputIterator.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+void test(int d_in) {
+  // Start
+  cub::ConstantInputIterator<int> Iter(d_in);
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$CountingInputIterator.cu b/clang/examples/DPCT/CUB/cub$$CountingInputIterator.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+void test(int d_in) {
+  // Start
+  cub::CountingInputIterator<int> Iter(d_in);
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$CurrentDevice.cu b/clang/examples/DPCT/CUB/cub$$CurrentDevice.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+__device__ void test(int res) {
+  // Start
+  res = cub::CurrentDevice();
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$Debug.cu b/clang/examples/DPCT/CUB/cub$$Debug.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+__device__ void test(cudaError_t e, const char* filename, int line) {
+  // Start
+  cub::Debug(e/*cudaError_t*/, filename/*const char**/, line/*int*/);
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$DeviceCount.cu b/clang/examples/DPCT/CUB/cub$$DeviceCount.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+__device__ void test(int res) {
+  // Start
+  res = cub::DeviceCount();
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$DeviceCountCachedValue.cu b/clang/examples/DPCT/CUB/cub$$DeviceCountCachedValue.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+__device__ void test(int res) {
+  // Start
+  res = cub::DeviceCountCachedValue();
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$DeviceCountUncached.cu b/clang/examples/DPCT/CUB/cub$$DeviceCountUncached.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+__device__ void test(int res) {
+  // Start
+  res = cub::DeviceCountUncached();
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$DiscardOutputIterator.cu b/clang/examples/DPCT/CUB/cub$$DiscardOutputIterator.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+void test() {
+  // Start
+  cub::DiscardOutputIterator<int> Iter;
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$IADD3.cu b/clang/examples/DPCT/CUB/cub$$IADD3.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+__device__ void test(int result, unsigned int a, unsigned int b, unsigned int c) {
+  // Start
+  result = cub::IADD3(a/*unsigned int*/, b/*unsigned int*/, c/*unsigned int*/);
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$LaneId.cu b/clang/examples/DPCT/CUB/cub$$LaneId.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+__device__ void test(int result) {
+  // Start
+  result = cub::LaneId();
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$LoadDirectBlocked.cu b/clang/examples/DPCT/CUB/cub$$LoadDirectBlocked.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+__device__ void test(int id, int *data, int (&thread_data)[4]) {
+  // Start
+  cub::LoadDirectBlocked(id/*int*/, data/*int **/, thread_data/*int (&)[4]*/);
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$LoadDirectStriped.cu b/clang/examples/DPCT/CUB/cub$$LoadDirectStriped.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+__device__ void test(int id, int *data, int (&thread_data)[4]) {
+  // Start
+  cub::LoadDirectStriped<128>(id/*int*/, data/*int **/, thread_data/*int (&)[4]*/);
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$LoadDirectWarpStriped.cu b/clang/examples/DPCT/CUB/cub$$LoadDirectWarpStriped.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+__device__ void test(int id, int *data, int (&thread_data)[4]) {
+  // Start
+  cub::LoadDirectWarpStriped(id/*int*/, data/*int **/, thread_data/*int (&)[4]*/);
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$PtxVersion.cu b/clang/examples/DPCT/CUB/cub$$PtxVersion.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+void test(int r) {
+  // Start
+  cub::PtxVersion(r/*int*/);
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$PtxVersionUncached.cu b/clang/examples/DPCT/CUB/cub$$PtxVersionUncached.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+void test(int r) {
+  // Start
+  cub::PtxVersionUncached(r/*int*/);
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$RowMajorTid.cu b/clang/examples/DPCT/CUB/cub$$RowMajorTid.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+__device__ void test(int r, int dim_x, int dim_y, int dim_z) {
+  // Start
+  r = cub::RowMajorTid(dim_x/*int*/, dim_y/*int*/, dim_z/*int*/);
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$SHL_ADD.cu b/clang/examples/DPCT/CUB/cub$$SHL_ADD.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+__device__ void test(int res, int a, int b, int c) {
+  // Start
+  res = cub::SHL_ADD(a/*int*/, b/*int*/, c/*int*/);
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$SHR_ADD.cu b/clang/examples/DPCT/CUB/cub$$SHR_ADD.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+__device__ void test(int res, int a, int b, int c) {
+  // Start
+  res = cub::SHR_ADD(a/*int*/, b/*int*/, c/*int*/);
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$SmVersion.cu b/clang/examples/DPCT/CUB/cub$$SmVersion.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+void test(int res) {
+  // Start
+  cub::SmVersion(res/*int*/);
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$SmVersionUncached.cu b/clang/examples/DPCT/CUB/cub$$SmVersionUncached.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+void test(int res) {
+  // Start
+  cub::SmVersionUncached(res/*int*/);
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$StoreDirectBlocked.cu b/clang/examples/DPCT/CUB/cub$$StoreDirectBlocked.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+__device__ void test(int id, int *data, int (&thread_data)[4]) {
+  // Start
+  cub::StoreDirectBlocked(id/*int*/, data/*int **/, thread_data/*int (&)[4]*/);
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$StoreDirectStriped.cu b/clang/examples/DPCT/CUB/cub$$StoreDirectStriped.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+__device__ void test(int id, int *data, int (&thread_data)[4]) {
+  // Start
+  cub::StoreDirectStriped<128>(id/*int*/, data/*int **/, thread_data/*int (&)[4]*/);
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$StoreDirectWarpStriped.cu b/clang/examples/DPCT/CUB/cub$$StoreDirectWarpStriped.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+__device__ void test(int id, int *data, int (&thread_data)[4]) {
+  // Start
+  cub::StoreDirectWarpStriped(id/*int*/, data/*int **/, thread_data/*int (&)[4]*/);
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$SyncStream.cu b/clang/examples/DPCT/CUB/cub$$SyncStream.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+__device__ void test(cudaStream_t s) {
+  // Start
+  cub::SyncStream(s/*cudaStream_t*/);
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$ThreadLoad.cu b/clang/examples/DPCT/CUB/cub$$ThreadLoad.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+__device__ void test(int res, int *data) {
+  // Start
+  res = cub::ThreadLoad<cub::LOAD_CA>(data/*int **/);
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$ThreadStore.cu b/clang/examples/DPCT/CUB/cub$$ThreadStore.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+__device__ void test(int *dst, int data) {
+  // Start
+  cub::ThreadStore<cub::STORE_CG>(dst/*int **/, data/*int*/);
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$TransformInputIterator.cu b/clang/examples/DPCT/CUB/cub$$TransformInputIterator.cu
@@ -0,0 +1,15 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+struct UserDefMul {
+  __device__ double operator()(double d) const {
+    return d * 3.0;
+  }
+};
+
+void test(double *d_in, UserDefMul op) {
+  // Start
+  cub::TransformInputIterator<double, UserDefMul, double *> iter(d_in /*double **/, op /*Op*/);
+  // End
+}
diff --git a/clang/examples/DPCT/CUB/cub$$WarpId.cu b/clang/examples/DPCT/CUB/cub$$WarpId.cu
@@ -0,0 +1,9 @@
+// clang-format off
+#include <cstddef>
+#include <cub/cub.cuh>
+
+__device__ void test(int res) {
+  // Start
+  res = cub::WarpId();
+  // End
+}
diff --git a/clang/examples/DPCT/cuDNN/cudnnGetConvolutionBackwardDataAlgorithmMaxCount.cu b/clang/examples/DPCT/cuDNN/cudnnGetConvolutionBackwardDataAlgorithmMaxCount.cu
@@ -0,0 +1,9 @@
+#include <cudnn.h>
+
+void test(int max_count) {
+  // Start
+  cudnnHandle_t h;
+  cudnnCreate(&h /*cudnnHandle_t **/);
+  cudnnGetConvolutionBackwardDataAlgorithmMaxCount(h /*cudnnHandle_t */, &max_count /*int **/);
+  // End
+}
diff --git a/clang/examples/DPCT/cuDNN/cudnnGetConvolutionBackwardFilterAlgorithmMaxCount.cu b/clang/examples/DPCT/cuDNN/cudnnGetConvolutionBackwardFilterAlgorithmMaxCount.cu
@@ -0,0 +1,9 @@
+#include <cudnn.h>
+
+void test(int max_count) {
+  // Start
+  cudnnHandle_t h;
+  cudnnCreate(&h /*cudnnHandle_t **/);
+  cudnnGetConvolutionBackwardFilterAlgorithmMaxCount(h /*cudnnHandle_t */, &max_count /*int **/);
+  // End
+}
diff --git a/clang/examples/DPCT/cuDNN/cudnnGetConvolutionForwardAlgorithmMaxCount.cu b/clang/examples/DPCT/cuDNN/cudnnGetConvolutionForwardAlgorithmMaxCount.cu
@@ -0,0 +1,9 @@
+#include <cudnn.h>
+
+void test(int max_count) {
+  // Start
+  cudnnHandle_t h;
+  cudnnCreate(&h /*cudnnHandle_t **/);
+  cudnnGetConvolutionForwardAlgorithmMaxCount(h /*cudnnHandle_t */, &max_count /*int **/);
+  // End
+}
diff --git a/clang/examples/DPCT/cuDNN/cudnnGetCudartVersion.cu b/clang/examples/DPCT/cuDNN/cudnnGetCudartVersion.cu
@@ -0,0 +1,7 @@
+#include <cudnn.h>
+
+void test(size_t version) {
+  // Start
+  version /*size_t*/ = cudnnGetCudartVersion();
+  // End
+}
diff --git a/clang/lib/DPCT/RulesLang/RulesLang.cpp b/clang/lib/DPCT/RulesLang/RulesLang.cpp
diff --git a/clang/test/dpct/disable-all-extensions.cu b/clang/test/dpct/disable-all-extensions.cu
diff --git a/clang/test/dpct/event_record_with_flags_no_qb.cu b/clang/test/dpct/event_record_with_flags_no_qb.cu
diff --git a/clang/test/dpct/event_record_with_flags_qb.cu b/clang/test/dpct/event_record_with_flags_qb.cu
diff --git a/clang/test/dpct/query_api_mapping/CUB/cub_misc.cu b/clang/test/dpct/query_api_mapping/CUB/cub_misc.cu
diff --git a/clang/test/dpct/query_api_mapping/cuDNN/dnn_part3.cu b/clang/test/dpct/query_api_mapping/cuDNN/dnn_part3.cu
diff --git a/clang/test/dpct/query_api_mapping/cuSPARSE/lit_cuSPARSE_101.cu b/clang/test/dpct/query_api_mapping/cuSPARSE/lit_cuSPARSE_101.cu
diff --git a/clang/test/dpct/query_api_mapping/test_all.cu b/clang/test/dpct/query_api_mapping/test_all.cu
diff --git a/clang/test/dpct/tm-complex-profiling.cu b/clang/test/dpct/tm-complex-profiling.cu
diff --git a/clang/test/dpct/tm-nonusm-no-submit-barrier-profiling.cu b/clang/test/dpct/tm-nonusm-no-submit-barrier-profiling.cu
diff --git a/clang/test/dpct/tm-nonusm-profiling.cu b/clang/test/dpct/tm-nonusm-profiling.cu
diff --git a/clang/test/dpct/tm-usm-no-submit-barrier-profiling.cu b/clang/test/dpct/tm-usm-no-submit-barrier-profiling.cu
