experimental/cuda2/dynamic_symbols_test.cc

// Copyright 2023 The IREE Authors
//
// Licensed under the Apache License v2.0 with LLVM Exceptions.
// See https://llvm.org/LICENSE.txt for license information.
// SPDX-License-Identifier: Apache-2.0 WITH LLVM-exception

#include <iostream>

#include "experimental/cuda2/cuda_dynamic_symbols.h"
#include "experimental/cuda2/nccl_dynamic_symbols.h"
#include "iree/base/api.h"
#include "iree/testing/gtest.h"

namespace iree {
namespace hal {
namespace cuda {
namespace {

#define CUDA_CHECK_ERRORS(expr)      \
  {                                  \
    CUresult status = expr;          \
    ASSERT_EQ(CUDA_SUCCESS, status); \
  }

TEST(DynamicSymbolsTest, CreateFromSystemLoader) {
  iree_hal_cuda2_dynamic_symbols_t symbols;
  iree_status_t status = iree_hal_cuda2_dynamic_symbols_initialize(
      iree_allocator_system(), &symbols);
  if (!iree_status_is_ok(status)) {
    iree_status_fprint(stderr, status);
    iree_status_ignore(status);
    std::cerr << "Symbols cannot be loaded, skipping test.";
    GTEST_SKIP();
  }

  int device_count = 0;
  CUDA_CHECK_ERRORS(symbols.cuInit(0));
  CUDA_CHECK_ERRORS(symbols.cuDeviceGetCount(&device_count));
  if (device_count > 0) {
    CUdevice device;
    CUDA_CHECK_ERRORS(symbols.cuDeviceGet(&device, /*ordinal=*/0));
  }

  iree_hal_cuda2_dynamic_symbols_deinitialize(&symbols);
}

#define NCCL_CHECK_ERRORS(expr)     \
  {                                 \
    ncclResult_t status = expr;     \
    ASSERT_EQ(ncclSuccess, status); \
  }

TEST(NCCLDynamicSymbolsTest, CreateFromSystemLoader) {
  iree_hal_cuda2_dynamic_symbols_t cuda_symbols;
  iree_status_t status = iree_hal_cuda2_dynamic_symbols_initialize(
      iree_allocator_system(), &cuda_symbols);
  if (!iree_status_is_ok(status)) {
    iree_status_fprint(stderr, status);
    iree_status_ignore(status);
    std::cerr << "CUDA symbols cannot be loaded, skipping test.";
    GTEST_SKIP();
  }

  iree_hal_cuda2_nccl_dynamic_symbols_t nccl_symbols;
  status = iree_hal_cuda2_nccl_dynamic_symbols_initialize(
      iree_allocator_system(), &cuda_symbols, &nccl_symbols);
  if (!iree_status_is_ok(status)) {
    iree_status_fprint(stderr, status);
    iree_status_ignore(status);
    std::cerr << "CUDA NCCL symbols cannot be loaded, skipping test.";
    GTEST_SKIP();
  }

  int nccl_version = 0;
  NCCL_CHECK_ERRORS(nccl_symbols.ncclGetVersion(&nccl_version));
  ASSERT_EQ(NCCL_VERSION_CODE, nccl_version);
  iree_hal_cuda2_nccl_dynamic_symbols_deinitialize(&nccl_symbols);
  iree_hal_cuda2_dynamic_symbols_deinitialize(&cuda_symbols);
}

}  // namespace
}  // namespace cuda
}  // namespace hal
}  // namespace iree