From 296176a4fd3bf61124ebee51928e37426b87b1af Mon Sep 17 00:00:00 2001 From: Wenkai Du Date: Wed, 23 Oct 2019 14:40:17 -0700 Subject: [PATCH] Disable HDP flush for RDMA --- src/transport/net.cc | 4 ++-- 1 file changed, 2 insertions(+), 2 deletions(-) diff --git a/src/transport/net.cc b/src/transport/net.cc index c0dbe5769c..86e332c72f 100644 --- a/src/transport/net.cc +++ b/src/transport/net.cc @@ -547,8 +547,8 @@ ncclResult_t netRecvProxy(struct ncclProxyArgs* args) { if (resources->useGdr) { ncclNetFlush(resources->netRecvComm, localBuff+buffSlot*stepSize, size, mhandle); // Flush local HDP register after local read-back finishes - STORE(resources->curr_hdp_reg, 0x1); - TRACE(NCCL_NET, "Flushing GPU memory via HDP %p", resources->curr_hdp_reg); + //STORE(resources->curr_hdp_reg, 0x1); + //TRACE(NCCL_NET, "Flushing GPU memory via HDP %p", resources->curr_hdp_reg); } STORE(&resources->hostRecvMem->tail, args->head); }