CodeQL / Analyze (actions) (push) Canceled after 0s
CodeQL / Analyze (python) (push) Canceled after 0s
pre-commit / pre-commit (push) Canceled after 0s
Multi-Arch CI / setup (push) Canceled after 0s
Publish build_manylinux_x86_64 images / publish_build_manylinux_x86_64 (push) Canceled after 0s
Setup (Multi-Arch) / setup (push) Canceled after 0s
Multi-Arch CI / Linux::${{ fromJSON(needs.setup.outputs.linux_build_config || '{}').build_variant_label || 'skip' }} (push) Canceled after 0s
Publish TheRock Docker image / build-and-push-image (push) Canceled after 0s
Publish no_rocm_image_ubi10 image / publish_no_rocm_image_ubi10 (push) Canceled after 0s
Multi-Arch CI / Windows::${{ fromJSON(needs.setup.outputs.windows_build_config || '{}').build_variant_label || 'skip' }} (push) Canceled after 0s
Publish TheRock Docker image / build-and-push-image (push) Canceled after 0s
Multi-Arch CI / Manifest Diff (push) Canceled after 0s
TheRock Manifest Diff Report / Generate Manifest Diff Report (push) Canceled after 0s
Multi-Arch CI / CI Summary (push) Canceled after 0s
Publish no_rocm_image_ubuntu24_04 images / publish_no_rocm_image_ubuntu24_04 (push) Canceled after 0s
Publish no_rocm_image_ubuntu24_04_ocl_rt images / publish_no_rocm_image_ubuntu24_04_ocl_rt (push) Canceled after 0s
Publish TheRock Docker image / build-and-push-image (push) Canceled after 0s
Publish TheRock Docker image / build-and-push-image (push) Canceled after 0s
Publish no_rocm_image_ubuntu24_04 images / publish_no_rocm_image_ubuntu24_04_rocgdb (push) Canceled after 0s
Publish no_rocm_image_ubuntu24_04_rocgdb images / publish_no_rocm_image_ubuntu24_04_rocgdb (push) Canceled after 0s
Publish no_rocm_image_ubuntu24_04 images / publish_no_rocm_image_ubuntu24_04_ocl_rt (push) Canceled after 0s
Publish TheRock Docker image / build-and-push-image (push) Canceled after 0s
Unit Tests / Unit Tests :: ubuntu-24.04 (push) Canceled after 0s
Unit Tests / Unit Tests :: windows-2022 (push) Canceled after 0s
Publish no_rocm_image_ubuntu24_04 images / publish_no_rocm_image_ubuntu24_04_media (push) Canceled after 0s
Unit Tests / Unit Tests Summary (push) Canceled after 0s
Publish no_rocm_image_ubuntu24_04 images / publish_no_rocm_image_ubuntu24_04_openmpi (push) Canceled after 0s
200 lines
7.1 KiB
C++
200 lines
7.1 KiB
C++
// Copyright © Advanced Micro Devices, Inc., or its affiliates.
|
|
// SPDX-License-Identifier: MIT
|
|
|
|
#include <gmock/gmock.h>
|
|
#include <gtest/gtest.h>
|
|
#include <memory>
|
|
#include <set>
|
|
|
|
#include <hipdnn_plugin_sdk/PluginException.hpp>
|
|
#include <hipdnn_test_sdk/utilities/MockEngineConfig.hpp>
|
|
#include <hipdnn_test_sdk/utilities/MockGraph.hpp>
|
|
|
|
#include "EngineManager.hpp"
|
|
#include "HipdnnEnginePluginExecutionContext.hpp"
|
|
#include "HipdnnEnginePluginHandle.hpp"
|
|
#include "mocks/MockEngine.hpp"
|
|
#include "mocks/MockHipdnnEnginePluginExecutionContext.hpp"
|
|
|
|
using namespace hipblaslt_plugin;
|
|
using namespace hipdnn_test_sdk::utilities;
|
|
using namespace hipdnn_plugin_sdk;
|
|
using namespace hipdnn_flatbuffers_sdk::flatbuffer_utilities;
|
|
using ::testing::Return;
|
|
|
|
TEST(TestHipblasltEngineManager, ReturnsApplicableEngineIds)
|
|
{
|
|
std::set<std::unique_ptr<IEngine>> const engines;
|
|
|
|
auto mockEngine1 = std::make_unique<MockEngine>();
|
|
EXPECT_CALL(*mockEngine1, id()).WillRepeatedly(Return(1));
|
|
EXPECT_CALL(*mockEngine1, isApplicable(::testing::_, ::testing::_))
|
|
.WillRepeatedly(Return(true));
|
|
|
|
auto mockEngine2 = std::make_unique<MockEngine>();
|
|
EXPECT_CALL(*mockEngine2, id()).WillRepeatedly(Return(2));
|
|
EXPECT_CALL(*mockEngine2, isApplicable(::testing::_, ::testing::_))
|
|
.WillRepeatedly(Return(false));
|
|
|
|
EngineManager manager;
|
|
manager.addEngine(std::move(mockEngine1));
|
|
manager.addEngine(std::move(mockEngine2));
|
|
|
|
MockGraph const mockGraph;
|
|
HipdnnEnginePluginHandle dummyHandle;
|
|
auto applicable = manager.getApplicableEngineIds(dummyHandle, mockGraph);
|
|
|
|
EXPECT_EQ(applicable.size(), 1);
|
|
EXPECT_EQ(applicable[0], 1);
|
|
}
|
|
|
|
TEST(TestHipblasltEngineManager, ReturnsMultipleApplicableEngineIds)
|
|
{
|
|
std::set<std::unique_ptr<IEngine>> const engines;
|
|
|
|
auto mockEngine1 = std::make_unique<MockEngine>();
|
|
EXPECT_CALL(*mockEngine1, id()).WillRepeatedly(Return(1));
|
|
EXPECT_CALL(*mockEngine1, isApplicable(::testing::_, ::testing::_))
|
|
.WillRepeatedly(Return(true));
|
|
|
|
auto mockEngine2 = std::make_unique<MockEngine>();
|
|
EXPECT_CALL(*mockEngine2, id()).WillRepeatedly(Return(2));
|
|
EXPECT_CALL(*mockEngine2, isApplicable(::testing::_, ::testing::_))
|
|
.WillRepeatedly(Return(true));
|
|
|
|
EngineManager manager;
|
|
manager.addEngine(std::move(mockEngine1));
|
|
manager.addEngine(std::move(mockEngine2));
|
|
|
|
MockGraph const mockGraph;
|
|
HipdnnEnginePluginHandle dummyHandle;
|
|
auto applicable = manager.getApplicableEngineIds(dummyHandle, mockGraph);
|
|
|
|
EXPECT_EQ(applicable.size(), 2);
|
|
EXPECT_TRUE(std::find(applicable.begin(), applicable.end(), 1) != applicable.end());
|
|
EXPECT_TRUE(std::find(applicable.begin(), applicable.end(), 2) != applicable.end());
|
|
}
|
|
|
|
TEST(TestHipblasltEngineManager, ReturnsNoApplicableEngineIds)
|
|
{
|
|
std::set<std::unique_ptr<IEngine>> const engines;
|
|
|
|
auto mockEngine1 = std::make_unique<MockEngine>();
|
|
EXPECT_CALL(*mockEngine1, id()).WillRepeatedly(Return(1));
|
|
EXPECT_CALL(*mockEngine1, isApplicable(::testing::_, ::testing::_))
|
|
.WillRepeatedly(Return(false));
|
|
|
|
auto mockEngine2 = std::make_unique<MockEngine>();
|
|
EXPECT_CALL(*mockEngine2, id()).WillRepeatedly(Return(2));
|
|
EXPECT_CALL(*mockEngine2, isApplicable(::testing::_, ::testing::_))
|
|
.WillRepeatedly(Return(false));
|
|
|
|
EngineManager manager;
|
|
manager.addEngine(std::move(mockEngine1));
|
|
manager.addEngine(std::move(mockEngine2));
|
|
|
|
MockGraph const mockGraph;
|
|
HipdnnEnginePluginHandle dummyHandle;
|
|
auto applicable = manager.getApplicableEngineIds(dummyHandle, mockGraph);
|
|
|
|
EXPECT_TRUE(applicable.empty());
|
|
}
|
|
|
|
TEST(TestHipblasltEngineManager, ReturnsEngineDetails)
|
|
{
|
|
EngineManager manager;
|
|
|
|
hipdnnPluginConstData_t engineDetails;
|
|
engineDetails.ptr = reinterpret_cast<const void*>(0x12345678);
|
|
engineDetails.size = 200;
|
|
auto mockEngine = std::make_unique<MockEngine>();
|
|
EXPECT_CALL(*mockEngine, id()).WillRepeatedly(Return(1));
|
|
EXPECT_CALL(*mockEngine, getDetails(::testing::_, ::testing::_))
|
|
.WillOnce([&engineDetails](HipdnnEnginePluginHandle& handle, hipdnnPluginConstData_t& out) {
|
|
(void)handle;
|
|
out.ptr = engineDetails.ptr;
|
|
out.size = engineDetails.size;
|
|
});
|
|
|
|
manager.addEngine(std::move(mockEngine));
|
|
|
|
MockGraph const mockGraph;
|
|
HipdnnEnginePluginHandle dummyHandle = {};
|
|
hipdnnPluginConstData_t details;
|
|
manager.getEngineDetails(dummyHandle, mockGraph, 1, details);
|
|
|
|
EXPECT_EQ(details.ptr, engineDetails.ptr);
|
|
EXPECT_EQ(details.size, engineDetails.size);
|
|
}
|
|
|
|
TEST(TestHipblasltEngineManager, ThrowsOnInvalidEngineId)
|
|
{
|
|
EngineManager manager;
|
|
|
|
MockGraph const mockGraph;
|
|
hipdnnPluginConstData_t engineDetails;
|
|
|
|
HipdnnEnginePluginHandle dummyHandle = {};
|
|
EXPECT_THROW(manager.getEngineDetails(dummyHandle, mockGraph, 999, engineDetails),
|
|
hipdnn_plugin_sdk::HipdnnPluginException);
|
|
}
|
|
|
|
TEST(TestHipblasltEngineManager, GetWorkspaceSizeReturnsCorrectValue)
|
|
{
|
|
EngineManager manager;
|
|
|
|
auto mockEngine = std::make_unique<MockEngine>();
|
|
EXPECT_CALL(*mockEngine, id()).WillRepeatedly(Return(42));
|
|
HipdnnEnginePluginHandle const dummyHandle = {};
|
|
MockGraph const mockGraph;
|
|
EXPECT_CALL(*mockEngine, getWorkspaceSize(::testing::_, ::testing::_)).WillOnce(Return(4096));
|
|
|
|
manager.addEngine(std::move(mockEngine));
|
|
|
|
size_t const workspaceSize = manager.getWorkspaceSize(dummyHandle, 42, mockGraph);
|
|
EXPECT_EQ(workspaceSize, 4096);
|
|
}
|
|
|
|
TEST(TestHipblasltEngineManager, GetWorkspaceSizeThrowsOnInvalidEngineId)
|
|
{
|
|
EngineManager const manager;
|
|
HipdnnEnginePluginHandle const dummyHandle = {};
|
|
MockGraph const mockGraph;
|
|
|
|
EXPECT_THROW(manager.getWorkspaceSize(dummyHandle, 999, mockGraph),
|
|
hipdnn_plugin_sdk::HipdnnPluginException);
|
|
}
|
|
|
|
TEST(TestHipblasltEngineManager, InitializeExecutionContextCallsEngine)
|
|
{
|
|
auto mockEngine = std::make_unique<MockEngine>();
|
|
EXPECT_CALL(*mockEngine, id()).WillRepeatedly(Return(7));
|
|
EXPECT_CALL(*mockEngine, initializeExecutionContext(::testing::_, ::testing::_, ::testing::_))
|
|
.Times(1);
|
|
|
|
EngineManager manager;
|
|
manager.addEngine(std::move(mockEngine));
|
|
HipdnnEnginePluginHandle const dummyHandle = {};
|
|
MockGraph const mockGraph;
|
|
MockEngineConfig const mockEngineConfig;
|
|
ON_CALL(mockEngineConfig, engineId()).WillByDefault(Return(7));
|
|
EXPECT_CALL(mockEngineConfig, engineId()).Times(testing::AnyNumber()); // Uninteresting call
|
|
MockHipdnnEnginePluginExecutionContext execCtx;
|
|
|
|
manager.initializeExecutionContext(dummyHandle, mockGraph, mockEngineConfig, execCtx);
|
|
}
|
|
|
|
TEST(TestHipblasltEngineManager, InitializeExecutionContextThrowsOnInvalidEngineId)
|
|
{
|
|
MockHipdnnEnginePluginExecutionContext execCtx;
|
|
EngineManager const manager;
|
|
HipdnnEnginePluginHandle const dummyHandle = {};
|
|
MockGraph const mockGraph;
|
|
MockEngineConfig const mockEngineConfig;
|
|
|
|
EXPECT_CALL(mockEngineConfig, engineId()).Times(testing::AnyNumber()); // Uninteresting call
|
|
EXPECT_THROW(
|
|
manager.initializeExecutionContext(dummyHandle, mockGraph, mockEngineConfig, execCtx),
|
|
hipdnn_plugin_sdk::HipdnnPluginException);
|
|
}
|