cavis/libnd4j/include/helpers/DebugHelper.h

/* ******************************************************************************
 *
 *
 * This program and the accompanying materials are made available under the
 * terms of the Apache License, Version 2.0 which is available at
 * https://www.apache.org/licenses/LICENSE-2.0.
 *
 *  See the NOTICE file distributed with this work for additional
 *  information regarding copyright ownership.
 * 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.
 *
 * SPDX-License-Identifier: Apache-2.0
 ******************************************************************************/

//
// Created by raver119 on 20/04/18.
//

#ifndef LIBND4J_DEBUGHELPER_H
#define LIBND4J_DEBUGHELPER_H

#include <system/pointercast.h>
#include <system/op_boilerplate.h>
#include <system/Environment.h>
#include <helpers/StringUtils.h>
#include <string>


#ifdef __CUDACC__

#include <cuda.h>
#include <driver_types.h>
#include <cuda_runtime_api.h>

#endif
#include <helpers/DebugInfo.h>
namespace sd {
    class NDArray;
    class ND4J_EXPORT DebugHelper {
    public:

    // cuda-specific debug functions
#ifdef __CUDACC__
        static FORCEINLINE void checkErrorCode(cudaStream_t *stream, int opNum = 0) {
            if (Environment::getInstance().isDebug()) {
                cudaError_t res = cudaStreamSynchronize(*stream);

                if (res != 0) {
                    //PRINT_FIRST("Kernel OpNum failed: [%i]\n", opNum);
                    std::string op = "Kernel OpNum failed: [";
                    op += StringUtils::valueToString<int>(opNum);
                    op += "]";

                    throw std::runtime_error(op);
                }
            }
        }

        static FORCEINLINE void checkErrorCode(cudaStream_t *stream, const char *failMessage = nullptr) {
            cudaError_t res = cudaStreamSynchronize(*stream);
            if (res != 0) {
                if (failMessage == nullptr) {
                    std::string op = "CUDA call ended with error code [" + StringUtils::valueToString<int>(res) + std::string("]");
                    throw std::runtime_error(op);
                } else {
                    std::string op = std::string(failMessage) + std::string("Error code [") + StringUtils::valueToString<int>(res) + std::string("]");
                    throw std::runtime_error(op);
                }
            }
        }
#endif
        static DebugInfo debugStatistics(NDArray const* input);
        static void retrieveDebugStatistics(DebugInfo* statistics, NDArray const* input);
    };
}


#endif //LIBND4J_DEBUGHELPER_H