use sycl_adapter in krnl_logic (#910)

Author: shssf

dpnp/backend/kernels/dpnp_krnl_logic.cpp

@@ -27,6 +27,7 @@
 
 #include "dpnp_fptr.hpp"
 #include "dpnp_iface.hpp"
+#include "dpnpc_memory_adapter.hpp"
 #include "queue_sycl.hpp"
 
 template <typename _DataType, typename _ResultType>
@@ -35,16 +36,17 @@ class dpnp_all_c_kernel;
 template <typename _DataType, typename _ResultType>
 void dpnp_all_c(const void* array1_in, void* result1, const size_t size)
 {
-    cl::sycl::event event;
-
-    const _DataType* array_in = reinterpret_cast<const _DataType*>(array1_in);
-    _ResultType* result = reinterpret_cast<_ResultType*>(result1);
-
     if (!array1_in || !result1)
     {
         return;
     }
 
+    cl::sycl::event event;
+    DPNPC_ptr_adapter<_DataType> input1_ptr(array1_in, size);
+    DPNPC_ptr_adapter<_ResultType> result1_ptr(result1, 1, true, true);
+    const _DataType* array_in = input1_ptr.get_ptr();
+    _ResultType* result = result1_ptr.get_ptr();
+
     result[0] = true;
 
     if (!size)
@@ -83,9 +85,13 @@ void dpnp_allclose_c(
         return;
     }
 
-    const _DataType1* array1 = reinterpret_cast<const _DataType1*>(array1_in);
-    const _DataType2* array2 = reinterpret_cast<const _DataType2*>(array2_in);
-    _ResultType* result = reinterpret_cast<_ResultType*>(result1);
+    cl::sycl::event event;
+    DPNPC_ptr_adapter<_DataType1> input1_ptr(array1_in, size);
+    DPNPC_ptr_adapter<_DataType2> input2_ptr(array2_in, size);
+    DPNPC_ptr_adapter<_ResultType> result1_ptr(result1, 1, true, true);
+    const _DataType1* array1 = input1_ptr.get_ptr();
+    const _DataType2* array2 = input2_ptr.get_ptr();
+    _ResultType* result = result1_ptr.get_ptr();
 
     result[0] = true;
 
@@ -94,8 +100,6 @@ void dpnp_allclose_c(
         return;
     }
 
-    cl::sycl::event event;
-
     cl::sycl::range<1> gws(size);
     auto kernel_parallel_for_func = [=](cl::sycl::id<1> global_id) {
         size_t i = global_id[0];
@@ -122,16 +126,17 @@ class dpnp_any_c_kernel;
 template <typename _DataType, typename _ResultType>
 void dpnp_any_c(const void* array1_in, void* result1, const size_t size)
 {
-    cl::sycl::event event;
-
-    const _DataType* array_in = reinterpret_cast<const _DataType*>(array1_in);
-    _ResultType* result = reinterpret_cast<_ResultType*>(result1);
-
     if (!array1_in || !result1)
     {
         return;
     }
 
+    cl::sycl::event event;
+    DPNPC_ptr_adapter<_DataType> input1_ptr(array1_in, size);
+    DPNPC_ptr_adapter<_ResultType> result1_ptr(result1, 1, true, true);
+    const _DataType* array_in = input1_ptr.get_ptr();
+    _ResultType* result = result1_ptr.get_ptr();
+
     result[0] = false;
 
     if (!size)