2022-12-13 07:51:04 +08:00
|
|
|
/*************************************************************************
|
|
|
|
|
* Copyright (c) Microsoft Corporation.
|
|
|
|
|
* Licensed under the MIT License.
|
|
|
|
|
************************************************************************/
|
|
|
|
|
|
|
|
|
|
#include "enqueue.h"
|
|
|
|
|
#include "msccl/msccl_parser.h"
|
|
|
|
|
#include "msccl/msccl_setup.h"
|
|
|
|
|
#include "msccl/msccl_status.h"
|
2024-08-22 12:36:07 -05:00
|
|
|
#include "api_trace.h"
|
2025-04-30 13:30:11 -05:00
|
|
|
#include "nvtx_payload_schemas.h"
|
2022-12-13 07:51:04 +08:00
|
|
|
#include <cstdio>
|
|
|
|
|
#include <cstdlib>
|
|
|
|
|
|
2025-04-19 00:21:27 -04:00
|
|
|
using namespace rccl;
|
|
|
|
|
|
2025-06-11 17:52:09 -06:00
|
|
|
NCCL_API(ncclResult_t, mscclLoadAlgo, const char *mscclAlgoFilePath, mscclAlgoHandle_t *mscclAlgoHandle, int rank);
|
|
|
|
|
ncclResult_t mscclLoadAlgo_impl(const char *mscclAlgoFilePath, mscclAlgoHandle_t *mscclAlgoHandle, int rank) {
|
|
|
|
|
// deprecated
|
2025-04-19 00:21:27 -04:00
|
|
|
Recorder::instance().record("mscclLoadAlgo");
|
2025-06-11 17:52:09 -06:00
|
|
|
WARN("mscclLoadAlgo is deprecated. Function call has no effect.");
|
2022-12-13 07:51:04 +08:00
|
|
|
return ncclSuccess;
|
|
|
|
|
}
|
|
|
|
|
|
|
|
|
|
NCCL_API(ncclResult_t, mscclRunAlgo,
|
|
|
|
|
const void* sendBuff, const size_t sendCounts[], const size_t sDisPls[],
|
|
|
|
|
void* recvBuff, const size_t recvCounts[], const size_t rDisPls[],
|
|
|
|
|
size_t count, ncclDataType_t dataType, int root, int peer, ncclRedOp_t op,
|
|
|
|
|
mscclAlgoHandle_t mscclAlgoHandle, ncclComm_t comm, hipStream_t stream);
|
2024-08-22 12:36:07 -05:00
|
|
|
ncclResult_t mscclRunAlgo_impl(
|
2022-12-13 07:51:04 +08:00
|
|
|
const void* sendBuff, const size_t sendCounts[], const size_t sDisPls[],
|
|
|
|
|
void* recvBuff, const size_t recvCounts[], const size_t rDisPls[],
|
|
|
|
|
size_t count, ncclDataType_t dataType, int root, int peer, ncclRedOp_t op,
|
|
|
|
|
mscclAlgoHandle_t mscclAlgoHandle, ncclComm_t comm, hipStream_t stream) {
|
2025-06-11 17:52:09 -06:00
|
|
|
// deprecated
|
2025-04-19 00:21:27 -04:00
|
|
|
Recorder::instance().record("mscclRunAlgo");
|
2025-04-30 13:30:11 -05:00
|
|
|
NVTX3_FUNC_WITH_PARAMS(MSCCL, NcclNvtxParamsMSCCL,
|
|
|
|
|
NVTX3_PAYLOAD(comm ? comm->commHash : 0, count * ncclTypeSize(dataType), op, dataType));
|
2025-06-11 17:52:09 -06:00
|
|
|
WARN("mscclRunAlgo is deprecated. Function call has no effect.");
|
2022-12-13 07:51:04 +08:00
|
|
|
return ncclSuccess;
|
|
|
|
|
}
|
|
|
|
|
|
|
|
|
|
NCCL_API(ncclResult_t, mscclUnloadAlgo, mscclAlgoHandle_t mscclAlgoHandle);
|
2024-08-22 12:36:07 -05:00
|
|
|
ncclResult_t mscclUnloadAlgo_impl(mscclAlgoHandle_t mscclAlgoHandle) {
|
2024-07-04 09:34:38 -06:00
|
|
|
// deprecated
|
2025-04-19 00:21:27 -04:00
|
|
|
Recorder::instance().record("mscclUnloadAlgo");
|
2025-06-11 17:52:09 -06:00
|
|
|
WARN("mscclUnloadAlgo is deprecated. Function call has no effect.");
|
2022-12-13 07:51:04 +08:00
|
|
|
return ncclSuccess;
|
|
|
|
|
}
|