Update on "introduce cuda stream into runtime backend"

This diff introduces CUDA streams into the Executorch runtime backend. The changes include:

* Adding CUDA stream support to the `cuda_backend.cpp` file
* Including the `cuda_runtime.h` header file in `cuda_backend.cpp`
* Adding a `void* cuda_stream` field to the `AOTInductorModelContainer` struct in `aoti_model_container.h` to store the CUDA stream
* Defining a new macro `ET_CHECK_OR_LOG` in `log.h` to check a condition and log an error message if the condition is false.

Differential Revision: [D84128173](https://our.internmc.facebook.com/intern/diff/D84128173/)

[ghstack-poisoned]

Author: Gasoonjia

backends/aoti/CMakeLists.txt

@@ -41,12 +41,7 @@ target_compile_options(aoti_common PUBLIC -fexceptions -frtti -fPIC)
 target_link_options(aoti_common PUBLIC -Wl,--export-dynamic)
 
 # Link against PyTorch libraries and standard libraries
-target_link_libraries(
-  aoti_common
-  PUBLIC extension_tensor ${CMAKE_DL_LIBS}
-         # Link PyTorch libraries for AOTI functions
-         ${TORCH_LIBRARIES}
-)
+target_link_libraries(aoti_common PUBLIC extension_tensor ${CMAKE_DL_LIBS})
 executorch_target_link_options_shared_lib(aoti_common)
 
 install(

backends/cuda/runtime/cuda_backend.cpp

@@ -345,7 +345,7 @@ class ET_EXPERIMENTAL CudaBackend final
     if (handle->cuda_stream != nullptr) {
       cudaStream_t cuda_stream = static_cast<cudaStream_t>(handle->cuda_stream);
       cudaError_t stream_err = cudaStreamDestroy(cuda_stream);
-      ET_CHECK_OR_LOG(
+      ET_CHECK_OR_LOG_ERROR(
           stream_err == cudaSuccess,
           "Failed to destroy CUDA stream: %s",
           cudaGetErrorString(stream_err));

runtime/platform/log.h

@@ -188,11 +188,11 @@ using ::executorch::runtime::LogLevel;
  * @param[in] _condition The condition to check.
  * @param[in] _format Log message format string.
  */
-#define ET_CHECK_OR_LOG(_condition, _format, ...) \
-  do {                                            \
-    if (!(_condition)) {                          \
-      ET_LOG(Error, _format, ##__VA_ARGS__);      \
-    }                                             \
+#define ET_CHECK_OR_LOG_ERROR(_condition, _format, ...) \
+  do {                                                  \
+    if (!(_condition)) {                                \
+      ET_LOG(Error, _format, ##__VA_ARGS__);            \
+    }                                                   \
   } while (0)
 
 #else // ET_LOG_ENABLED
@@ -211,6 +211,6 @@ using ::executorch::runtime::LogLevel;
  * @param[in] _condition The condition to check.
  * @param[in] _format Log message format string.
  */
-#define ET_CHECK_OR_LOG(_condition, _format, ...) ((void)0)
+#define ET_CHECK_OR_LOG_ERROR(_condition, _format, ...) ((void)0)
 
 #endif // ET_LOG_ENABLED