quickstart/IntroNotebooks/onnx_helper.py

#
# SPDX-FileCopyrightText: Copyright (c) 1993-2024 NVIDIA CORPORATION & AFFILIATES. All rights reserved.
# SPDX-License-Identifier: Apache-2.0
#
# 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.
#

import numpy as np
import tensorrt as trt
import weakref

from cuda import cudart


def _cleanup_cuda_resources(d_input, d_output, stream):
    """cleanup function for CUDA resources"""
    if d_input is not None:
        cudart.cudaFree(d_input)
    if d_output is not None:
        cudart.cudaFree(d_output)
    if stream is not None:
        cudart.cudaStreamDestroy(stream)


class ONNXClassifierWrapper:
    def __init__(self, file, target_dtype=np.float32):
        self.stream = None
        self.d_input = None
        self.d_output = None

        self.target_dtype = target_dtype
        self.num_classes = 1000
        self.load(file)

        self._finalizer = weakref.finalize(self, _cleanup_cuda_resources, self.d_input, self.d_output, self.stream)

    def load(self, file):
        with open(file, "rb") as f:
            self.runtime = trt.Runtime(trt.Logger(trt.Logger.WARNING))
            self.engine = self.runtime.deserialize_cuda_engine(f.read())
            self.context = self.engine.create_execution_context()

    def allocate_memory(self, batch):
        self.output = np.empty(
            self.num_classes, dtype=self.target_dtype
        )  # Need to set both input and output precisions to FP16 to fully enable FP16

        # allocate device memory
        err, self.d_input = cudart.cudaMalloc(batch.nbytes)
        if err != cudart.cudaError_t.cudaSuccess:
            raise RuntimeError(f"Failed to allocate input memory: {cudart.cudaGetErrorString(err)}")

        err, self.d_output = cudart.cudaMalloc(self.output.nbytes)
        if err != cudart.cudaError_t.cudaSuccess:
            raise RuntimeError(f"Failed to allocate output memory: {cudart.cudaGetErrorString(err)}")

        tensor_names = [self.engine.get_tensor_name(i) for i in range(self.engine.num_io_tensors)]
        assert len(tensor_names) == 2

        self.context.set_tensor_address(tensor_names[0], int(self.d_input))
        self.context.set_tensor_address(tensor_names[1], int(self.d_output))

        err, self.stream = cudart.cudaStreamCreate()
        if err != cudart.cudaError_t.cudaSuccess:
            raise RuntimeError(f"Failed to create stream: {cudart.cudaGetErrorString(err)}")

        # update the finalizer with new resources
        self._finalizer.detach()
        self._finalizer = weakref.finalize(self, _cleanup_cuda_resources, self.d_input, self.d_output, self.stream)

    def predict(self, batch):  # result gets copied into output
        if self.stream is None:
            self.allocate_memory(batch)

        # transfer input data to device
        err = cudart.cudaMemcpyAsync(
            self.d_input, batch.ctypes.data, batch.nbytes, cudart.cudaMemcpyKind.cudaMemcpyHostToDevice, self.stream
        )
        if err != cudart.cudaError_t.cudaSuccess:
            raise RuntimeError(f"Failed to copy input to device: {cudart.cudaGetErrorString(err)}")

        # execute model
        self.context.execute_async_v3(self.stream)

        # transfer predictions back
        err = cudart.cudaMemcpyAsync(
            self.output.ctypes.data,
            self.d_output,
            self.output.nbytes,
            cudart.cudaMemcpyKind.cudaMemcpyDeviceToHost,
            self.stream,
        )
        if err != cudart.cudaError_t.cudaSuccess:
            raise RuntimeError(f"Failed to copy output from device: {cudart.cudaGetErrorString(err)}")

        # synchronize threads
        err = cudart.cudaStreamSynchronize(self.stream)
        if err != cudart.cudaError_t.cudaSuccess:
            raise RuntimeError(f"Failed to synchronize stream: {cudart.cudaGetErrorString(err)}")

        return self.output

    def cleanup(self):
        """free allocated CUDA memory and destroy stream"""
        if hasattr(self, "_finalizer"):
            self._finalizer()

        self.d_input = None
        self.d_output = None
        self.stream = None


def convert_onnx_to_engine(onnx_filename, engine_filename=None, max_workspace_size=1 << 30, fp16_mode=True):
    logger = trt.Logger(trt.Logger.WARNING)
    with trt.Builder(logger) as builder, builder.create_network() as network, trt.OnnxParser(
        network, logger
    ) as parser, builder.create_builder_config() as builder_config:
        builder_config.set_memory_pool_limit(trt.MemoryPoolType.WORKSPACE, max_workspace_size)
        if fp16_mode:
            builder_config.set_flag(trt.BuilderFlag.FP16)

        print("Parsing ONNX file.")
        with open(onnx_filename, "rb") as model:
            if not parser.parse(model.read()):
                for error in range(parser.num_errors):
                    print(parser.get_error(error))

        print("Building TensorRT engine. This may take a few minutes.")
        serialized_engine = builder.build_serialized_network(network, builder_config)

        if engine_filename:
            with open(engine_filename, "wb") as f:
                f.write(serialized_engine)

        return serialized_engine, logger