Add tests for uninitialized_fill[_n] for hetero backend

Author: rarutyun

test/parallel_api/memory/specialized.algorithms/uninitialized_fill_destroy.pass.cpp

@@ -260,10 +260,12 @@ void test_empty_list_initialization_for_uninitialized_fill()
         }
     }
 #if TEST_DPCPP_BACKEND_PRESENT
-    std::vector<int> v{3,6,5,4,3,7,8,0,2,4};
-    sycl::buffer<int> buf(v);
-    auto it = oneapi::dpl::uninitialized_fill(oneapi::dpl::execution::dpcpp_default, oneapi::dpl::begin(buf), oneapi::dpl::end(buf), {});
-    EXPECT_TRUE(std::count(v.begin(), v.end(), 0) == v.size(), "a sequence is not filled properly by oneapi::dpl::uninitialized_fill with `device_policy` policy");
+    auto usm_deleter = [] (auto ptr) { sycl::free(ptr, oneapi::dpl::execution::dpcpp_default.queue()); };
+    using usm_deleter_type = decltype(usm_deleter);
+    std::unique_ptr<int, usm_deleter_type> ptr{sycl::malloc_shared<int>(size, oneapi::dpl::execution::dpcpp_default.queue()), usm_deleter};
+    oneapi::dpl::uninitialized_fill(oneapi::dpl::execution::dpcpp_default, ptr.get(), ptr.get() + size, {1});
+    EXPECT_TRUE(std::count(ptr.get(), ptr.get() + size, 1) == size, "a sequence is not filled properly by oneapi::dpl::uninitialized_fill with `device_policy` policy");
+    // no need to call destroy for a trivial type
 #endif
 }
 
@@ -320,10 +322,12 @@ void test_empty_list_initialization_for_uninitialized_fill_n()
         }
     }
 #if TEST_DPCPP_BACKEND_PRESENT
-    std::vector<int> v{3,6,5,4,3,7,8,0,2,4};
-    sycl::buffer<int> buf(v);
-    auto it = oneapi::dpl::uninitialized_fill_n(oneapi::dpl::execution::dpcpp_default, oneapi::dpl::begin(buf), oneapi::dpl::end(buf), {});
-    EXPECT_TRUE(std::count(v.begin(), v.end(), 0) == v.size(), "a sequence is not filled properly by oneapi::dpl::uninitialized_fill_n with `device_policy` policy");
+    auto usm_deleter = [] (auto ptr) { sycl::free(ptr, oneapi::dpl::execution::dpcpp_default.queue()); };
+    using usm_deleter_type = decltype(usm_deleter);
+    std::unique_ptr<int, usm_deleter_type> ptr{sycl::malloc_shared<int>(size, oneapi::dpl::execution::dpcpp_default.queue()), usm_deleter};
+    oneapi::dpl::uninitialized_fill_n(oneapi::dpl::execution::dpcpp_default, ptr.get(), size, {1});
+    EXPECT_TRUE(std::count(ptr.get(), ptr.get() + size, 1) == size, "a sequence is not filled properly by oneapi::dpl::uninitialized_fill with `device_policy` policy");
+    // no need to call destroy for a trivial type
 #endif
 }