Address SDL issues (#613)

* Address SDL issues
This change tries to address below SDL issues:
T31: Validate all forms of input
T159: Follow best practices for secure error and exception handling

Author: drprajap

lib/ExecutionEngine/LEVELZERORUNTIME/LevelZeroRuntimeWrappers.cpp

@@ -203,7 +203,7 @@ static void *allocDeviceMemory(GPUL0QUEUE *queue, size_t size, size_t alignment,
 }
 
 static void deallocDeviceMemory(GPUL0QUEUE *queue, void *ptr) {
-  zeMemFree(queue->zeContext_, ptr);
+  CHECK_ZE_RESULT(zeMemFree(queue->zeContext_, ptr));
 }
 
 static ze_module_handle_t loadModule(GPUL0QUEUE *queue, const void *data,

lib/ExecutionEngine/SYCLRUNTIME/SyclRuntimeWrappers.cpp

@@ -136,6 +136,10 @@ static void *allocDeviceMemory(GPUSYCLQUEUE *queue, size_t size,
   } else {
     memPtr = sycl::aligned_alloc_device(alignment, size, queue->syclQueue_);
   }
+  if (memPtr == nullptr) {
+    throw std::runtime_error(
+        "aligned_alloc_shared() failed to allocate memory!");
+  }
   return memPtr;
 }
 
@@ -277,35 +281,56 @@ extern "C" SYCL_RUNTIME_EXPORT void gpuStreamDestroy(GPUSYCLQUEUE *queue) {
 
 extern "C" SYCL_RUNTIME_EXPORT void *
 gpuMemAlloc(GPUSYCLQUEUE *queue, size_t size, size_t alignment, bool isShared) {
-  return catchAll(
-      [&]() { return allocDeviceMemory(queue, size, alignment, isShared); });
+  return catchAll([&]() {
+    if (queue) {
+      return allocDeviceMemory(queue, size, alignment, isShared);
+    }
+  });
 }
 
 extern "C" SYCL_RUNTIME_EXPORT void gpuMemFree(GPUSYCLQUEUE *queue, void *ptr) {
-  catchAll([&]() { deallocDeviceMemory(queue, ptr); });
+  catchAll([&]() {
+    if (queue && ptr) {
+      deallocDeviceMemory(queue, ptr);
+    }
+  });
 }
 
 extern "C" SYCL_RUNTIME_EXPORT ze_module_handle_t
 gpuModuleLoad(GPUSYCLQUEUE *queue, const void *data, size_t dataSize) {
-  return catchAll([&]() { return loadModule(queue, data, dataSize); });
+  return catchAll([&]() {
+    if (queue) {
+      return loadModule(queue, data, dataSize);
+    }
+  });
 }
 
 extern "C" SYCL_RUNTIME_EXPORT sycl::kernel *
 gpuKernelGet(GPUSYCLQUEUE *queue, ze_module_handle_t module, const char *name) {
-  return catchAll([&]() { return getKernel(queue, module, name); });
+  return catchAll([&]() {
+    if (queue) {
+      return getKernel(queue, module, name);
+    }
+  });
 }
 
 extern "C" SYCL_RUNTIME_EXPORT void
 gpuLaunchKernel(GPUSYCLQUEUE *queue, sycl::kernel *kernel, size_t gridX,
                 size_t gridY, size_t gridZ, size_t blockX, size_t blockY,
                 size_t blockZ, size_t sharedMemBytes, void *params) {
   return catchAll([&]() {
-    launchKernel(queue, kernel, gridX, gridY, gridZ, blockX, blockY, blockZ,
-                 sharedMemBytes, static_cast<ParamDesc *>(params));
+    if (queue) {
+      launchKernel(queue, kernel, gridX, gridY, gridZ, blockX, blockY, blockZ,
+                   sharedMemBytes, static_cast<ParamDesc *>(params));
+    }
   });
 }
 
 extern "C" SYCL_RUNTIME_EXPORT void gpuWait(GPUSYCLQUEUE *queue) {
 
-  catchAll([&]() { queue->syclQueue_.wait(); });
+  catchAll([&]() {
+    if (queue) {
+      queue->syclQueue_.wait();
+    }
+  });
 }