SWDEV-306122 - [catch2][dtest] Adding following tests for hipGraphEventWaitNodeGetEvent() API (#2631)

1. Functional Tests
2. Negative Tests

Change-Id: I65781564a63b6c8c74183abcdd86d32914d1e5a3


[ROCm/hip commit: 59f9765af8]

projects/hip/tests/catch/unit/graph/CMakeLists.txt

@@ -52,6 +52,7 @@ set(TEST_SRC
   hipGraphMemsetNodeGetParams.cc
   hipGraphMemsetNodeSetParams.cc
   hipGraphExecMemcpyNodeSetParamsFromSymbol.cc
+  hipGraphEventWaitNodeGetEvent.cc
   hipGraphExecMemcpyNodeSetParams.cc
 )
 

projects/hip/tests/catch/unit/graph/hipGraphEventWaitNodeGetEvent.cc

@@ -0,0 +1,130 @@
+/*
+Copyright (c) 2022 Advanced Micro Devices, Inc. All rights reserved.
+Permission is hereby granted, free of charge, to any person obtaining a copy
+of this software and associated documentation files (the "Software"), to deal
+in the Software without restriction, including without limitation the rights
+to use, copy, modify, merge, publish, distribute, sublicense, and/or sell
+copies of the Software, and to permit persons to whom the Software is
+furnished to do so, subject to the following conditions:
+The above copyright notice and this permission notice shall be included in
+all copies or substantial portions of the Software.
+THE SOFTWARE IS PROVIDED "AS IS", WITHOUT WARRANNTY OF ANY KIND, EXPRESS OR
+IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF MERCHANTABILITY,
+FITNNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT.  IN NO EVENT SHALL THE
+AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY CLAIM, DAMAGES OR OTHER
+LIABILITY, WHETHER INN AN ACTION OF CONTRACT, TORT OR OTHERWISE, ARISING FROM,
+OUT OF OR INN CONNECTION WITH THE SOFTWARE OR THE USE OR OTHER DEALINGS IN
+THE SOFTWARE.
+*/
+
+/**
+Testcase Scenarios :
+ 1) Validate that the event returned by hipGraphEventWaitNodeGetEvent matches
+with the event set in hipGraphAddEventWaitNode.
+ 2) Negative Scenarios
+    - Input node parameter is passed as nullptr.
+    - Output event parameter is passed as nullptr.
+    - Input node parameter is an empty node.
+    - Input node parameter is a memset node.
+    - Input node parameter is an uninitialized node.
+*/
+
+#include <hip_test_common.hh>
+#include <hip_test_checkers.hh>
+#include <hip_test_kernels.hh>
+
+/**
+ * Local Function
+ */
+static void validateEventWaitNodeGetEvent(unsigned flag) {
+  hipGraph_t graph;
+  HIP_CHECK(hipGraphCreate(&graph, 0));
+  hipEvent_t event, event_out;
+  HIP_CHECK(hipEventCreateWithFlags(&event, flag));
+  hipGraphNode_t eventwait;
+  HIP_CHECK(hipGraphAddEventWaitNode(&eventwait, graph, nullptr, 0,
+                                                          event));
+  HIP_CHECK(hipGraphEventWaitNodeGetEvent(eventwait, &event_out));
+  // validate set event and get event are same
+  REQUIRE(event == event_out);
+  // Instantiate and launch the graph
+  HIP_CHECK(hipGraphDestroy(graph));
+  HIP_CHECK(hipEventDestroy(event));
+}
+
+/**
+ * Scenario 1
+ */
+TEST_CASE("Unit_hipGraphEventWaitNodeGetEvent_Functional") {
+  // Create event nodes with different flags and validate with
+  // hipGraphEventWaitNodeGetEvent.
+  SECTION("Flag = hipEventDefault") {
+    validateEventWaitNodeGetEvent(hipEventDefault);
+  }
+
+  SECTION("Flag = hipEventBlockingSync") {
+    validateEventWaitNodeGetEvent(hipEventBlockingSync);
+  }
+
+  SECTION("Flag = hipEventDisableTiming") {
+    validateEventWaitNodeGetEvent(hipEventDisableTiming);
+  }
+}
+
+/**
+ * Scenario 2
+ */
+TEST_CASE("Unit_hipGraphEventWaitNodeGetEvent_Negative") {
+  hipGraph_t graph;
+  HIP_CHECK(hipGraphCreate(&graph, 0));
+  hipEvent_t event, event_out;
+  HIP_CHECK(hipEventCreate(&event));
+  hipGraphNode_t eventwait;
+  HIP_CHECK(hipGraphAddEventWaitNode(&eventwait, graph, nullptr, 0,
+                                                            event));
+  SECTION("node = nullptr") {
+    REQUIRE(hipErrorInvalidValue == hipGraphEventWaitNodeGetEvent(nullptr,
+                                    &event_out));
+  }
+
+  SECTION("event_out = nullptr") {
+    REQUIRE(hipErrorInvalidValue == hipGraphEventWaitNodeGetEvent(eventwait,
+                                    nullptr));
+  }
+
+  SECTION("input node is empty node") {
+    hipGraphNode_t EmptyGraphNode;
+    HIP_CHECK(hipGraphAddEmptyNode(&EmptyGraphNode, graph, nullptr, 0));
+    REQUIRE(hipErrorInvalidValue ==
+            hipGraphEventWaitNodeGetEvent(EmptyGraphNode, &event_out));
+  }
+
+  SECTION("input node is memset node") {
+    constexpr size_t Nbytes = 1024;
+    char *A_d;
+    hipGraphNode_t memset_A;
+    hipMemsetParams memsetParams{};
+    HIP_CHECK(hipMalloc(&A_d, Nbytes));
+    memset(&memsetParams, 0, sizeof(memsetParams));
+    memsetParams.dst = reinterpret_cast<void*>(A_d);
+    memsetParams.value = 0;
+    memsetParams.pitch = 0;
+    memsetParams.elementSize = sizeof(char);
+    memsetParams.width = Nbytes;
+    memsetParams.height = 1;
+    HIP_CHECK(hipGraphAddMemsetNode(&memset_A, graph, nullptr, 0,
+                                    &memsetParams));
+    REQUIRE(hipErrorInvalidValue ==
+            hipGraphEventWaitNodeGetEvent(memset_A, &event_out));
+    HIP_CHECK(hipFree(A_d));
+  }
+
+  SECTION("input node is uninitialized") {
+    hipGraphNode_t node_uninit{};
+    REQUIRE(hipErrorInvalidValue ==
+            hipGraphEventWaitNodeGetEvent(node_uninit, &event_out));
+  }
+
+  HIP_CHECK(hipGraphDestroy(graph));
+  HIP_CHECK(hipEventDestroy(event));
+}