MegEngine/dnn/src/rocm/batch_normalization/opr_impl.h

/**
 * \file dnn/src/rocm/batch_normalization/opr_impl.h
 * MegEngine is Licensed under the Apache License, Version 2.0 (the "License")
 *
 * Copyright (c) 2014-2021 Megvii Inc. All rights reserved.
 *
 * Unless required by applicable law or agreed to in writing,
 * software distributed under the License is distributed on an
 * "AS IS" BASIS, WITHOUT ARRANTIES OR CONDITIONS OF ANY KIND, either express or
 * implied.
 */
#pragma once
#include "megdnn/oprs.h"

#include "src/rocm/miopen_wrapper.h"

namespace megdnn {
namespace rocm {

namespace batch_normalization {

struct BNTensorDescHolder {
    using ParamDim = param::BN::ParamDim;

    TensorDesc xy_desc;
    BNParamDesc param_desc;
    miopenBatchNormMode_t bn_mode;

    void setup(const TensorLayout& x, const ParamDim& param_dim);
};

}  // namespace batch_normalization

class BNForwardImpl final : public BNForward {
public:
    using BNForward::BNForward;
    void exec(
            _megdnn_tensor_in src, _megdnn_tensor_in bn_scale,
            _megdnn_tensor_in bn_bias, _megdnn_tensor_out mean,
            _megdnn_tensor_out variance, _megdnn_tensor_out batch_mean,
            _megdnn_tensor_out batch_inv_variance, _megdnn_tensor_out reserve,
            _megdnn_tensor_out dst, _megdnn_workspace workspace) override;

    size_t get_workspace_in_bytes(
            const TensorLayout&, const TensorLayout&, const TensorLayout&,
            const TensorLayout&, const TensorLayout&, const TensorLayout&,
            const TensorLayout&, const TensorLayout&, const TensorLayout&) override {
        return 0;
    }
    size_t get_reserve_in_bytes(const TensorLayout&) override { return 0; }

private:
    batch_normalization::BNTensorDescHolder m_tensor_desc;
};

class BNBackwardImpl final : public BNBackward {
public:
    using BNBackward::BNBackward;
    void exec(
            _megdnn_tensor_in x, _megdnn_tensor_in dy,
            _megdnn_tensor_in saved_batch_mean,
            _megdnn_tensor_in saved_batch_inv_variance, _megdnn_tensor_in bn_scale,
            _megdnn_tensor_in reserve, _megdnn_tensor_out d_bn_scale,
            _megdnn_tensor_out d_bn_bias, _megdnn_tensor_out dx,
            _megdnn_workspace workspace) override;

    size_t get_workspace_in_bytes(
            const TensorLayout&, const TensorLayout&, const TensorLayout&,
            const TensorLayout&, const TensorLayout&, const TensorLayout&,
            const TensorLayout&, const TensorLayout&, const TensorLayout&) override {
        return 0;
    }
    size_t get_reserve_in_bytes(const TensorLayout&) override { return 0; }

private:
    batch_normalization::BNTensorDescHolder m_tensor_desc;
};

}  // namespace rocm
}  // namespace megdnn

// vim: syntax=cpp.doxygen