generic: skip unsupported examples

Author: sgeor255

examples/CMakeLists.txt

@@ -94,6 +94,20 @@ if(NOT ONEDNN_BUILD_GRAPH)
         )
 endif()
 
+if(DNNL_SYCL_GENERIC)
+    list(REMOVE_ITEM sources
+        # XXX: Enable when InnerProduct is implemented
+        ${CMAKE_CURRENT_SOURCE_DIR}/cnn_inference_f32.cpp
+        ${CMAKE_CURRENT_SOURCE_DIR}/primitives/inner_product.cpp
+        ${CMAKE_CURRENT_SOURCE_DIR}/rnn_training_f32.cpp
+        # XXX: Enable when Reduction is implemented
+        ${CMAKE_CURRENT_SOURCE_DIR}/primitives/reduction.cpp
+        ${CMAKE_CURRENT_SOURCE_DIR}/primitives/group_normalization.cpp
+        ${CMAKE_CURRENT_SOURCE_DIR}/primitives/lbr_gru.cpp
+        ${CMAKE_CURRENT_SOURCE_DIR}/primitives/lstm.cpp
+        ${CMAKE_CURRENT_SOURCE_DIR}/primitives/vanilla_rnn.cpp)
+endif()
+
 if(DNNL_SYCL_HIP)
     # Build examples for supported primitives that support required features.
     set(sources)

src/gpu/generic/sycl/ref_convolution.hpp

@@ -154,11 +154,13 @@ struct ref_convolution_bwd_data_t : public gpu::generic::sycl::primitive_t {
                     && check_convolution_formats(
                             diff_data_d, weights_d, diff_dst_d)
                     && attr()->has_default_values(sm::scales_runtime
-                            | sm::zero_points_runtime | sm::sum_dt)
+                            | sm::zero_points_runtime | sm::sum_dt
+                            | sm::post_ops)
                     && IMPLICATION(!attr()->scales_.has_default_values(),
                             attr_scales_ok()
                                     && check_convolution_scales_types(attr()))
-                    && set_default_alg_kind(alg_kind::convolution_direct);
+                    && set_default_alg_kind(alg_kind::convolution_direct)
+                    && sycl_post_ops_t::post_ops_ok(attr(), false);
             if (!ok) return status::unimplemented;
 
             return init_conf();

tests/gtests/test_deconvolution.cpp

@@ -310,10 +310,20 @@ class deconvolution_test_t
                         strides, padL, padR);
 
         auto aa = allows_attr_t {false};
+
+#ifndef DNNL_SYCL_GENERIC
         aa.po_binary = !is_nvidia_gpu(eng) && !is_amd_gpu(eng);
         aa.po_eltwise = !is_nvidia_gpu(eng) && !is_amd_gpu(eng);
         aa.po_prelu = !is_nvidia_gpu(eng) && !is_amd_gpu(eng);
         aa.po_sum = !is_nvidia_gpu(eng) && !is_amd_gpu(eng);
+#else
+        aa.po_eltwise = true;
+        aa.po_sum = true;
+        if (eng.get_kind() == dnnl::engine::kind::cpu) {
+            aa.po_binary = true;
+            aa.po_prelu = true;
+        }
+#endif
 
         bool is_int8 = impl::utils::one_of(dec_src_desc->get_data_type(),
                 memory::data_type::s8, memory::data_type::u8);