diff --git a/Project.toml b/Project.toml
index 51859d2ee..775be0e79 100644
--- a/Project.toml
+++ b/Project.toml
@@ -36,7 +36,7 @@ Atomix = "0.1, 1"
 EnzymeCore = "0.7, 0.8.1"
 GPUCompiler = "1.2"
 InteractiveUtils = "1.6"
-LLVM = "9"
+LLVM = "9.4.1"
 LinearAlgebra = "1.6"
 MacroTools = "0.5"
 PrecompileTools = "1"
diff --git a/src/pocl/device/runtime.jl b/src/pocl/device/runtime.jl
index 2d11f701f..f980f683b 100644
--- a/src/pocl/device/runtime.jl
+++ b/src/pocl/device/runtime.jl
@@ -10,23 +10,23 @@ report_oom(sz) = return
 import SPIRVIntrinsics: get_global_id
 
 function report_exception(ex)
-    # SPIRVIntrinsics.@printf(
-    #     "ERROR: a %s was thrown during kernel execution on thread (%d, %d, %d).\n",
-    #     ex, get_global_id(UInt32(0)), get_global_id(UInt32(1)), get_global_id(UInt32(2))
-    # )
+    SPIRVIntrinsics.@printf(
+        "ERROR: a %s was thrown during kernel execution on thread (%d, %d, %d).\n",
+        ex, get_global_id(UInt32(0)), get_global_id(UInt32(1)), get_global_id(UInt32(2))
+    )
     return
 end
 
 function report_exception_name(ex)
-    # SPIRVIntrinsics.@printf(
-    #     "ERROR: a %s was thrown during kernel execution on thread (%d, %d, %d).\n",
-    #     ex, get_global_id(UInt32(0)), get_global_id(UInt32(1)), get_global_id(UInt32(2))
-    # )
-    # SPIRVIntrinsics.@printf("Stacktrace:\n")
+    SPIRVIntrinsics.@printf(
+        "ERROR: a %s was thrown during kernel execution on thread (%d, %d, %d).\n",
+        ex, get_global_id(UInt32(0)), get_global_id(UInt32(1)), get_global_id(UInt32(2))
+    )
+    SPIRVIntrinsics.@printf("Stacktrace:\n")
     return
 end
 
 function report_exception_frame(idx, func, file, line)
-    # SPIRVIntrinsics.@printf(" [%d] %s at %s:%d\n", idx, func, file, line)
+    SPIRVIntrinsics.@printf(" [%d] %s at %s:%d\n", idx, func, file, line)
     return
 end