• Stars
    star
    205
  • Rank 190,048 (Top 4 %)
  • Language
    C++
  • License
    Other
  • Created over 8 years ago
  • Updated 3 months ago

Reviews

There are no reviews yet. Be the first to send feedback to the community and the maintainers!

Repository Details

ROCm Platform Runtime: ROCr a HPC market enhanced HSA based runtime

HSA Runtime API and runtime for ROCm

This repository includes the user-mode API interfaces and libraries necessary for host applications to launch compute kernels to available HSA ROCm kernel agents. Reference source code for the core runtime is also available.

Initial target platform requirements

  • CPU: Intel Haswell or newer, Core i5, Core i7, Xeon E3 v4 & v5; Xeon E5 v3
  • GPU: Fiji ASIC (AMD R9 Nano, R9 Fury and R9 Fury X)
  • GPU: Polaris ASIC (AMD RX480)

Source code

The HSA core runtime source code for the ROCR runtime is located in the src subdirectory. Please consult the associated README.md file for contents and build instructions.

Binaries for Ubuntu & Fedora and installation instructions

Pre-built binaries are available for installation from the ROCm package repository. For ROCR, they include:

Core runtime package:

  • HSA include files to support application development on the HSA runtime for the ROCR runtime
  • A 64-bit version of AMD's HSA core runtime for the ROCR runtime

Runtime extension package:

  • A 64-bit version of AMD's runtime tools library
  • A 64-bit version of AMD's runtime image library

The contents of these packages are installed in /opt/rocm/hsa and /opt/rocm by default. The core runtime package depends on the hsakmt-roct-dev package

Installation instructions can be found in the ROCm manifest repository README.md:

https://github.com/RadeonOpenCompute/ROCm

Infrastructure

The HSA runtime is a thin, user-mode API that exposes the necessary interfaces to access and interact with graphics hardware driven by the AMDGPU driver set and the ROCK kernel driver. Together they enable programmers to directly harness the power of AMD discrete graphics devices by allowing host applications to launch compute kernels directly to the graphics hardware.

The capabilities expressed by the HSA Runtime API are:

  • Error handling
  • Runtime initialization and shutdown
  • System and agent information
  • Signals and synchronization
  • Architected dispatch
  • Memory management
  • HSA runtime fits into a typical software architecture stack.

The HSA runtime provides direct access to the graphics hardware to give the programmer more control of the execution. An example of low level hardware access is the support of one or more user mode queues provides programmers with a low-latency kernel dispatch interface, allowing them to develop customized dispatch algorithms specific to their application.

The HSA Architected Queuing Language is an open standard, defined by the HSA Foundation, specifying the packet syntax used to control supported AMD/ATI Radeon (c) graphics devices. The AQL language supports several packet types, including packets that can command the hardware to automatically resolve inter-packet dependencies (barrier AND & barrier OR packet), kernel dispatch packets and agent dispatch packets.

In addition to user mode queues and AQL, the HSA runtime exposes various virtual address ranges that can be accessed by one or more of the system's graphics devices, and possibly the host. The exposed virtual address ranges either support a fine grained or a coarse grained access. Updates to memory in a fine grained region are immediately visible to all devices that can access it, but only one device can have access to a coarse grained allocation at a time. Ownership of a coarse grained region can be changed using the HSA runtime memory APIs, but this transfer of ownership must be explicitly done by the host application.

Programmers should consult the HSA Runtime Programmer's Reference Manual for a full description of the HSA Runtime APIs, AQL and the HSA memory policy.

Known issues

  • Each HSA process creates an internal DMA queue, but there is a system-wide limit of four DMA queues. When the limit is reached HSA processes will use internal kernels for copies.

Disclaimer

The information contained herein is for informational purposes only, and is subject to change without notice. While every precaution has been taken in the preparation of this document, it may contain technical inaccuracies, omissions and typographical errors, and AMD is under no obligation to update or otherwise correct this information. Advanced Micro Devices, Inc. makes no representations or warranties with respect to the accuracy or completeness of the contents of this document, and assumes no liability of any kind, including the implied warranties of noninfringement, merchantability or fitness for particular purposes, with respect to the operation or use of AMD hardware, software or other products described herein. No license, including implied or arising by estoppel, to any intellectual property rights is granted by this document. Terms and limitations applicable to the purchase or use of AMD's products are as set forth in a signed agreement between the parties or in AMD's Standard Terms and Conditions of Sale.

