Debug

Author: aelovikov-intel

sycl-jit/jit-compiler/lib/rtc/DeviceCompilation.cpp

@@ -72,6 +72,12 @@ using namespace llvm::util;
 using namespace llvm::vfs;
 using namespace jit_compiler;
 
+#if defined(__linux__)
+#define PRETTY __PRETTY_FUNCTION__
+#else
+#define PRETTY __FUNCSIG__
+#endif
+
 namespace {
 struct AutoPCHError : public ErrorInfo<AutoPCHError> {
 public:
@@ -282,6 +288,7 @@ class SYCLToolchain {
         std::unique_ptr<MemoryBuffer> PrecompiledPreamble,
         const PreambleBounds &Bounds, CompilerInvocation &CI,
         IntrusiveRefCntPtr<llvm::vfs::FileSystem> &VFS) {
+      std::cerr << PRETTY << "\n";
 
       // Processing similar to PrecompiledPreamble::configurePreamble.
 
@@ -361,15 +368,18 @@ class SYCLToolchain {
         // need this extra `Success` variable to be able to properly return
         // compilatoin status.
         bool Success = false;
-        auto RunWithoutPCH = [&]() -> bool {
+        auto RunWithoutPCH = [&](unsigned LINE = __builtin_LINE()) -> bool {
+          std::cerr << PRETTY << " " << LINE << "\n";
           // Run original invocation:
           Success =
               Action::runInvocation(std::move(Invocation), Files,
                                     std::move(PCHContainerOps), DiagConsumer);
           return Success;
         };
 
-        auto UseCachedPreamble = [&](StringRef PCHContent) {
+        auto UseCachedPreamble = [&](StringRef PCHContent,
+                                     unsigned LINE = __builtin_LINE()) {
+          std::cerr << PRETTY << " " << LINE << "\n";
           std::unique_ptr<MemoryBuffer> PCHMemBuf =
               MemoryBuffer::getMemBufferCopy(PCHContent);
 
@@ -395,6 +405,8 @@ class SYCLToolchain {
 
         auto CacheCallback = [&](size_t, const Twine &,
                                  std::unique_ptr<MemoryBuffer> MB) -> void {
+          std::cerr << PRETTY << " " << std::boolalpha << CacheHit
+                    << "\n";
           if (!CacheHit)
             return; // See above.
 
@@ -468,7 +480,11 @@ class SYCLToolchain {
 
         OS << NewPreamble->memoryContents();
 
-        consumeError(CFS->commit());
+        auto Err = CFS->commit();
+        if (Err) {
+          std::cerr << "Error in commit\n";
+        }
+        consumeError(std::move(Err));
 
         return Success;
       } else {

sycl/test-e2e/KernelCompiler/persistent_auto_pch_read_error.cpp

@@ -19,9 +19,14 @@
 // RUN: %{run-aux} cp %s %t.dir/*
 // RUN: %{run-unfiltered-devices} %t.out
 
+// RUN: %{run-aux} false
+// RUN: false
+
 #include <sycl/detail/core.hpp>
 #include <sycl/kernel_bundle.hpp>
 
+#include <iostream>
+
 namespace syclexp = sycl::ext::oneapi::experimental;
 
 const std::string src = R"""(
@@ -38,6 +43,7 @@ void foo(int *p) {
 )""";
 
 int main() {
+  std::cout << "PCH_DIR: " PCH_DIR << std::endl;
   sycl::queue q;
   auto kb_src = syclexp::create_kernel_bundle_from_source(
       q.get_context(), syclexp::source_language::sycl, src);