Implement wait_and_free using detail::free

For buffer support

Author: joeatodd

sycl/include/syclcompat/memory.hpp

@@ -1005,7 +1005,7 @@ static inline void wait_and_free(void *ptr,
   get_current_device().queues_wait_and_throw();
   q.wait();
   if (ptr) {
-    sycl::free(ptr, q);
+    detail::free(ptr, q);
   }
 }
 

sycl/test-e2e/syclcompat/memory/memory_management_test3_usmnone.cpp

@@ -52,9 +52,7 @@ void test_mempcy_async() {
   syclcompat::memcpy_async((void*) (d_A + N1), (void*) h_B, (Num-N1) * sizeof(float));
   syclcompat::memcpy_async((void*) h_C, (void*) d_A, Num * sizeof(float));
 
-  syclcompat::get_default_queue().wait_and_throw();
-
-  syclcompat::free((void*)d_A);
+  syclcompat::wait_and_free((void*)d_A);
 
   syclcompat::free(0);
   syclcompat::free(NULL);
@@ -465,8 +463,7 @@ void test_memset_async(sycl::queue &q) {
 
   // deviceA -> hostA
   syclcompat::memcpy_async((void*) h_A, (void*) d_A, Num * sizeof(int), q);
-  q.wait_and_throw();
-  syclcompat::free((void*)d_A, q);
+  syclcompat::wait_and_free((void*)d_A, q);
 
   // check d_A[0,..., 6] = 0
   for (int i = 0; i < Num - 3; i++) {