AMD, the AMD Arrow logo, and combinations thereof are trademarks of Advanced Micro Devices, Inc. Other product names used in this publication are for identification purposes only and may be trademarks of their respective companies.

Copyright (c) 2014-2021 Advanced Micro Devices, Inc. All rights reserved.

More Repositories

1

ROCm

AMD ROCm™ Software - GitHub Home
Shell
4,470
star
2

HIP

HIP: C++ Heterogeneous-Compute Interface for Portability
C++
3,398
star
3

MIOpen

AMD's Machine Intelligence Library
Assembly
1,046
star
4

HIPIFY

HIPIFY: Convert CUDA to Portable C++ Code
C++
440
star
5

hcc

HCC is an Open Source, Optimizing C++ Compiler for Heterogeneous Compute currently for the ROCm GPU Computing Platform
C++
425
star
6

rocBLAS

Next generation BLAS implementation for ROCm platform
C++
308
star
7

composable_kernel

Composable Kernel: Performance Portable Programming Model for Machine Learning Tensor Operators
C++
285
star
8

omnitrace

Omnitrace: Application Profiling, Tracing, and Analysis
C++
283
star
9

rccl

ROCm Communication Collectives Library (RCCL)
C++
231
star
10

Tensile

Stretching GPU performance for GEMMs and tensor contractions.
Python
211
star
11

aomp

AOMP is an open source Clang/LLVM based compiler with added support for the OpenMP® API on Radeon™ GPUs. Use this repository for releases, issues, documentation, packaging, and examples.
Fortran
203
star
12

AMDMIGraphX

AMD's graph optimization engine.
C++
181
star
13

rocFFT

Next generation FFT implementation for ROCm
C++
174
star
14

MIVisionX

MIVisionX toolkit is a set of comprehensive computer vision and machine intelligence libraries, utilities, and applications bundled into a single toolkit. AMD MIVisionX also delivers a highly optimized open-source implementation of the Khronos OpenVX™ and OpenVX™ Extensions.
C++
168
star
15

gpufort

GPUFORT: S2S translation tool for CUDA Fortran and Fortran+X in the spirit of hipify
Fortran
159
star
16

rocPRIM

ROCm Parallel Primitives
C++
154
star
17

omniperf

Advanced Profiling and Analytics for AMD Hardware
Python
128
star
18

rocprofiler

ROC profiler library. Profiling with perf-counters and derived metrics.
C
122
star
19

rocm-examples

A collection of examples for the ROCm software stack
C++
121
star
20

rocMLIR

C++
120
star
21

rocSPARSE

Next generation SPARSE implementation for ROCm platform
C++
117
star
22

rocm_smi_lib

ROCm SMI LIB
C++
114
star
23

rocRAND

RAND library for HIP programming language
C++
111
star
24

HIP-CPU

An implementation of HIP that works on CPUs, across OSes.
C++
107
star
25

rocThrust

ROCm Thrust - run Thrust dependent software on AMD GPUs
C++
100
star
26

ROCm-Device-Libs

ROCm Device Libraries
C
99
star
27

rocSOLVER

Next generation LAPACK implementation for ROCm platform
C++
91
star
28

hipCUB

Reusable software components for ROCm developers
C++
79
star
29

rocALUTION

Next generation library for iterative sparse solvers for ROCm platform
C++
74
star
30

rocWMMA

rocWMMA
C++
71
star
31

roctracer

ROCm Tracer Callback/Activity Library for Performance tracing AMD GPUs
C++
67
star
32

hipSPARSE

ROCm SPARSE marshalling library
C++
67
star
33

hipfort

Fortran interfaces for ROCm libraries
Fortran
66
star
34

atmi

Asynchronous Task and Memory Interface, or ATMI, is a runtime framework and programming model for heterogeneous CPU-GPU systems. It provides a consistent, declarative API to create task graphs on CPUs and GPUs (integrated and discrete).
C++
65
star
35

ROCmValidationSuite

The ROCm Validation Suite is a system administrator’s and cluster manager's tool for detecting and troubleshooting common problems affecting AMD GPU(s) running in a high-performance computing environment, enabled using the ROCm software stack on a compatible platform.
C++
61
star
36

rocm-cmake

CMake modules used within the ROCm libraries
CMake
59
star
37

hipFFT

hipFFT is a FFT marshalling library.
C++
52
star
38

amd_matrix_instruction_calculator

A tool for generating information about the matrix multiplication instructions in AMD Radeon™ and AMD Instinct™ accelerators
Python
48
star
39

ROCm-CompilerSupport

The compiler support repository provides various Lightning Compiler related services.
C++
46
star
40

