// Copyright (c) 2018 PaddlePaddle Authors. All Rights Reserved. // // Licensed under the Apache License, Version 2.0 (the "License"); // you may not use this file except in compliance with the License. // You may obtain a copy of the License at // // http://www.apache.org/licenses/LICENSE-2.0 // // Unless required by applicable law or agreed to in writing, software // distributed under the License is distributed on an "AS IS" BASIS, // WITHOUT WARRANTIES OR CONDITIONS OF ANY KIND, either express or implied. // See the License for the specific language governing permissions and // limitations under the License. #include "paddle/fluid/framework/details/eager_deletion_op_handle.h" #include "paddle/fluid/framework/ir/memory_optimize_pass/memory_optimization_var_info.h" #include "paddle/fluid/platform/profiler.h" #if defined(PADDLE_WITH_CUDA) || defined(PADDLE_WITH_HIP) #include "paddle/fluid/platform/cuda_device_guard.h" #endif #include namespace paddle { namespace framework { class Variable; } // namespace framework } // namespace paddle namespace paddle { namespace framework { namespace details { EagerDeletionOpHandle::EagerDeletionOpHandle( ir::Node *node, Scope *scope, size_t scope_idx, const platform::Place &place, const std::unordered_set &vars, GarbageCollector *gc) : OpHandleBase(node), scope_(scope), scope_idx_(scope_idx), place_(place), var_infos_(vars.begin(), vars.end()), gc_(gc) { #if defined(PADDLE_WITH_CUDA) || defined(PADDLE_WITH_HIP) if (platform::is_gpu_place(place)) { dev_ctx_ = reinterpret_cast( platform::DeviceContextPool::Instance().Get(place)); if (dynamic_cast(gc_)) { platform::CUDADeviceGuard guard( BOOST_GET_CONST(platform::CUDAPlace, place).device); #ifdef PADDLE_WITH_HIP PADDLE_ENFORCE_CUDA_SUCCESS( hipEventCreateWithFlags(&event_, hipEventDisableTiming)); #else PADDLE_ENFORCE_CUDA_SUCCESS( cudaEventCreateWithFlags(&event_, cudaEventDisableTiming)); #endif PADDLE_ENFORCE_NOT_NULL(event_, platform::errors::InvalidArgument( "The cuda envet created is NULL.")); } } #endif PADDLE_ENFORCE_NE(vars.empty(), true, platform::errors::InvalidArgument( "The variables to be deleted are empty.")); for (auto *var : var_infos_) { PADDLE_ENFORCE_NOT_NULL(var, platform::errors::InvalidArgument( "The memory optimization info is NULL.")); } } EagerDeletionOpHandle::~EagerDeletionOpHandle() { #if defined(PADDLE_WITH_CUDA) || defined(PADDLE_WITH_HIP) if (event_) { auto gpu_place = BOOST_GET_CONST(platform::CUDAPlace, dev_ctx_->GetPlace()); platform::CUDADeviceGuard guard(gpu_place.device); #ifdef PADDLE_WITH_HIP PADDLE_ENFORCE_CUDA_SUCCESS(hipEventDestroy(event_)); #else PADDLE_ENFORCE_CUDA_SUCCESS(cudaEventDestroy(event_)); #endif } #endif } void EagerDeletionOpHandle::InitCUDA() { #if defined(PADDLE_WITH_CUDA) || defined(PADDLE_WITH_HIP) int dev_id = BOOST_GET_CONST(platform::CUDAPlace, dev_ctxes_.begin()->first).device; events_[dev_id] = nullptr; #endif } void EagerDeletionOpHandle::CallOnce() { PADDLE_ENFORCE_EQ( vars_.empty(), true, platform::errors::InvalidArgument( "The variables to be deleted should be initialized here.")); Scope *exec_scope = local_exec_scopes_[0]; for (auto *var_info : var_infos_) { auto *var = exec_scope->FindVar(var_info->Name()); PADDLE_ENFORCE_NOT_NULL( var, platform::errors::NotFound( "The variable(%s) to be inplaced is not found in scope.", var_info->Name())); vars_.emplace_back(var); } } std::string EagerDeletionOpHandle::Name() const { return "eager_deletion"; } void EagerDeletionOpHandle::RunImpl() { if (vars_.size() != var_infos_.size() || is_variant_scope_) { vars_.clear(); CallOnce(); } platform::RecordEvent record_event(Name()); std::deque> garbages; for (size_t i = 0; i < var_infos_.size(); ++i) { auto *var_info = var_infos_[i]; if (var_info->IsSkippedAllMemoryOptimization() || !var_info->DecreaseRefCnt()) { VLOG(4) << "skip memory optimization with var: " << var_info->Name(); continue; } VLOG(2) << "Erase variable " << var_info->Name() << " on " << place_; Variable *var = vars_[i]; if (var->IsType()) { garbages.emplace_back(var->GetMutable()->MoveMemoryHolder()); } else if (var->IsType()) { garbages.emplace_back( var->GetMutable()->mutable_value()->MoveMemoryHolder()); } else if (var->IsType()) { auto *tensor_arr = var->GetMutable(); for (auto &t : *tensor_arr) { garbages.emplace_back(t.MoveMemoryHolder()); } } else { PADDLE_THROW(platform::errors::Unimplemented( "The variable(%s) of type %s is not supported in eager deletion.", framework::ToTypeName(var->Type()), var_info->Name())); } } if (!garbages.empty()) { ClearGarbages(&garbages); } } void EagerDeletionOpHandle::ClearGarbages( std::deque> *garbages) { #if defined(PADDLE_WITH_CUDA) || defined(PADDLE_WITH_HIP) if (event_) { auto compute_stream = dev_ctx_->stream(); auto callback_stream = reinterpret_cast(gc_)->stream(); auto callback_func = [=]() { #ifdef PADDLE_WITH_HIP PADDLE_ENFORCE_CUDA_SUCCESS(hipEventRecord(event_, compute_stream)); PADDLE_ENFORCE_CUDA_SUCCESS( hipStreamWaitEvent(callback_stream, event_, 0)); #else PADDLE_ENFORCE_CUDA_SUCCESS(cudaEventRecord(event_, compute_stream)); PADDLE_ENFORCE_CUDA_SUCCESS( cudaStreamWaitEvent(callback_stream, event_, 0)); #endif }; gc_->Add(std::move(*garbages), callback_func); } else { #endif gc_->Add(std::move(*garbages)); #if defined(PADDLE_WITH_CUDA) || defined(PADDLE_WITH_HIP) } #endif } std::vector EagerDeletionOpHandle::VarsToDelete() const { std::vector var_names; var_names.reserve(var_infos_.size()); for (auto &info : var_infos_) { var_names.emplace_back(info->Name()); } std::sort(var_names.begin(), var_names.end()); return var_names; } } // namespace details } // namespace framework } // namespace paddle