[SYCL] Remove program class

SYCL/Basic/get_backend.cpp

@@ -46,11 +46,6 @@ int main() {
         return_fail();
       }
 
-      program prog(c);
-      if (prog.get_backend() != plt.get_backend()) {
-        return_fail();
-      }
-
       default_selector sel;
       queue q(c, sel);
       if (q.get_backend() != plt.get_backend()) {

SYCL/Basic/kernel_info.cpp

@@ -26,13 +26,13 @@ int main() {
   queue q;
 
   buffer<int, 1> buf(range<1>(1));
-  program prg(q.get_context());
-
-  prg.build_with_kernel_type<class SingleTask>();
-  assert(prg.has_kernel<class SingleTask>());
-  kernel krn = prg.get_kernel<class SingleTask>();
+  auto KernelID = sycl::get_kernel_id<class SingleTask>();
+  auto KB =
+      get_kernel_bundle<bundle_state::executable>(q.get_context(), {KernelID});
+  kernel krn = KB.get_kernel(KernelID);
 
   q.submit([&](handler &cgh) {
+    cgh.use_kernel_bundle(KB);
     auto acc = buf.get_access<access::mode::read_write>(cgh);
     cgh.single_task<class SingleTask>(krn, [=]() { acc[0] = acc[0] + 1; });
   });
@@ -43,8 +43,6 @@ int main() {
   assert(krnArgCount > 0);
   const context krnCtx = krn.get_info<info::kernel::context>();
   assert(krnCtx == q.get_context());
-  const program krnPrg = krn.get_info<info::kernel::program>();
-  assert(krnPrg == prg);
   const cl_uint krnRefCount = krn.get_info<info::kernel::reference_count>();
   assert(krnRefCount > 0);
   const std::string krnAttr = krn.get_info<info::kernel::attributes>();

SYCL/SpecConstants/1.2.1/composite-in-functor.cpp → SYCL/DeprecatedFeatures/SpecConsts1.2.1/composite-in-functor.cpp

@@ -1,6 +1,6 @@
 // UNSUPPORTED: cuda || hip
 //
-// RUN: %clangxx -fsycl %s -o %t.out
+// RUN: %clangxx -fsycl %s -D__SYCL_INTERNAL_API -o %t.out
 // RUN: %HOST_RUN_PLACEHOLDER %t.out %HOST_CHECK_PLACEHOLDER
 // RUN: %CPU_RUN_PLACEHOLDER %t.out %CPU_CHECK_PLACEHOLDER
 // RUN: %GPU_RUN_PLACEHOLDER %t.out %GPU_CHECK_PLACEHOLDER

SYCL/SpecConstants/1.2.1/composite-type.cpp → SYCL/DeprecatedFeatures/SpecConsts1.2.1/composite-type.cpp

@@ -1,6 +1,6 @@
 // UNSUPPORTED: cuda || hip
 //
-// RUN: %clangxx -fsycl %s -o %t.out
+// RUN: %clangxx -fsycl -D__SYCL_INTERNAL_API %s -o %t.out
 // RUN: %HOST_RUN_PLACEHOLDER %t.out
 // RUN: %CPU_RUN_PLACEHOLDER %t.out
 // RUN: %GPU_RUN_PLACEHOLDER %t.out

SYCL/SpecConstants/1.2.1/multiple-usages-of-composite.cpp → SYCL/DeprecatedFeatures/SpecConsts1.2.1/multiple-usages-of-composite.cpp

@@ -1,6 +1,6 @@
 // UNSUPPORTED: cuda || hip
 //
-// RUN: %clangxx -fsycl %s -o %t.out -v
+// RUN: %clangxx -fsycl -D__SYCL_INTERNAL_API %s -o %t.out -v
 // RUN: %HOST_RUN_PLACEHOLDER %t.out %HOST_CHECK_PLACEHOLDER
 // RUN: %CPU_RUN_PLACEHOLDER %t.out %CPU_CHECK_PLACEHOLDER
 // RUN: %GPU_RUN_PLACEHOLDER %t.out %GPU_CHECK_PLACEHOLDER

SYCL/SpecConstants/1.2.1/spec_const_hw.cpp → SYCL/DeprecatedFeatures/SpecConsts1.2.1/spec_const_hw.cpp

@@ -1,6 +1,6 @@
 // UNSUPPORTED: cuda || hip
 //
-// RUN: %clangxx -fsycl -fsycl-targets=%sycl_triple %s -o %t.out
+// RUN: %clangxx -fsycl -fsycl-targets=%sycl_triple -D__SYCL_INTERNAL_API %s -o %t.out
 // RUN: %HOST_RUN_PLACEHOLDER %t.out
 // RUN: %CPU_RUN_PLACEHOLDER %t.out
 // RUN: %GPU_RUN_PLACEHOLDER %t.out

SYCL/SpecConstants/1.2.1/spec_const_neg.cpp → SYCL/DeprecatedFeatures/SpecConsts1.2.1/spec_const_neg.cpp

@@ -1,4 +1,4 @@
-// RUN: %clangxx -fsycl %s -o %t.out
+// RUN: %clangxx -fsycl -D__SYCL_INTERNAL_API %s -o %t.out
 // RUN: %HOST_RUN_PLACEHOLDER %t.out
 // RUN: %CPU_RUN_PLACEHOLDER %t.out
 // RUN: %GPU_RUN_PLACEHOLDER %t.out

SYCL/SpecConstants/1.2.1/spec_const_redefine.cpp → SYCL/DeprecatedFeatures/SpecConsts1.2.1/spec_const_redefine.cpp

@@ -2,7 +2,7 @@
 //
 // FIXME Disable fallback assert so that it doesn't interferes with number of
 // program builds at run-time
-// RUN: %clangxx -DSYCL_DISABLE_FALLBACK_ASSERT -fsycl -fsycl-targets=%sycl_triple %s -o %t.out
+// RUN: %clangxx -DSYCL_DISABLE_FALLBACK_ASSERT -D__SYCL_INTERNAL_API -fsycl -fsycl-targets=%sycl_triple %s -o %t.out
 // RUN: %HOST_RUN_PLACEHOLDER %t.out
 // RUN: env SYCL_PI_TRACE=2 %CPU_RUN_PLACEHOLDER %t.out 2>&1 %CPU_CHECK_PLACEHOLDER
 // RUN: env SYCL_PI_TRACE=2 %GPU_RUN_PLACEHOLDER %t.out 2>&1 %GPU_CHECK_PLACEHOLDER