rpp

AMD ROCm Performance Primitives (RPP) library is a comprehensive high-performance computer vision library for AMD processors with HIP/OpenCL/CPU back-ends.
C++
46
star
41

ROCclr

44
star
42

ROCgdb

This is ROCgdb, the ROCm source-level debugger for Linux, based on GDB, the GNU source-level debugger.
C
44
star
43

rocm_bandwidth_test

Bandwidth test for ROCm
C++
41
star
44

HIPCC

HIPCC: HIP compiler driver
C++
39
star
45

Experimental_ROC

Experimental and Intriguing Tools for ROCm
Shell
35
star
46

rocHPCG

HPCG benchmark based on ROCm platform
C++
35
star
47

ROC_SHMEM

ROC_SHMEM intra-kernel networking runtime for AMD dGPUs on the ROCm platform.
C++
34
star
48

MISA

Machine Intelligence Shader Autogen. AMDGPU ML shader code generator. (previously iGEMMgen)
Python
33
star
49

amdsmi

AMD SMI
C++
32
star
50

ROCm.github.io

ROCm Website
32
star
51

TransferBench

TransferBench is a utility capable of benchmarking simultaneous copies between user-specified devices (CPUs/GPUs)
C++
27
star
52

clang-ocl

OpenCL compilation with clang compiler.
CMake
26
star
53

hipSOLVER

ROCm SOLVER marshalling library
C++
25
star
54

aotriton

Ahead of Time (AOT) Triton Math Library
Python
24
star
55

ROCm-OpenCL-Driver

ROCm OpenCL Compiler Tool Driver
C++
24
star
56

rocm-blogs

Jupyter Notebook
22
star
57

rccl-tests

RCCL Performance Benchmark Tests
Cuda
21
star
58

hipRAND

Random number library that generate pseudo-random and quasi-random numbers.
C++
21
star
59

rdc

RDC
C++
19
star
60

ROCdbgapi

The AMD Debugger API is a library that provides all the support necessary for a debugger and other tools to perform low level control of the execution and inspection of execution state of AMD's commercially available GPU architectures.
C++
19
star
61

pyrsmi

python package of rocm-smi-lib
Python
17
star
62

hip-python

HIP Python Low-level Bindings
Shell
16
star
63

hip-tests

C++
15
star
64

roc-stdpar

C++
14
star
65

pytorch-micro-benchmarking

Python
14
star
66

hipify_torch

Python
13
star
67

rocmProfileData

C++
13
star
68

rocm-docs-core

ROCm Documentation Python package for ReadTheDocs build standardization
CSS
12
star
69

rocAL

The AMD rocAL is designed to efficiently decode and process images and videos from a variety of storage formats and modify them through a processing graph programmable by the user.
C++
10
star
70

half

C++
9
star
71

rocprofiler-sdk

C++
9
star
72

rocBLAS-Examples

Examples illustrating usage of the rocBLAS library
C++
9
star
73

OSU_Microbenchmarks

ROCm - UCX enabled OSU_Benchmarks
C
8
star
74

MITuna

Python
7
star
75

rtg_tracer

C++
7
star
76

rocm-spack-pkgs

Repository to host spack recipes for ROCm
Python
6
star
77

rbuild

Rocm build tool
Python
6
star
78

Gromacs

ROCm's implementation of Gromacs
C++
5
star
79

rocm-core

CMake
4
star
80

hip-testsuite

Python
4
star
81

MIFin

Tuna centric MIOpen client
C++
4
star
82

rocm-llvm-python

Low-level Cython and Python bindings to the (ROCm) LLVM C API.
Shell
3
star
83

flang

Mirror of flang repo: The source repo is https://github.com/flang-compiler/flang . Once a day the master branch is updated from the upstream source repo and then locked. AOMP or ROCm developers may commit or create PRs on branch aomp-dev.
C++
3
star
84

hipSPARSELt

C++
2
star
85

aomp-extras

hostcall services library, math library, and utilities
Shell
2
star
86

MIOpenExamples

MIOpen examples
C++
2
star
87

hipOMB

OSU MPI benchmarks with ROCm support
C
1
star
88

numba-hip

HIP backend patch for Numba, the NumPy aware dynamic Python compiler using LLVM.
Python
1
star
89

migraphx-benchmark

1
star
90

tensorcast

Python
1
star
91

rocm-recipes

Recipes for rocm
CMake
1
star
92

rocprofiler-register

CMake
1
star
93

rocm-install-on-windows

1
star