[SYCLomatic] Migrate the cudaCpuDeviceId defined macro. (#2725)

Signed-off-by: Chen, Sheng S <[email protected]>

Author: ShengchenJ

clang/lib/DPCT/RuleInfra/MapNames.cpp

@@ -290,6 +290,10 @@ void MapNames::setExplicitNamespaceMap(
       {"CubDebugExit",
        MacroMigrationRule("dpct_build_in_macro_rule", RulePriority::Fallback,
                           "CubDebugExit", MapNames::getCheckErrorMacroName())},
+      {"cudaCpuDeviceId",
+       MacroMigrationRule("cudaCpuDeviceId", RulePriority::Fallback,
+                          "cudaCpuDeviceId",
+                          getDpctNamespace() + "get_cpu_device_id()")},
       //...
   };
   // Type names mapping.

clang/runtime/dpct-rt/include/dpct/device.hpp

@@ -953,6 +953,10 @@ static inline unsigned int get_device_id(const sycl::device &dev){
   return dev_mgr::instance().get_device_id(dev);
 }
 
+static inline unsigned int get_cpu_device_id() {
+  return get_device_id(cpu_device());
+}
+
 /// Util function to do implicit sync among queues of the same device then
 /// insert a synchronize barrier in the queue. For USM, If the queue is the
 /// default in-order queue, try to sync with all queues available in the current

clang/test/dpct/memory_management_restricted.cu

@@ -92,6 +92,9 @@ int main(){
     // CHECK: MY_ERROR_CHECKER(DPCT_CHECK_ERROR(dpct::cpu_device().in_order_queue().prefetch(a,100)));
     MY_ERROR_CHECKER(cudaMemPrefetchAsync(a, 100, cudaCpuDeviceId, nullptr));
 
+    // CHECK: int dev_id = dpct::get_cpu_device_id();
+    int dev_id = cudaCpuDeviceId;
+
     //CHECK: stream_array[0]->memcpy(h_A, d_A, size2);
     cudaMemcpyAsync(h_A, d_A, size2, cudaMemcpyDeviceToHost, stream_array[0]);