Fix empty case for cuda device

Author: AlexanderKalistratov

dpnp/backend/extensions/sycl_ext/histogram.cpp

@@ -212,6 +212,10 @@ std::tuple<sycl::event, sycl::event>
 {
     validate(sample, bins, weights, histogram);
 
+    if (sample.get_size() == 0) {
+        return {sycl::event(), sycl::event()};
+    }
+
     const int sample_typenum = sample.get_typenum();
     const int bins_typenum = bins.get_typenum();
     const int hist_typenum = histogram.get_typenum();

dpnp/backend/extensions/sycl_ext/histogram_common.cpp

@@ -91,6 +91,16 @@ void validate(const usm_ndarray &sample,
                               " parameter is not c-contiguos");
     }
 
+    if (bins.get_size() < 2) {
+        throw py::value_error(get_name(&bins) +
+                              " parameter must have at least 2 elements");
+    }
+
+    if (histogram.get_size() < 1) {
+        throw py::value_error(get_name(&histogram) +
+                              " parameter must have at least 1 element");
+    }
+
     if (histogram.get_ndim() != 1) {
         throw py::value_error(get_name(&histogram) +
                               " parameter must be 1d. Actual " +