[SYCL][CUDA] Lit exceptions (intel#1304)

# Conflicts:
#	sycl/test/basic_tests/image_api.cpp

Author: fwyzard

sycl/test/aot/accelerator.cpp

@@ -36,6 +36,7 @@ void simple_vadd(const std::array<T, N>& VA, const std::array<T, N>& VB,
           std::cerr << "Unknown async exception was caught." << std::endl;
         }
       }
+      throw "ERROR: Asynchronous exception(s)";
     });
 
   cl::sycl::range<1> numOfItems{N};

sycl/test/aot/cpu.cpp

@@ -36,6 +36,7 @@ void simple_vadd(const std::array<T, N>& VA, const std::array<T, N>& VB,
           std::cerr << "Unknown async exception was caught." << std::endl;
         }
       }
+      throw "ERROR: Asynchronous exception(s)";
     });
 
   cl::sycl::range<1> numOfItems{N};

sycl/test/aot/gpu.cpp

@@ -38,6 +38,7 @@ void simple_vadd(const std::array<T, N>& VA, const std::array<T, N>& VB,
           std::cerr << "Unknown async exception was caught." << std::endl;
         }
       }
+      throw "ERROR: Asynchronous exception(s)";
     });
 
   cl::sycl::range<1> numOfItems{N};

sycl/test/aot/multiple-devices.cpp

@@ -90,6 +90,7 @@ void simple_vadd(const std::array<T, N>& VA, const std::array<T, N>& VB,
           std::cerr << "Unknown async exception was caught." << std::endl;
         }
       }
+      throw "ERROR: Asynchronous exception(s)";
     });
 
   cl::sycl::range<1> numOfItems{N};

sycl/test/aot/with-llvm-bc.cpp

@@ -40,6 +40,7 @@ void simple_vadd(const std::array<T, N>& VA, const std::array<T, N>& VB,
           std::cerr << "Unknown async exception was caught." << std::endl;
         }
       }
+      throw "ERROR: Asynchronous exception(s)";
     });
 
   cl::sycl::range<1> numOfItems{N};

sycl/test/basic_tests/accessor/accessor.cpp

@@ -215,7 +215,7 @@ int main() {
 
     } catch (cl::sycl::exception e) {
       std::cout << "SYCL exception caught: " << e.what();
-      return 1;
+      throw;
     }
   }
 
@@ -237,7 +237,7 @@ int main() {
         buf.get_access<sycl::access::mode::discard_read_write>();
     } catch (cl::sycl::exception e) {
       std::cout << "SYCL exception caught: " << e.what();
-      return 1;
+      throw;
     }
   }
 
@@ -349,11 +349,11 @@ int main() {
 
       auto host_acc = buf.get_access<sycl::access::mode::read>();
       for (int i = 0; i != 3; ++i)
-        assert(host_acc[i] == 42);
+        CHECK(host_acc[i] == 42);
 
     } catch (cl::sycl::exception e) {
       std::cout << "SYCL exception caught: " << e.what();
-      return 1;
+      throw;
     }
   }
 
@@ -376,8 +376,8 @@ int main() {
       }
       CHECK(data == 399);
     } catch (sycl::exception e) {
-      std::cout << "SYCL exception caught: " << e.what();
-      return 1;
+      std::cerr << "SYCL exception caught: " << e.what();
+      throw;
     }
   }
 

sycl/test/basic_tests/context.cpp

@@ -20,6 +20,7 @@ int main() {
     context c;
   } catch (device_error e) {
     std::cout << "Failed to create device for context" << std::endl;
+    throw;
   }
 
   auto devices = device::get_devices();

sycl/test/basic_tests/device_event.cpp

@@ -66,6 +66,7 @@ int test_strideN(size_t stride) {
           std::cout << e.what();
         }
       }
+      throw "ERROR: Asynchronous exception(s)";
     });
 
     buffer<int, 1> out_buf(out_data, range<1>(nElems));
@@ -109,7 +110,7 @@ int test_strideN(size_t stride) {
 
   } catch (exception e) {
     std::cout << "SYCL exception caught: " << e.what();
-    return 2;
+    throw;
   }
 
   return check_results(out_data, stride);

sycl/test/basic_tests/event_async_exception.cpp

@@ -33,7 +33,7 @@ int main() {
 
     e.wait_and_throw();
     return 1;
-  } catch (runtime_error e) {
+  } catch (runtime_error expectedException) {
     return 0;
   }
 }

sycl/test/basic_tests/info.cpp

@@ -363,4 +363,6 @@ int main() {
   std::cout << separator << "Platform from context information\n" << separator;
   auto cplt = ctx.get_info<cl::sycl::info::context::platform>();
   print_info<info::platform::name, string_class>(cplt, "Name");
+
+  return 0;
 }