mirror of
https://github.com/ROCm/ROCm.git
synced 2026-01-09 22:58:17 -05:00
Compare commits
423 Commits
| Author | SHA1 | Date | |
|---|---|---|---|
|
|
8c835d14fc | ||
|
|
25dea0df9f | ||
|
|
11968356fc | ||
|
|
c2d8aa3426 | ||
|
|
cc37d13828 | ||
|
|
63ed31781d | ||
|
|
5502ce3c41 | ||
|
|
2adb254db3 | ||
|
|
640b0e0cec | ||
|
|
4b67bbc512 | ||
|
|
4eddbb0f2f | ||
|
|
6dd212c1ff | ||
|
|
1b49b1d598 | ||
|
|
d85d330f17 | ||
|
|
c3efbe0263 | ||
|
|
e72d9d16f2 | ||
|
|
d6ebde1c2b | ||
|
|
c270440e1d | ||
|
|
87212e992e | ||
|
|
b9f3ba6cda | ||
|
|
befa37295e | ||
|
|
6e957870bd | ||
|
|
6906210c51 | ||
|
|
88a2c6a311 | ||
|
|
10366c7bae | ||
|
|
613020c029 | ||
|
|
bbf233a8a0 | ||
|
|
6dfc3154dc | ||
|
|
f38ab28a19 | ||
|
|
5aa6de9001 | ||
|
|
45bc0b6e8f | ||
|
|
46fe870c8d | ||
|
|
2d3d61969f | ||
|
|
6d9651756c | ||
|
|
435eee1860 | ||
|
|
ca7d03f4a6 | ||
|
|
aa48cad227 | ||
|
|
2f3d09e898 | ||
|
|
82ecac74bb | ||
|
|
d693175b09 | ||
|
|
293b24d915 | ||
|
|
950874f674 | ||
|
|
34586f3bd4 | ||
|
|
39790b6ea4 | ||
|
|
b6bf0086d0 | ||
|
|
c81f5e59cf | ||
|
|
353f901378 | ||
|
|
21e76e3fa5 | ||
|
|
488b62219f | ||
|
|
1a5a5efbd3 | ||
|
|
f69a8c19e5 | ||
|
|
6eb53b9931 | ||
|
|
4bfa3780e3 | ||
|
|
c159d23e3c | ||
|
|
fb1709623b | ||
|
|
e853bbe63d | ||
|
|
657ed79dee | ||
|
|
da8a01deb0 | ||
|
|
fbdfeecd14 | ||
|
|
c524da62f0 | ||
|
|
854b2278e9 | ||
|
|
b00a2885ea | ||
|
|
0e53cfa829 | ||
|
|
fef7342549 | ||
|
|
f6565e7f3f | ||
|
|
c56404399b | ||
|
|
664311f4fe | ||
|
|
f45bfbfeed | ||
|
|
f00e4fdf7b | ||
|
|
ae5f7d7be9 | ||
|
|
720760ad63 | ||
|
|
b8a0a90287 | ||
|
|
73ed1122fa | ||
|
|
d50a208edd | ||
|
|
720c7cddc7 | ||
|
|
586a57823a | ||
|
|
c546c5fe3c | ||
|
|
a3ce396048 | ||
|
|
51a22a97f9 | ||
|
|
72ddeef85b | ||
|
|
6cafd3b8fd | ||
|
|
111f8e8409 | ||
|
|
27bc1477f1 | ||
|
|
edc179783c | ||
|
|
65f1d2ee30 | ||
|
|
21cc30341c | ||
|
|
8fac5002c4 | ||
|
|
77764b4887 | ||
|
|
b952ebd666 | ||
|
|
107bbd8abc | ||
|
|
77e77172a4 | ||
|
|
db6dbdcc7a | ||
|
|
924f08a6af | ||
|
|
9406a51332 | ||
|
|
c76270cb72 | ||
|
|
5a82caca04 | ||
|
|
f0d15004a0 | ||
|
|
6a4ae7c703 | ||
|
|
f49275a805 | ||
|
|
93858f653b | ||
|
|
2a1c123ad8 | ||
|
|
7676103619 | ||
|
|
202562d9fe | ||
|
|
c10e1fcfe2 | ||
|
|
a298b06a72 | ||
|
|
2f9e5b68e7 | ||
|
|
a899984e4e | ||
|
|
ccfe2f1a34 | ||
|
|
09196ba787 | ||
|
|
606cc11ebe | ||
|
|
caead32d16 | ||
|
|
75d01b3a23 | ||
|
|
6e3be7651a | ||
|
|
a7d27a43dc | ||
|
|
af5b8e1b93 | ||
|
|
b7e9232861 | ||
|
|
dd86238927 | ||
|
|
f452920919 | ||
|
|
150d8a89da | ||
|
|
7af0f9144b | ||
|
|
ca1f7bc166 | ||
|
|
a0773a297a | ||
|
|
b421b06456 | ||
|
|
754ebcec86 | ||
|
|
27daab068e | ||
|
|
6c70298860 | ||
|
|
29576d17a3 | ||
|
|
92a74beed5 | ||
|
|
4ac14e8095 | ||
|
|
04379e089e | ||
|
|
f5cae8347d | ||
|
|
2759642432 | ||
|
|
8879e01c90 | ||
|
|
5d05e3fdb6 | ||
|
|
5c8047181e | ||
|
|
eba4c1a25c | ||
|
|
01d806e5c1 | ||
|
|
d3ede323b6 | ||
|
|
f5ab073219 | ||
|
|
56e083faac | ||
|
|
fd95c06730 | ||
|
|
0852725b63 | ||
|
|
0bcf42d721 | ||
|
|
789ab1a6db | ||
|
|
65beddddb8 | ||
|
|
917a03430f | ||
|
|
fefcb606fa | ||
|
|
8f3d0331e0 | ||
|
|
9f39dd9458 | ||
|
|
7b52d73349 | ||
|
|
b22c12266a | ||
|
|
c02e11b650 | ||
|
|
9ff3311a58 | ||
|
|
1ca2e8eb87 | ||
|
|
886af2c92f | ||
|
|
7370793bc7 | ||
|
|
20cd1c8e53 | ||
|
|
a65935a02e | ||
|
|
03270a5bd5 | ||
|
|
1d24ed9f9c | ||
|
|
c0876b7ae5 | ||
|
|
6b5707bfd9 | ||
|
|
e6499f1563 | ||
|
|
8ac3b0dcd9 | ||
|
|
7f986f30d1 | ||
|
|
87aa7362a3 | ||
|
|
dde6ae15db | ||
|
|
63eea0e9e7 | ||
|
|
0ffc79f9b8 | ||
|
|
32d48a74b9 | ||
|
|
f6aa4d149e | ||
|
|
6ef9776d50 | ||
|
|
929f927ada | ||
|
|
e0043fa0a1 | ||
|
|
354d8b5615 | ||
|
|
aa17cc4dd0 | ||
|
|
c73d4777b9 | ||
|
|
cd0a756584 | ||
|
|
3d6de36a21 | ||
|
|
19efdc7d7b | ||
|
|
ea1b9f85f5 | ||
|
|
d948b1c844 | ||
|
|
046a4c35a6 | ||
|
|
916bc37963 | ||
|
|
caf1f2e5aa | ||
|
|
e5bbf892a9 | ||
|
|
36e7bc054b | ||
|
|
d8fb001470 | ||
|
|
c67e8b1e2f | ||
|
|
3ec6301df1 | ||
|
|
dffe4ff850 | ||
|
|
77d20a4b1d | ||
|
|
7c52f68bd4 | ||
|
|
c6bb911570 | ||
|
|
e8c598d156 | ||
|
|
e9490d3a0b | ||
|
|
afa76ba6a4 | ||
|
|
da16cd49f3 | ||
|
|
67a3649dce | ||
|
|
d54224f6f5 | ||
|
|
84efdd8493 | ||
|
|
8bd9a52740 | ||
|
|
fbf04f0680 | ||
|
|
33b01a9d73 | ||
|
|
6df6f25b24 | ||
|
|
06b723a026 | ||
|
|
ac085f166f | ||
|
|
269e6dde84 | ||
|
|
664d08dd66 | ||
|
|
9c038ae6cd | ||
|
|
8b11d2d51c | ||
|
|
cd14a94f45 | ||
|
|
cd0c1a7158 | ||
|
|
c135c6ca16 | ||
|
|
29398068cb | ||
|
|
36f1dc6467 | ||
|
|
215a0ca513 | ||
|
|
3af7f0c2b6 | ||
|
|
5798b691bf | ||
|
|
81ca4c3ae8 | ||
|
|
c6c9850a46 | ||
|
|
e6adf53679 | ||
|
|
e88d9b533c | ||
|
|
0a41c5df4e | ||
|
|
e5fab6d043 | ||
|
|
efbfe487e2 | ||
|
|
48f8ce93b8 | ||
|
|
9623efac90 | ||
|
|
258740b489 | ||
|
|
b178fa0666 | ||
|
|
1f0e2c2d7a | ||
|
|
ae0503cad3 | ||
|
|
c1ecf02269 | ||
|
|
8f26cf300e | ||
|
|
725f57b531 | ||
|
|
70f9bf263e | ||
|
|
614f5a6d5f | ||
|
|
445ac506cb | ||
|
|
360fa794e1 | ||
|
|
b58b254b29 | ||
|
|
128e3af2bd | ||
|
|
71993cf7c6 | ||
|
|
a9bb319d96 | ||
|
|
6d5e854277 | ||
|
|
b1b081fa8f | ||
|
|
5a0d73e84f | ||
|
|
1ea6f22864 | ||
|
|
f26b2d6af3 | ||
|
|
ce5e75fb6a | ||
|
|
a84e61094a | ||
|
|
1fc51c91ab | ||
|
|
0ad89931cc | ||
|
|
f73d5b629c | ||
|
|
a13f8c94a4 | ||
|
|
38c8ed8136 | ||
|
|
beebbf0c1d | ||
|
|
7063676c93 | ||
|
|
ce3a851464 | ||
|
|
edcdd2a947 | ||
|
|
444ec79edb | ||
|
|
e7fd4042f4 | ||
|
|
48f21b22e6 | ||
|
|
a8989c7ed0 | ||
|
|
159a69a8ab | ||
|
|
7cf79c8dc4 | ||
|
|
a3340581a7 | ||
|
|
d07fdb05d7 | ||
|
|
c86686a2e7 | ||
|
|
04e2bba9ed | ||
|
|
83f9bd1272 | ||
|
|
4a5104c882 | ||
|
|
40b4be64e6 | ||
|
|
bd790cb4d2 | ||
|
|
35a5c80b55 | ||
|
|
3d7812a48c | ||
|
|
23beff10b8 | ||
|
|
ddc0e1f2b4 | ||
|
|
dd00206633 | ||
|
|
575c4c9a63 | ||
|
|
e4efd1c9f6 | ||
|
|
0b95356d45 | ||
|
|
d4ccc7729e | ||
|
|
239b9ee77e | ||
|
|
c6763c13c4 | ||
|
|
dd33dc7742 | ||
|
|
030455ef47 | ||
|
|
f02621bc8a | ||
|
|
2a4c16ee51 | ||
|
|
4dec756b2d | ||
|
|
77cc24a773 | ||
|
|
7bfed202a0 | ||
|
|
980738d46e | ||
|
|
d7c97882e1 | ||
|
|
c4eb6cd4be | ||
|
|
3e4bda88e7 | ||
|
|
8512273309 | ||
|
|
a1bb81003b | ||
|
|
fbcc9809de | ||
|
|
b834187cae | ||
|
|
260cb81efd | ||
|
|
62c11b68f7 | ||
|
|
c7ea2df946 | ||
|
|
3b442534f8 | ||
|
|
84a097d55d | ||
|
|
7cc5548ea3 | ||
|
|
cf7c039199 | ||
|
|
648af6f3f8 | ||
|
|
4f8d605b12 | ||
|
|
783eec4643 | ||
|
|
dfdb135954 | ||
|
|
2b19ff91a6 | ||
|
|
ac4bd217aa | ||
|
|
7c07ce6e89 | ||
|
|
17dce4c250 | ||
|
|
5a113b7799 | ||
|
|
36d82f83f1 | ||
|
|
2d09dfa9ca | ||
|
|
ae280c5745 | ||
|
|
af228d3b64 | ||
|
|
620a4af0b3 | ||
|
|
549042b40e | ||
|
|
a6e1b016fa | ||
|
|
ca40c6ff09 | ||
|
|
9959f915b3 | ||
|
|
94ef8cd402 | ||
|
|
f8af328270 | ||
|
|
d8e77a4181 | ||
|
|
8b91b9c980 | ||
|
|
378cf1eb7d | ||
|
|
73bb1da071 | ||
|
|
cd4ea291e2 | ||
|
|
eeae755296 | ||
|
|
9f8d733da1 | ||
|
|
389750df8c | ||
|
|
93301e03e2 | ||
|
|
7f15331a67 | ||
|
|
3f4e60c4d0 | ||
|
|
f558960c7e | ||
|
|
c1e71f0dcc | ||
|
|
cf622281f4 | ||
|
|
08257cbca7 | ||
|
|
88d4832e84 | ||
|
|
4a77b8ec63 | ||
|
|
47cb66122f | ||
|
|
cb75f9faeb | ||
|
|
8c1d89e69f | ||
|
|
1a315e093f | ||
|
|
42e58efc65 | ||
|
|
04628c0e85 | ||
|
|
883df8b9f5 | ||
|
|
d46888fe1e | ||
|
|
5dd391eb49 | ||
|
|
04534f7b52 | ||
|
|
3e82c69b04 | ||
|
|
39c0ecbbda | ||
|
|
95c6ddd586 | ||
|
|
3b73215554 | ||
|
|
39ebe697ba | ||
|
|
b6c6392ee4 | ||
|
|
6e5b253e67 | ||
|
|
a93a3fe488 | ||
|
|
dfff4e0f40 | ||
|
|
8bd9db4e8e | ||
|
|
bb158e9d7f | ||
|
|
3387f5b9d8 | ||
|
|
42ed737183 | ||
|
|
eab9718cb8 | ||
|
|
4c7d3cdd4c | ||
|
|
2a0d469a95 | ||
|
|
67197a8232 | ||
|
|
38a3c6dbcf | ||
|
|
a0e3f8b827 | ||
|
|
274fe660e7 | ||
|
|
47b44a6256 | ||
|
|
58b931ebcb | ||
|
|
629d40bfc7 | ||
|
|
906cc8ff0d | ||
|
|
d1bee880ec | ||
|
|
5848c31366 | ||
|
|
81748fb6bc | ||
|
|
31c471261f | ||
|
|
c74c95fc68 | ||
|
|
4285f8a098 | ||
|
|
dd62072371 | ||
|
|
2a71da0814 | ||
|
|
516c0e0959 | ||
|
|
f1bfe97835 | ||
|
|
a2b5a947f6 | ||
|
|
c015023a07 | ||
|
|
30803ce928 | ||
|
|
54d89493a0 | ||
|
|
a17b25b6c6 | ||
|
|
2102aee014 | ||
|
|
6aeb011170 | ||
|
|
9d2c8fc3cd | ||
|
|
45aa402d90 | ||
|
|
c933b9f835 | ||
|
|
5b7d3da9e4 | ||
|
|
567ef05eda | ||
|
|
c2065eaf8d | ||
|
|
2e30be09db | ||
|
|
06afbf1bad | ||
|
|
f18cad3aee | ||
|
|
75b1372a5f | ||
|
|
535a1a6dfb | ||
|
|
318b9d5b9b | ||
|
|
b33cd08098 | ||
|
|
e7e724056a | ||
|
|
70f898a228 | ||
|
|
1a6703a2af | ||
|
|
10c3f0c4bf | ||
|
|
48f0be701c | ||
|
|
d0a595787a | ||
|
|
b06d137097 | ||
|
|
fc75746299 | ||
|
|
fd261de461 | ||
|
|
e28d968135 | ||
|
|
985724f3e4 | ||
|
|
4b454b72ea | ||
|
|
e1e1e4f569 | ||
|
|
c83fabc3b7 | ||
|
|
92ee3d7ec7 | ||
|
|
4ebc4b1513 |
BIN
AMD_ROCm_Release_Notes_v3.5.1.pdf
Normal file
BIN
AMD_ROCm_Release_Notes_v3.5.1.pdf
Normal file
Binary file not shown.
BIN
HIPClang2.png
Normal file
BIN
HIPClang2.png
Normal file
Binary file not shown.
|
After Width: | Height: | Size: 42 KiB |
631
README.md
631
README.md
@@ -1,201 +1,490 @@
|
||||
## Are You Ready to ROCK!
|
||||
The ROCm Platform delivers on the vision of the Boltzmann Initiative, bringing
|
||||
new opportunities in GPU Computing Research.
|
||||
# AMD ROCm v3.5.1 Patch Release
|
||||
|
||||
On November 16th, 2015, the Radeon Technology Group rolled out Boltzmann
|
||||
Initiative with three core foundation elements:
|
||||
AMD ROCm released a maintenance patch release v3.5.1. For more information about the release see,
|
||||
|
||||
* New Linux(R) Driver and Runtime Stack optimized for HPC & Ultra-scale class
|
||||
computing,
|
||||
* Heterogeneous C and C++ compiler which best address the whole system not just
|
||||
a single device
|
||||
* HIP acknowledging the need for platform choice when utilizing GPU computing
|
||||
API
|
||||
https://github.com/RadeonOpenCompute/ROCm/blob/master/AMD_ROCm_Release_Notes_v3.5.1.pdf
|
||||
|
||||
Using our knowledge of the HSA Standards and, more importantly, the HSA 1.1
|
||||
Runtime we have been able to successfully extended support to the dGPU with
|
||||
critical features for NUMA class acceleration. As a result, the ROCK driver is
|
||||
composed of several components based on our efforts to develop the
|
||||
Heterogeneous System Architecture for APUs, including the new AMDGPU driver,
|
||||
the Kernel Fusion Driver (KFD), the HSA+ Runtime and an LLVM based compilation
|
||||
stack for the building of key language support. This support starts with AMD’s
|
||||
FIJI Family of dGPU, but support is planned to expand to include future ASICS.
|
||||
|
||||
### The Latest ROCm Platform - ROCm 1.1
|
||||
The latest tested version of the drivers, tools, libraries and source code for
|
||||
the ROCm platform have been released and are available under the roc-1.1.0 tag
|
||||
of the following GitHub repositories:
|
||||
|
||||
* [ROCK-Kernel-Driver](https://github.com/RadeonOpenCompute/ROCK-Kernel-Driver/tree/roc-1.1.0)
|
||||
* [ROCR-Runtime](https://github.com/RadeonOpenCompute/ROCR-Runtime/tree/roc-1.1.0)
|
||||
* [ROCT-Thunk-Interface](https://github.com/RadeonOpenCompute/ROCT-Thunk-Interface/tree/roc-1.1.0)
|
||||
* [HCC compiler](https://github.com/RadeonOpenCompute/hcc/tree/roc-1.1.0)
|
||||
* [LLVM-AMDGPU-Assembler-Extra](https://github.com/RadeonOpenCompute/LLVM-AMDGPU-Assembler-Extra/tree/roc-1.1.0)
|
||||
* [ROC-smi](https://github.com/RadeonOpenCompute/ROC-smi/tree/roc-1.1.0)
|
||||
* [ROCnRDMA](https://github.com/RadeonOpenCompute/ROCnRDMA/tree/roc-1.1.0)
|
||||
* [HIP](https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/tree/roc-1.1.0)
|
||||
* [HIP-Examples](https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP-Examples/tree/roc-1.1.0)
|
||||
# AMD ROCm Release Notes v3.5.0
|
||||
This page describes the features, fixed issues, and information about downloading and installing the ROCm software.
|
||||
It also covers known issues and deprecated features in the ROCm v3.5.0 release.
|
||||
|
||||
In addition the following mirror repositories that support the HCC compiler are
|
||||
also available on GitHub, and frozen for the roc-1.1.0 release:
|
||||
- [Supported Operating Systems and Documentation Updates](#Supported-Operating-Systems-and-Documentation-Updates)
|
||||
* [Supported Operating Systems](#Supported-Operating-Systems)
|
||||
* [Documentation Updates](#Documentation-Updates)
|
||||
|
||||
- [What\'s New in This Release](#Whats-New-in-This-Release)
|
||||
* [Upgrading to This Release](#Upgrading-to-This-Release)
|
||||
* [Heterogeneous-Compute Interface for Portability](#Heterogeneous-Compute-Interface-for-Portability)
|
||||
* [Radeon Open Compute Common Language Runtime](#Radeon-Open-Compute-Common-Language-Runtime)
|
||||
* [OpenCL Runtime](#OpenCL-Runtime)
|
||||
* [AMD ROCm GNU Debugger ROCgdb](#AMD-ROCm-GNU-Debugger-ROCgdb)
|
||||
* [AMD ROCm Debugger API Library](#AMD-ROCm-Debugger-API-Library)
|
||||
* [rocProfiler Dispatch Callbacks Start/Stop API](#rocProfiler-Dispatch-Callbacks-Start-Stop-API)
|
||||
* [ROCm Communications Collective Library](#ROCm-Communications-Collective-Library)
|
||||
* [NVIDIA Communications Collective Library Version Compatibility](#NVIDIA-Communications-Collective-Library-Version-Compatibility)
|
||||
* [MIOpen Optional Kernel Package Installation](#MIOpen-Optional-Kernel-Package-Installation)
|
||||
* [New SMI Event Interface and Library](#New-SMI-Event-Interface-and-Library)
|
||||
* [API for CPU Affinity](#API-for-CPU-Affinity)
|
||||
* [Radeon Performance Primitives Library](#Radeon-Performance-Primitives-Library)
|
||||
|
||||
|
||||
- [Fixed Issues](#Fixed-Issues)
|
||||
|
||||
* [llvm](https://github.com/RadeonOpenCompute/llvm/tree/roc-1.1.0)
|
||||
* [clang](https://github.com/RadeonOpenCompute/clang/tree/roc-1.1.0)
|
||||
- [Known Issues](#Known-Issues)
|
||||
|
||||
### Installing from AMD ROCm Repositories
|
||||
AMD is hosting both debian and rpm repositories for the ROCm 1.1 packages. The
|
||||
packages in both repositories have been signed to ensure package integrity.
|
||||
Directions for each repository are given below:
|
||||
- [Deprecations](#Deprecations)
|
||||
* [Heterogeneous Compute Compiler](#Heterogeneous-Compute-Compiler)
|
||||
|
||||
#### Supported Operating Systems
|
||||
- [Deploying ROCm](#Deploying-ROCm)
|
||||
|
||||
- [Hardware and Software Support](#Hardware-and-Software-Support)
|
||||
|
||||
The ROCm platform has been tested on the following operating systems:
|
||||
* Ubuntu 14.04.04
|
||||
* Fedora 23
|
||||
- [Machine Learning and High Performance Computing Software Stack for AMD GPU](#Machine-Learning-and-High-Performance-Computing-Software-Stack-for-AMD-GPU)
|
||||
* [ROCm Binary Package Structure](#ROCm-Binary-Package-Structure)
|
||||
* [ROCm Platform Packages](#ROCm-Platform-Packages)
|
||||
|
||||
|
||||
There is experimental support for the following operating systems:
|
||||
* Ubuntu 16.04
|
||||
* Fedora 22
|
||||
|
||||
#### Debian repository - apt-get
|
||||
# Supported Operating Systems and Documentation Updates
|
||||
|
||||
##### Add the ROCm apt repository
|
||||
For Debian based systems, like Ubuntu, configure the Debian ROCm repository as
|
||||
follows:
|
||||
## Supported Operating Systems
|
||||
|
||||
```shell
|
||||
wget -qO - http://packages.amd.com/rocm/apt/debian/rocm.gpg.key | sudo apt-key add -
|
||||
sudo sh -c 'echo deb [arch=amd64] http://packages.amd.com/rocm/apt/debian/ trusty main > /etc/apt/sources.list.d/rocm.list'
|
||||
The AMD ROCm v3.5.x platform is designed to support the following operating systems:
|
||||
|
||||
* Ubuntu 16.04.6(Kernel 4.15) and 18.04.4(Kernel 5.3)
|
||||
* CentOS 7.7 (Kernel 3.10-1062) and RHEL 7.8(Kernel 3.10.0-1127)(Using devtoolset-7 runtime support)
|
||||
* SLES 15 SP1
|
||||
* CentOS and RHEL 8.1(Kernel 4.18.0-147)
|
||||
|
||||
|
||||
## Documentation Updates
|
||||
|
||||
### HIP-Clang Compile
|
||||
|
||||
* [HIP FAQ - Transition from HCC to HIP-Clang](https://rocmdocs.amd.com/en/latest/Programming_Guides/HIP-FAQ.html#hip-faq)
|
||||
* [HIP-Clang Porting Guide](https://rocmdocs.amd.com/en/latest/Programming_Guides/HIP-porting-guide.html#hip-porting-guide)
|
||||
* [HIP - Glossary of Terms](https://rocmdocs.amd.com/en/latest/ROCm_Glossary/ROCm-Glossary.html)
|
||||
|
||||
### AMD ROCDebugger (ROCgdb)
|
||||
|
||||
* [ROCgdb User Guide](https://github.com/RadeonOpenCompute/ROCm/blob/master/gdb.pdf)
|
||||
* [ROCgdbapi Guide](https://github.com/RadeonOpenCompute/ROCm/blob/master/amd-dbgapi.pdf)
|
||||
|
||||
### AMD ROCm Systems Management Interface
|
||||
|
||||
* [System Management Interface Event API Guide](https://github.com/RadeonOpenCompute/ROCm/blob/master/ROCm_SMI_Manual.pdf)
|
||||
|
||||
### AMD ROCm Deep Learning
|
||||
|
||||
* [MIOpen API](https://github.com/ROCmSoftwarePlatform/MIOpen)
|
||||
|
||||
### AMD ROCm Glossary of Terms
|
||||
|
||||
* [Updated Glossary of Terms and Definitions](https://rocmdocs.amd.com/en/latest/ROCm_Glossary/ROCm-Glossary.html)
|
||||
|
||||
### General AMD ROCm Documentatin Links
|
||||
|
||||
Access the following links for more information on:
|
||||
|
||||
* For AMD ROCm documentation, see
|
||||
|
||||
https://rocmdocs.amd.com/en/latest/
|
||||
|
||||
* For installation instructions on supported platforms, see
|
||||
|
||||
https://rocmdocs.amd.com/en/latest/Installation_Guide/Installation-Guide.html
|
||||
|
||||
* For AMD ROCm binary structure, see
|
||||
|
||||
https://rocmdocs.amd.com/en/latest/Installation_Guide/Installation-Guide.html#machine-learning-and-high-performance-computing-software-stack-for-amd-gpu-v3-3-0
|
||||
|
||||
* For AMD ROCm Release History, see
|
||||
|
||||
https://rocmdocs.amd.com/en/latest/Installation_Guide/Installation-Guide.html#amd-rocm-version-history
|
||||
|
||||
|
||||
# What\'s New in This Release
|
||||
|
||||
## Upgrading to This Release
|
||||
|
||||
You must perform a fresh and a clean AMD ROCm install to successfully upgrade from v3.3 to v3.5. The following changes apply in this release:
|
||||
|
||||
* HCC is deprecated and replaced with the HIP-Clang compiler
|
||||
* HIP-HCC runtime is changed to Radeon Open Compute Common Language Runtime (HIP-ROCClr)
|
||||
* In the v3.5 release, the firmware is separated from the kernel package. The difference is as follows:
|
||||
* v3.5 release has two separate rock-dkms and rock-dkms-firmware packages
|
||||
* v3.3 release had the firmware as part of the rock-dkms package
|
||||
|
||||
|
||||
## rocProf Command Line Tool Python Requirement
|
||||
SQLite3 is a required Python module for the rocprof command-line tool. You can install the SQLite3 Python module using the pip utility and set env var ROCP_PYTHON_VERSION to the Python version, which includes the SQLite3 module.
|
||||
|
||||
|
||||
|
||||
## Heterogeneous-Compute Interface for Portability
|
||||
|
||||
In this release, the Heterogeneous Compute Compiler (HCC) compiler is deprecated and the HIP-Clang compiler is introduced for compiling Heterogeneous-Compute Interface for Portability (HIP) programs.
|
||||
|
||||
NOTE: The HCC environment variables will be gradually deprecated in subsequent releases.
|
||||
|
||||
The majority of the codebase for the HIP-Clang compiler has been upstreamed to the Clang trunk. The HIP-Clang implementation has undergone a strict code review by the LLVM/Clang community and comprehensive tests consisting of LLVM/Clang build bots. These reviews and tests resulted in higher productivity, code quality, and lower cost of maintenance.
|
||||
|
||||

|
||||
|
||||
For most HIP applications, the transition from HCC to HIP-Clang is transparent and efficient as the HIPCC and HIP cmake files automatically choose compilation options for HIP-Clang and hide the difference between the HCC and HIP-Clang code. However, minor changes may be required as HIP-Clang has a stricter syntax and semantic checks compared to HCC.
|
||||
|
||||
NOTE: Native HCC language features are no longer supported.
|
||||
|
||||
## Radeon Open Compute Common Language Runtime
|
||||
In this release, the HIP runtime API is implemented on top of Radeon Open Compute Common Language Runtime (ROCclr). ROCclr is an abstraction layer that provides the ability to interact with different runtime backends such as ROCr.
|
||||
|
||||
## OpenCL Runtime
|
||||
The following OpenCL runtime changes are made in this release:
|
||||
|
||||
* AMD ROCm OpenCL Runtime extends support to OpenCL2.2
|
||||
* The developer branch is changed from master to master-next
|
||||
|
||||
## AMD ROCm GNU Debugger (ROCgdb)
|
||||
The AMD ROCm Debugger (ROCgdb) is the AMD ROCm source-level debugger for Linux based on the GNU Debugger (GDB). It enables heterogeneous debugging on the AMD ROCm platform of an x86-based host architecture along with AMD GPU architectures and supported by the AMD Debugger API Library (ROCdbgapi).
|
||||
|
||||
The AMD ROCm Debugger is installed by the rocm-gdb package. The rocm-gdb package is part of the rocm-dev meta-package, which is in the rocm-dkms package.
|
||||
|
||||
The current AMD ROCm Debugger (ROCgdb) is an initial prototype that focuses on source line debugging. Note, symbolic variable debugging capabilities are not currently supported.
|
||||
|
||||
You can use the standard GDB commands for both CPU and GPU code debugging. For more information about ROCgdb, refer to the ROCgdb User Guide, which is installed at:
|
||||
|
||||
* /opt/rocm/share/info/gdb.info as a texinfo file
|
||||
* /opt/rocm/share/doc/gdb/gdb.pdf as a PDF file
|
||||
|
||||
The AMD ROCm Debugger User Guide is available as a PDF at:
|
||||
|
||||
https://github.com/RadeonOpenCompute/ROCm/blob/master/gdb.pdf
|
||||
|
||||
For more information about GNU Debugger (GDB), refer to the GNU Debugger (GDB) web site at: http://www.gnu.org/software/gdb
|
||||
|
||||
|
||||
## AMD ROCm Debugger API Library
|
||||
|
||||
The AMD ROCm Debugger API Library (ROCdbgapi) implements an AMD GPU debugger application programming interface (API) that provides the support necessary for a client of the library to control the execution and inspect the state of AMD GPU devices.
|
||||
|
||||
The following AMD GPU architectures are supported:
|
||||
* Vega 10
|
||||
* Vega 7nm
|
||||
|
||||
The AMD ROCm Debugger API Library is installed by the rocm-dbgapi package. The rocm-gdb package is part of the rocm-dev meta-package, which is in the rocm-dkms package.
|
||||
The AMD ROCm Debugger API Specification is available as a PDF at:
|
||||
|
||||
https://github.com/RadeonOpenCompute/ROCm/blob/master/amd-dbgapi.pdf
|
||||
|
||||
## rocProfiler Dispatch Callbacks Start Stop API
|
||||
|
||||
In this release, a new rocprofiler start/stop API is added to enable/disable GPU kernel HSA dispatch callbacks. The callback can be registered with the 'rocprofiler_set_hsa_callbacks' API. The API helps you eliminate some profiling performance impact by invoking the profiler only for kernel dispatches of interest. This optimization will result in significant performance gains.
|
||||
|
||||
The API provides the following functions:
|
||||
* *hsa_status_t rocprofiler_start_queue_callbacks();* is used to start profiling
|
||||
* *hsa_status_t rocprofiler_stop_queue_callbacks();* is used to stop profiling.
|
||||
|
||||
For more information on kernel dispatches, see the HSA Platform System Architecture Specification guide at http://www.hsafoundation.com/standards/.
|
||||
|
||||
## ROCm Communications Collective Library
|
||||
The ROCm Communications Collective Library (RCCL) consists of the following enhancements:
|
||||
* Re-enable target 0x803
|
||||
* Build time improvements for the HIP-Clang compiler
|
||||
|
||||
### NVIDIA Communications Collective Library Version Compatibility
|
||||
AMD RCCL is now compatible with NVIDIA Communications Collective Library (NCCL) v2.6.4 and provides the following features:
|
||||
* Network interface improvements with API v3
|
||||
* Network topology detection
|
||||
* Improved CPU type detection
|
||||
* Infiniband adaptive routing support
|
||||
|
||||
## MIOpen Optional Kernel Package Installation
|
||||
MIOpen provides an optional pre-compiled kernel package to reduce startup latency.
|
||||
|
||||
NOTE: The installation of this package is optional. MIOpen will continue to function as expected even if you choose to not install the pre-compiled kernel package. This is because MIOpen compiles the kernels on the target machine once the kernel is run. However, the compilation step may significantly increase the startup time for different operations.
|
||||
|
||||
To install the kernel package for your GPU architecture, use the following command:
|
||||
|
||||
*apt-get install miopen-kernels-<arch>-<num cu>*
|
||||
|
||||
* <arch> is the GPU architecture. For example, gfx900, gfx906
|
||||
* <num cu> is the number of CUs available in the GPU. For example, 56 or 64
|
||||
|
||||
|
||||
## New SMI Event Interface and Library
|
||||
|
||||
A Systems Management Interface (SMI) event interface is added to the kernel and ROCm SMI lib for system administrators to get notified when specific events occur. On the kernel side, AMDKFD_IOC_SMI_EVENTS input/output control is enhanced to allow notifications propagation to user mode through the event channel.
|
||||
|
||||
On the ROCm SMI lib side, APIs are added to set an event mask and receive event notifications with a timeout option. Further, ROCm SMI API details can be found in the PDF generated by Doxygen from source or by referring to the rocm_smi.h header file (see the rsmi_event_notification_* functions).
|
||||
|
||||
For the more details about ROCm SMI API, see
|
||||
|
||||
https://github.com/RadeonOpenCompute/ROCm/blob/master/ROCm_SMI_Manual.pdf
|
||||
|
||||
## API for CPU Affinity
|
||||
A new API is introduced for aiding applications to select the appropriate memory node for a given accelerator(GPU).
|
||||
|
||||
The API for CPU affinity has the following signature:
|
||||
|
||||
*rsmi_status_t rsmi_topo_numa_affinity_get(uint32_t dv_ind, uint32_t *numa_node);*
|
||||
|
||||
This API takes as input, device index (dv_ind), and returns the NUMA node (CPU affinity), stored at the location pointed by numa_node pointer, associated with the device.
|
||||
|
||||
Non-Uniform Memory Access (NUMA) is a computer memory design used in multiprocessing, where the memory access time depends on the memory location relative to the processor.
|
||||
|
||||
## Radeon Performance Primitives Library
|
||||
The new Radeon Performance Primitives (RPP) library is a comprehensive high-performance computer vision library for AMD (CPU and GPU) with the HIP and OpenCL backend. The target operating system is Linux.
|
||||
|
||||

|
||||
|
||||
For more information about prerequisites and library functions, see
|
||||
|
||||
https://github.com/GPUOpen-ProfessionalCompute-Libraries/MIVisionX/tree/master/docs
|
||||
|
||||
# Fixed Issues
|
||||
|
||||
## Device printf Support for HIP-Clang
|
||||
HIP now supports the use of printf in the device code. The parameters and return value for the device-side printf follow the POSIX.1 standard, with the exception that the "%n" specifier is not supported. A call to printf blocks the calling wavefront until the operation is completely processed by the host.
|
||||
|
||||
No host-side runtime calls by the application are needed to cause the output to appear. There is also no limit on the number of device-side calls to printf or the amount of data that is printed.
|
||||
|
||||
For more details, refer the HIP Programming Guide at:
|
||||
https://rocmdocs.amd.com/en/latest/Programming_Guides/HIP-GUIDE.html#hip-guide
|
||||
|
||||
## Assertions in HIP Device Code
|
||||
Previously, a failing assertion caused early termination of kernels and the application to exit with a line number, file, and failing condition printed to the screen.
|
||||
This issue is now fixed and the assert() and abort() functions are implemented for HIP device code.
|
||||
NOTE: There may be a performance impact in the use of device assertions in its current form.
|
||||
|
||||
You may choose to disable the assertion in the production code. For example, to disable an assertion of:
|
||||
|
||||
*assert(foo != 0);*
|
||||
|
||||
you may comment it out as:
|
||||
|
||||
*//assert(foo != 0);*
|
||||
|
||||
NOTE: Assertions are currently enabled by default.
|
||||
|
||||
# Known Issues
|
||||
The following are the known issues in the v3.5 release.
|
||||
|
||||
## HIPify-Clang Installation Failure on CentOS/RHEL
|
||||
|
||||
HIPify-Clang fails to install on CentOS/RHEL with the following error:
|
||||
|
||||
*file from install of hipify-clang conflicts with file from package hip-base*
|
||||
|
||||
**Workaround**: This is a known issue and the following workaround is recommended for a successful installation of HIPify-Clang on CentOS/RHEL:
|
||||
|
||||
* Download HIPify-Clang RPM. For example, *hipify-clang-11.0.0.x86_64.rpm*
|
||||
* Perform a force install using the following command:
|
||||
|
||||
*sudo rpm -ivh --force hipify-clang-11.0.0.x86_64.rpm*
|
||||
|
||||
|
||||
## Failure to Process Breakpoint before Queue Destroy Results in ROCm Debugger Error
|
||||
When ROCgdb is in non-stop mode with an application that rapidly creates and destroys queues, a breakpoint may be reported that is not processed by the debugger before the queue is deleted. In some cases, this can result in the following error that prevents further debugging:
|
||||
|
||||
*[amd-dbgapi]: fatal error: kfd_queue_id 2 should have been reported as a NEW_QUEUE before next_pending_event failed (rc=-2)*
|
||||
|
||||
There are no known workarounds at this time.
|
||||
|
||||
## Failure to Process Breakpoint before Queue Destroy Results in ROCm Debugger API Error
|
||||
|
||||
When the ROCdbgapi library is used with an application that rapidly creates and destroys queues, a breakpoint may be reported that is not processed by the client before the queue is deleted. In some cases, this can result in a fatal error and the following error log message is produced:
|
||||
|
||||
*[amd-dbgapi]: fatal error: kfd_queue_id 2 should have been reported as a NEW_QUEUE before next_pending_event failed (rc=-2)*
|
||||
|
||||
There are no known workarounds at this time.
|
||||
|
||||
## rocThrust and hipCUB Unit Test Failures
|
||||
|
||||
The following unit test failures have been observed due to known issues in the ROCclr runtime.
|
||||
|
||||
rocThrust
|
||||
* sort
|
||||
* sort_by_key
|
||||
|
||||
hipCUB
|
||||
* BlockDiscontinuity
|
||||
* BlockExchange
|
||||
* BlockHistogram
|
||||
* BlockRadixSort
|
||||
* BlockReduce
|
||||
* BlockScan
|
||||
|
||||
There are no known workarounds in the current release.
|
||||
|
||||
|
||||
## Multiple GPU Configuration Freezes with Imagenet Training and tf_cnn_benchmark on TensorFlow
|
||||
|
||||
A random freeze has been observed with Imagenet training and tf_cnn_benchmark on TensorFlow when multiple GPU configurations are involved.
|
||||
|
||||
There is no freeze observed with single GPUs.
|
||||
|
||||
There are no known workarounds at this time.
|
||||
|
||||
## Issue with Running AMD ROCm v3.3 User Mode with AMD ROCm v3.5 DKMS Kernel Module
|
||||
|
||||
Running AMD ROCm v3.3 in the user mode with the AMD ROCm v3.5 DKMS kernel module will cause the following features to be broken:
|
||||
|
||||
* IPC import/export, cross memory copy (used by UCX and MPI)
|
||||
* Experimental GDB support
|
||||
|
||||
**Resolution**: Install ROCm v3.5 Thunk (*Hsakmt*) when using ROCm 3.5 Kernel Fusion Driver (KFD).
|
||||
|
||||
|
||||
## SQLite3 Library Not Found in ROCProfiler
|
||||
|
||||
The ROCProfiler tool appears to be broken when the SQLite3 library is not found.
|
||||
|
||||
**Resolution**: Install the SQLite3 Python module separately and ensure the environment variable is set to ROCP_PYTHON_VERSION to confirm the Python version, which includes the SQLite3 module.
|
||||
|
||||
|
||||
|
||||
# Deprecations
|
||||
Install ROCm v3.5 Thunk (Hsakmt) when using ROCm 3.5 Kernel Fusion Driver (KFD). You can access the Thunk package at:
|
||||
|
||||
https://github.com/RadeonOpenCompute/ROCT-Thunk-Interface
|
||||
## Heterogeneous Compute Compiler
|
||||
In this release, the Heterogeneous Compute Compiler (HCC) compiler is deprecated and the HIP-Clang compiler is introduced for compiling Heterogeneous-Compute Interface for Portability (HIP) programs.
|
||||
|
||||
For more information, see HIP documentation at:
|
||||
https://rocmdocs.amd.com/en/latest/Programming_Guides/Programming-Guides.html
|
||||
|
||||
|
||||
## Deploying ROCm
|
||||
AMD hosts both Debian and RPM repositories for the ROCm v3.5.x packages.
|
||||
|
||||
For more information on ROCM installation on all platforms, see
|
||||
|
||||
https://rocmdocs.amd.com/en/latest/Installation_Guide/Installation-Guide.html
|
||||
|
||||
## Hardware and Software Support
|
||||
ROCm is focused on using AMD GPUs to accelerate computational tasks such as machine learning, engineering workloads, and scientific computing.
|
||||
In order to focus our development efforts on these domains of interest, ROCm supports a targeted set of hardware configurations which are detailed further in this section.
|
||||
|
||||
#### Supported GPUs
|
||||
Because the ROCm Platform has a focus on particular computational domains, we offer official support for a selection of AMD GPUs that are designed to offer good performance and price in these domains.
|
||||
|
||||
ROCm officially supports AMD GPUs that use following chips:
|
||||
|
||||
* GFX8 GPUs
|
||||
* "Fiji" chips, such as on the AMD Radeon R9 Fury X and Radeon Instinct MI8
|
||||
* "Polaris 10" chips, such as on the AMD Radeon RX 580 and Radeon Instinct MI6
|
||||
* GFX9 GPUs
|
||||
* "Vega 10" chips, such as on the AMD Radeon RX Vega 64 and Radeon Instinct MI25
|
||||
* "Vega 7nm" chips, such as on the Radeon Instinct MI50, Radeon Instinct MI60 or AMD Radeon VII
|
||||
|
||||
ROCm is a collection of software ranging from drivers and runtimes to libraries and developer tools.
|
||||
Some of this software may work with more GPUs than the "officially supported" list above, though AMD does not make any official claims of support for these devices on the ROCm software platform.
|
||||
The following list of GPUs are enabled in the ROCm software, though full support is not guaranteed:
|
||||
|
||||
* GFX8 GPUs
|
||||
* "Polaris 11" chips, such as on the AMD Radeon RX 570 and Radeon Pro WX 4100
|
||||
* "Polaris 12" chips, such as on the AMD Radeon RX 550 and Radeon RX 540
|
||||
* GFX7 GPUs
|
||||
* "Hawaii" chips, such as the AMD Radeon R9 390X and FirePro W9100
|
||||
|
||||
As described in the next section, GFX8 GPUs require PCI Express 3.0 (PCIe 3.0) with support for PCIe atomics. This requires both CPU and motherboard support. GFX9 GPUs require PCIe 3.0 with support for PCIe atomics by default, but they can operate in most cases without this capability.
|
||||
|
||||
The integrated GPUs in AMD APUs are not officially supported targets for ROCm.
|
||||
As described [below](#limited-support), "Carrizo", "Bristol Ridge", and "Raven Ridge" APUs are enabled in our upstream drivers and the ROCm OpenCL runtime.
|
||||
However, they are not enabled in our HCC or HIP runtimes, and may not work due to motherboard or OEM hardware limitations.
|
||||
As such, they are not yet officially supported targets for ROCm.
|
||||
|
||||
For a more detailed list of hardware support, please see [the following documentation](https://rocm.github.io/hardware.html).
|
||||
|
||||
#### Supported CPUs
|
||||
As described above, GFX8 GPUs require PCIe 3.0 with PCIe atomics in order to run ROCm.
|
||||
In particular, the CPU and every active PCIe point between the CPU and GPU require support for PCIe 3.0 and PCIe atomics.
|
||||
The CPU root must indicate PCIe AtomicOp Completion capabilities and any intermediate switch must indicate PCIe AtomicOp Routing capabilities.
|
||||
|
||||
Current CPUs which support PCIe Gen3 + PCIe Atomics are:
|
||||
|
||||
* AMD Ryzen CPUs
|
||||
* The CPUs in AMD Ryzen APUs
|
||||
* AMD Ryzen Threadripper CPUs
|
||||
* AMD EPYC CPUs
|
||||
* Intel Xeon E7 v3 or newer CPUs
|
||||
* Intel Xeon E5 v3 or newer CPUs
|
||||
* Intel Xeon E3 v3 or newer CPUs
|
||||
* Intel Core i7 v4, Core i5 v4, Core i3 v4 or newer CPUs (i.e. Haswell family or newer)
|
||||
* Some Ivy Bridge-E systems
|
||||
|
||||
Beginning with ROCm 1.8, GFX9 GPUs (such as Vega 10) no longer require PCIe atomics.
|
||||
We have similarly opened up more options for number of PCIe lanes.
|
||||
GFX9 GPUs can now be run on CPUs without PCIe atomics and on older PCIe generations, such as PCIe 2.0.
|
||||
This is not supported on GPUs below GFX9, e.g. GFX8 cards in the Fiji and Polaris families.
|
||||
|
||||
If you are using any PCIe switches in your system, please note that PCIe Atomics are only supported on some switches, such as Broadcom PLX.
|
||||
When you install your GPUs, make sure you install them in a PCIe 3.1.0 x16, x8, x4, or x1 slot attached either directly to the CPU's Root I/O controller or via a PCIe switch directly attached to the CPU's Root I/O controller.
|
||||
|
||||
In our experience, many issues stem from trying to use consumer motherboards which provide physical x16 connectors that are electrically connected as e.g. PCIe 2.0 x4, PCIe slots connected via the Southbridge PCIe I/O controller, or PCIe slots connected through a PCIe switch that does
|
||||
not support PCIe atomics.
|
||||
|
||||
If you attempt to run ROCm on a system without proper PCIe atomic support, you may see an error in the kernel log (`dmesg`):
|
||||
```
|
||||
kfd: skipped device 1002:7300, PCI rejects atomics
|
||||
```
|
||||
|
||||
##### Install or Update
|
||||
Next, update the apt-get repository list and install/update the rocm package:
|
||||
Experimental support for our Hawaii (GFX7) GPUs (Radeon R9 290, R9 390, FirePro W9100, S9150, S9170)
|
||||
does not require or take advantage of PCIe Atomics. However, we still recommend that you use a CPU
|
||||
from the list provided above for compatibility purposes.
|
||||
|
||||
>**Warning**: Before proceeding, make sure to completely
|
||||
>[uninstall any pre-release ROCm packages](https://github.com/RadeonOpenCompute/ROCm#removing-pre-release-packages):
|
||||
#### Not supported or limited support under ROCm
|
||||
##### Limited support
|
||||
|
||||
```shell
|
||||
sudo apt-get update
|
||||
sudo apt-get install rocm
|
||||
```
|
||||
Then, make the ROCm kernel your default kernel. If using grub2 as your
|
||||
bootloader, you can edit the `GRUB_DEFAULT` variable in the following file:
|
||||
* ROCm 2.9.x should support PCIe 2.0 enabled CPUs such as the AMD Opteron, Phenom, Phenom II, Athlon, Athlon X2, Athlon II and older Intel Xeon and Intel Core Architecture and Pentium CPUs. However, we have done very limited testing on these configurations, since our test farm has been catering to CPUs listed above. This is where we need community support. _If you find problems on such setups, please report these issues_.
|
||||
* Thunderbolt 1, 2, and 3 enabled breakout boxes should now be able to work with ROCm. Thunderbolt 1 and 2 are PCIe 2.0 based, and thus are only supported with GPUs that do not require PCIe 3.1.0 atomics (e.g. Vega 10). However, we have done no testing on this configuration and would need community support due to limited access to this type of equipment.
|
||||
* AMD "Carrizo" and "Bristol Ridge" APUs are enabled to run OpenCL, but do not yet support HCC, HIP, or our libraries built on top of these compilers and runtimes.
|
||||
* As of ROCm 2.1, "Carrizo" and "Bristol Ridge" require the use of upstream kernel drivers.
|
||||
* In addition, various "Carrizo" and "Bristol Ridge" platforms may not work due to OEM and ODM choices when it comes to key configurations parameters such as inclusion of the required CRAT tables and IOMMU configuration parameters in the system BIOS.
|
||||
* Before purchasing such a system for ROCm, please verify that the BIOS provides an option for enabling IOMMUv2 and that the system BIOS properly exposes the correct CRAT table. Inquire with your vendor about the latter.
|
||||
* AMD "Raven Ridge" APUs are enabled to run OpenCL, but do not yet support HCC, HIP, or our libraries built on top of these compilers and runtimes.
|
||||
* As of ROCm 2.1, "Raven Ridge" requires the use of upstream kernel drivers.
|
||||
* In addition, various "Raven Ridge" platforms may not work due to OEM and ODM choices when it comes to key configurations parameters such as inclusion of the required CRAT tables and IOMMU configuration parameters in the system BIOS.
|
||||
* Before purchasing such a system for ROCm, please verify that the BIOS provides an option for enabling IOMMUv2 and that the system BIOS properly exposes the correct CRAT table. Inquire with your vendor about the latter.
|
||||
|
||||
```shell
|
||||
sudo vi /etc/default/grub
|
||||
sudo update-grub
|
||||
```
|
||||
##### Not supported
|
||||
|
||||
Once complete, reboot your system.
|
||||
* "Tonga", "Iceland", "Vega M", and "Vega 12" GPUs are not supported in ROCm 2.9.x
|
||||
* We do not support GFX8-class GPUs (Fiji, Polaris, etc.) on CPUs that do not have PCIe 3.0 with PCIe atomics.
|
||||
* As such, we do not support AMD Carrizo and Kaveri APUs as hosts for such GPUs.
|
||||
* Thunderbolt 1 and 2 enabled GPUs are not supported by GFX8 GPUs on ROCm. Thunderbolt 1 & 2 are based on PCIe 2.0.
|
||||
|
||||
We recommend you [verify your installation](https://github.com/RadeonOpenCompute/ROCm#verify-installation) to make sure everything completed successfully.
|
||||
#### ROCm support in upstream Linux kernels
|
||||
|
||||
##### Un-install
|
||||
To un-install the entire rocm-dev development package execute:
|
||||
As of ROCm 1.9.0, the ROCm user-level software is compatible with the AMD drivers in certain upstream Linux kernels.
|
||||
As such, users have the option of either using the ROCK kernel driver that are part of AMD's ROCm repositories or using the upstream driver and only installing ROCm user-level utilities from AMD's ROCm repositories.
|
||||
|
||||
```shell
|
||||
sudo apt-get autoremove rocm
|
||||
```
|
||||
These releases of the upstream Linux kernel support the following GPUs in ROCm:
|
||||
* 4.17: Fiji, Polaris 10, Polaris 11
|
||||
* 4.18: Fiji, Polaris 10, Polaris 11, Vega10
|
||||
* 4.20: Fiji, Polaris 10, Polaris 11, Vega10, Vega 7nm
|
||||
|
||||
##### Installing development packages for cross compilation
|
||||
It is often useful to develop and test on different systems. In this scenario,
|
||||
you may prefer to avoid installing the ROCm Kernel to your development system.
|
||||
The upstream driver may be useful for running ROCm software on systems that are not compatible with the kernel driver available in AMD's repositories.
|
||||
For users that have the option of using either AMD's or the upstreamed driver, there are various tradeoffs to take into consideration:
|
||||
|
||||
In this case, install the development subset of packages:
|
||||
| | Using AMD's `rock-dkms` package | Using the upstream kernel driver |
|
||||
| ---- | ------------------------------------------------------------| ----- |
|
||||
| Pros | More GPU features, and they are enabled earlier | Includes the latest Linux kernel features |
|
||||
| | Tested by AMD on supported distributions | May work on other distributions and with custom kernels |
|
||||
| | Supported GPUs enabled regardless of kernel version | |
|
||||
| | Includes the latest GPU firmware | |
|
||||
| Cons | May not work on all Linux distributions or versions | Features and hardware support varies depending on kernel version |
|
||||
| | Not currently supported on kernels newer than 5.4 | Limits GPU's usage of system memory to 3/8 of system memory (before 5.6). For 5.6 and beyond, both DKMS and upstream kernels allow use of 15/16 of system memory. |
|
||||
| | | IPC and RDMA capabilities are not yet enabled |
|
||||
| | | Not tested by AMD to the same level as `rock-dkms` package |
|
||||
| | | Does not include most up-to-date firmware |
|
||||
|
||||
```shell
|
||||
sudo apt-get update
|
||||
sudo apt-get install rocm-dev
|
||||
```
|
||||
|
||||
>**Note:** To execute ROCm enabled apps you will require a system with the full
|
||||
>ROCm driver stack installed
|
||||
|
||||
##### Removing pre-release packages
|
||||
If you installed any of the ROCm pre-release packages from github, they will
|
||||
need to be manually un-installed:
|
||||
## Machine Learning and High Performance Computing Software Stack for AMD GPU
|
||||
|
||||
```shell
|
||||
sudo apt-get purge libhsakmt
|
||||
sudo apt-get purge radeon-firmware
|
||||
sudo apt-get purge $(dpkg -l | grep 'kfd\|rocm' | grep linux | grep -v libc | awk '{print $2}')
|
||||
```
|
||||
For an updated version of the software stack for AMD GPU, see
|
||||
|
||||
If possible, we would recommend starting with a fresh OS install.
|
||||
|
||||
#### RPM repository - dnf (yum)
|
||||
|
||||
A dnf (yum) repostiory is also available for installation of rpm packages. To configure a
|
||||
system to use the ROCm rpm directory create the file /etc/yum.repos.d/rocm.repo with
|
||||
the following contents:
|
||||
|
||||
```shell
|
||||
[remote]
|
||||
|
||||
name=ROCm Repo
|
||||
|
||||
baseurl=http://packages.amd.com/rocm/yum/rpm/
|
||||
|
||||
enabled=1
|
||||
|
||||
gpgcheck=0
|
||||
```
|
||||
Execute the following commands:
|
||||
|
||||
```shell
|
||||
sudo dnf clean all
|
||||
sudo dnf install rocm
|
||||
```
|
||||
|
||||
As with the debian packages, it is possible to install rocm-dev or rocm-kernel individually.
|
||||
To uninstall the packages execute:
|
||||
|
||||
```shell
|
||||
sudo dnf remove rocm
|
||||
```
|
||||
|
||||
#### Verify Installation
|
||||
|
||||
To verify that the ROCm stack completed successfully you can execute to HSA
|
||||
vectory\_copy sample application:
|
||||
|
||||
```shell
|
||||
cd /opt/rocm/hsa/sample
|
||||
make
|
||||
./vector_copy
|
||||
```
|
||||
|
||||
#### Closed Source Components
|
||||
The ROCm platform relies on a few closed source components to provide legacy
|
||||
functionality like HSAIL finalization and debugging/profiling support. These
|
||||
components are only available through the ROCm repositories, and will either be
|
||||
deprecated or become open source components in the future. These components are
|
||||
made available in the following packages:
|
||||
|
||||
* hsa-ext-rocr-dev
|
||||
|
||||
### Getting ROCm Source Code
|
||||
Modifications can be made to the ROCm 1.1 components by modifying the open
|
||||
source code base and rebuilding the components. Source code can be cloned from
|
||||
each of the GitHub repositories using git, or users can use the repo command
|
||||
and the ROCm 1.1 manifest file to download the entire ROCm 1.1 source code.
|
||||
|
||||
#### Installing repo
|
||||
Google's repo tool allows you to manage multiple git repositories
|
||||
simultaneously. You can install it by executing the following commands:
|
||||
|
||||
```shell
|
||||
curl https://storage.googleapis.com/git-repo-downloads/repo > ~/bin/repo
|
||||
chmod a+x ~/bin/repo
|
||||
```
|
||||
Note: make sure ~/bin exists and it is part of your PATH
|
||||
|
||||
#### Cloning the code
|
||||
```shell
|
||||
mkdir ROCm && cd ROCm
|
||||
repo init -u https://github.com/RadeonOpenCompute/ROCm.git -b roc-1.1.0
|
||||
repo sync
|
||||
```
|
||||
|
||||
These series of commands will pull all of the open source code associated with
|
||||
the ROCm 1.1 release.
|
||||
https://rocmdocs.amd.com/en/latest/Installation_Guide/Installation-Guide.html#machine-learning-and-high-performance-computing-software-stack-for-amd-gpu-v3-5-0
|
||||
|
||||
BIN
ROCm_SMI_Manual.pdf
Normal file
BIN
ROCm_SMI_Manual.pdf
Normal file
Binary file not shown.
BIN
amd-dbgapi.pdf
Normal file
BIN
amd-dbgapi.pdf
Normal file
Binary file not shown.
95
default.xml
95
default.xml
@@ -1,27 +1,80 @@
|
||||
<?xml version="1.0" encoding="UTF-8"?>
|
||||
<manifest>
|
||||
|
||||
<remote name="roc-github"
|
||||
fetch="ssh://git@github.com/RadeonOpenCompute/" />
|
||||
<remote name="pctools-github"
|
||||
fetch="ssh://git@github.com/GPUOpen-ProfessionalCompute-Tools/" />
|
||||
|
||||
<default revision="master"
|
||||
fetch="http://github.com/RadeonOpenCompute/" />
|
||||
<remote name="rocm-devtools"
|
||||
fetch="https://github.com/ROCm-Developer-Tools/" />
|
||||
<remote name="rocm-swplat"
|
||||
fetch="https://github.com/ROCmSoftwarePlatform/" />
|
||||
<remote name="gpuopen-libs"
|
||||
fetch="https://github.com/GPUOpen-ProfessionalCompute-Libraries/" />
|
||||
<remote name="gpuopen-tools"
|
||||
fetch="https://github.com/GPUOpen-Tools/" />
|
||||
<remote name="KhronosGroup"
|
||||
fetch="https://github.com/KhronosGroup/" />
|
||||
<default revision="refs/tags/rocm-3.5.0"
|
||||
remote="roc-github"
|
||||
sync-c="true"
|
||||
sync-j="4" />
|
||||
|
||||
<project path="llvm" name="llvm" />
|
||||
<project path="llvm-amdgpu-assembler-extra" name="LLVM-AMDGPU-Assembler-Extra" />
|
||||
<project path="clang" name="clang" />
|
||||
|
||||
<project path="hcc" name="hcc" />
|
||||
<project path="ROCT-Thunk-Interface" name="ROCT-Thunk-Interface" />
|
||||
<project path="ROCK-Kernel-Driver" name="ROCK-Kernel-Driver" />
|
||||
<project path="ROC-smi" name="ROC-smi" />
|
||||
<project path="ROCnRDMA" name="ROCnRDMA" />
|
||||
<project path="rdma-perftest" name="rdma-perftest" />
|
||||
<project path="ROCR-Runtime" name="ROCR-Runtime" />
|
||||
<project path="HIP" remote="pctools-github" name="HIP" />
|
||||
<project path="HIP-Examples" remote="pctools-github" name="HIP-Examples" />
|
||||
|
||||
<!--list of projects for ROCM-->
|
||||
<project name="ROCK-Kernel-Driver" revision="refs/tags/rocm-3.5.1" />
|
||||
<project name="ROCT-Thunk-Interface" />
|
||||
<project name="ROCR-Runtime" />
|
||||
<project name="ROC-smi" />
|
||||
<project name="rocm_smi_lib" remote="roc-github" />
|
||||
<project name="rocm-cmake" />
|
||||
<project name="rocminfo" />
|
||||
<project name="rocprofiler" remote="rocm-devtools" />
|
||||
<project name="roctracer" remote="rocm-devtools" />
|
||||
<project name="ROCm-OpenCL-Runtime" revision="refs/tags/roc-3.5.0" />
|
||||
<project path="ROCm-OpenCL-Runtime/api/opencl/khronos/icd" name="OpenCL-ICD-Loader" remote="KhronosGroup" revision="6c03f8b58fafd9dd693eaac826749a5cfad515f8" />
|
||||
<project name="clang-ocl" />
|
||||
<!--HIP Projects-->
|
||||
<project name="HCC-Example-Application" remote="rocm-devtools" revision="ffd6533305e79eed667badd3c4cdb7879a1281b8" />
|
||||
<project name="HIP" remote="rocm-devtools" revision="refs/tags/rocm-3.5.1" />
|
||||
<project name="HIP-Examples" remote="rocm-devtools" />
|
||||
<project name="ROCclr" remote="rocm-devtools" revision="refs/tags/roc-3.5.0" />
|
||||
<project name="HIPIFY" remote="rocm-devtools" />
|
||||
<!-- The following projects are all associated with the AMDGPU LLVM compiler -->
|
||||
<project name="llvm-project" path="llvm_amd-stg-open" />
|
||||
<project name="ROCm-Device-Libs" />
|
||||
<project name="atmi" />
|
||||
<project name="ROCm-CompilerSupport" />
|
||||
<project name="rocr_debug_agent" remote="rocm-devtools" revision="refs/tags/roc-3.5.0" />
|
||||
<project name="rocm_bandwidth_test" />
|
||||
<project name="RCP" remote="gpuopen-tools" revision="3a49405a1500067c49d181844ec90aea606055bb" />
|
||||
<!-- gdb projects -->
|
||||
<project name="ROCgdb" remote="rocm-devtools" />
|
||||
<project name="ROCdbgapi" remote="rocm-devtools" />
|
||||
<!-- ROCm Libraries -->
|
||||
<project name="rocBLAS" remote="rocm-swplat" />
|
||||
<project name="hipBLAS" remote="rocm-swplat" />
|
||||
<project name="rocFFT" remote="rocm-swplat" />
|
||||
<project name="rocRAND" remote="rocm-swplat" />
|
||||
<project name="rocSPARSE" remote="rocm-swplat" />
|
||||
<project name="rocSOLVER" remote="rocm-swplat" />
|
||||
<project name="hipSPARSE" remote="rocm-swplat" />
|
||||
<project name="rocALUTION" remote="rocm-swplat" />
|
||||
<project name="MIOpenGEMM" remote="rocm-swplat" revision="refs/tags/1.1.6" />
|
||||
<project name="MIOpen" remote="rocm-swplat" />
|
||||
<project name="rccl" remote="rocm-swplat" />
|
||||
<project name="MIVisionX" remote="gpuopen-libs" revision="refs/tags/1.7" />
|
||||
<project name="rocThrust" remote="rocm-swplat" />
|
||||
<project name="hipCUB" remote="rocm-swplat" />
|
||||
<project name="rocPRIM" remote="rocm-swplat" revision="refs/tags/rocm-3.5.1" />
|
||||
<project name="AMDMIGraphX" remote="rocm-swplat" />
|
||||
<project name="ROCmValidationSuite" remote="rocm-devtools" />
|
||||
<!-- Projects for AOMP -->
|
||||
<project name="ROCT-Thunk-Interface" path="aomp/roct-thunk-interface" remote="roc-github" />
|
||||
<project name="ROCR-Runtime" path="aomp/rocr-runtime" remote="roc-github" />
|
||||
<project name="ROCm-Device-Libs" path="aomp/rocm-device-libs" remote="roc-github" />
|
||||
<project name="ROCm-CompilerSupport" path="aomp/rocm-compilersupport" remote="roc-github" />
|
||||
<project name="rocminfo" path="aomp/rocminfo" remote="roc-github" />
|
||||
<project name="HIP" path="aomp/hip-on-vdi" remote="rocm-devtools" revision="ffcbd7e63395f8a4d3ccb7e4d5133f8d2dde793e" />
|
||||
<project name="aomp" path="aomp/aomp" remote="rocm-devtools" />
|
||||
<project name="aomp-extras" path="aomp/aomp-extras" remote="rocm-devtools" />
|
||||
<project name="flang" path="aomp/flang" remote="rocm-devtools" />
|
||||
<project name="amd-llvm-project" path="aomp/amd-llvm-project" remote="rocm-devtools" />
|
||||
<project name="ROCclr" path="aomp/vdi" remote="rocm-devtools" revision="72ce2c9783d514fc7da94db40f9f420320df098d" />
|
||||
<project name="ROCm-OpenCL-Runtime" path="aomp/opencl-on-vdi" remote="roc-github" revision="12fb33212c99cb4b596b0f34691e7d044218e3e9" />
|
||||
</manifest>
|
||||
|
||||
503
version_history.md
Normal file
503
version_history.md
Normal file
@@ -0,0 +1,503 @@
|
||||
## ROCm Version History
|
||||
This file contains archived version history information for the [ROCm project](https://github.com/RadeonOpenCompute/ROCm)
|
||||
|
||||
### Current ROCm Version: 3.3
|
||||
- [New features and enhancements in ROCm v3.1](#new-features-and-enhancements-in-rocm-v31)
|
||||
- [New features and enhancements in ROCm v3.0](#new-features-and-enhancements-in-rocm-v30)
|
||||
- [New features and enhancements in ROCm v2.10](#new-features-and-enhancements-in-rocm-v210)
|
||||
- [New features and enhancements in ROCm 2.9](#new-features-and-enhancements-in-rocm-29)
|
||||
- [New features and enhancements in ROCm 2.8](#new-features-and-enhancements-in-rocm-28)
|
||||
- [New features and enhancements in ROCm 2.7.2](#new-features-and-enhancements-in-rocm-272)
|
||||
- [New features and enhancements in ROCm 2.7](#new-features-and-enhancements-in-rocm-27)
|
||||
- [New features and enhancements in ROCm 2.6](#new-features-and-enhancements-in-rocm-26)
|
||||
- [New features and enhancements in ROCm 2.5](#new-features-and-enhancements-in-rocm-25)
|
||||
- [New features and enhancements in ROCm 2.4](#new-features-and-enhancements-in-rocm-24)
|
||||
- [New features and enhancements in ROCm 2.3](#new-features-and-enhancements-in-rocm-23)
|
||||
- [New features and enhancements in ROCm 2.2](#new-features-and-enhancements-in-rocm-22)
|
||||
- [New features and enhancements in ROCm 2.1](#new-features-and-enhancements-in-rocm-21)
|
||||
- [New features and enhancements in ROCm 2.0](#new-features-and-enhancements-in-rocm-20)
|
||||
- [New features and enhancements in ROCm 1.9.2](#new-features-and-enhancements-in-rocm-192)
|
||||
- [New features and enhancements in ROCm 1.9.2](#new-features-and-enhancements-in-rocm-192-1)
|
||||
- [New features and enhancements in ROCm 1.9.1](#new-features-and-enhancements-in-rocm-191)
|
||||
- [New features and enhancements in ROCm 1.9.0](#new-features-and-enhancements-in-rocm-190)
|
||||
- [New features as of ROCm 1.8.3](#new-features-as-of-rocm-183)
|
||||
- [New features as of ROCm 1.8](#new-features-as-of-rocm-18)
|
||||
- [New Features as of ROCm 1.7](#new-features-as-of-rocm-17)
|
||||
- [New Features as of ROCm 1.5](#new-features-as-of-rocm-15)
|
||||
|
||||
|
||||
## New features and enhancements in ROCm v3.2
|
||||
The AMD ROCm v3.2 release was not productized.
|
||||
|
||||
## New features and enhancements in ROCm v3.1
|
||||
### Change in ROCm Installation Directory Structure
|
||||
|
||||
A fresh installation of the ROCm toolkit installs the packages in the /opt/rocm-<version> folder. Previously, ROCm toolkit packages were installed in the /opt/rocm folder.
|
||||
|
||||
### Reliability, Accessibility, and Serviceability Support for Vega 7nm
|
||||
|
||||
The Reliability, Accessibility, and Serviceability (RAS) support for Vega7nm is now available.
|
||||
|
||||
### SLURM Support for AMD GPU
|
||||
|
||||
SLURM (Simple Linux Utility for Resource Management) is an open source, fault-tolerant, and highly scalable cluster management and job scheduling system for large and small Linux clusters.
|
||||
|
||||
|
||||
## New features and enhancements in ROCm v3.0
|
||||
### Support for CentOS RHEL v7.7 <a id="centos-anchor"></a>
|
||||
Support is extended for CentOS/RHEL v7.7 in the ROCm v3.0 release. For more information about the CentOS/RHEL v7.7 release, see:
|
||||
|
||||
[CentOS/RHEL](https://centos.org/forums/viewtopic.php?t=71657)
|
||||
|
||||
|
||||
### Initial distribution of AOMP 0.7-5 in ROCm v3.0 <a id="aomp-anchor"></a>
|
||||
The code base for this release of AOMP is the Clang/LLVM 9.0 sources as of October 8th, 2019. The LLVM-project branch used to build this release is AOMP-191008. It is now locked. With this release, an artifact tarball of the entire source tree is created. This tree includes a Makefile in the root directory used to build AOMP from the release tarball. You can use Spack to build AOMP from this source tarball or build manually without Spack.
|
||||
|
||||
For more information about AOMP 0.7-5, see: [AOMP](https://github.com/ROCm-Developer-Tools/aomp/tree/roc-3.0.0)
|
||||
|
||||
|
||||
### Fast Fourier Transform Updates
|
||||
The Fast Fourier Transform (FFT) is an efficient algorithm for computing the Discrete Fourier Transform. Fast Fourier transforms are used in signal processing, image processing, and many other areas. The following real FFT performance change is made in the ROCm v3.0 release:
|
||||
|
||||
• Implement efficient real/complex 2D transforms for even lengths.
|
||||
|
||||
Other improvements:
|
||||
|
||||
• More 2D test coverage sizes.
|
||||
|
||||
• Fix buffer allocation error for large 1D transforms.
|
||||
|
||||
• C++ compatibility improvements.
|
||||
|
||||
### MemCopy Enhancement for rocProf
|
||||
In the v3.0 release, the rocProf tool is enhanced with an additional capability to dump asynchronous GPU memcopy information into a .csv file. You can use the '-hsa-trace' option to create the results_mcopy.csv file.
|
||||
Future enhancements will include column labels.
|
||||
|
||||
|
||||
### New features and enhancements in ROCm v2.10
|
||||
#### rocBLAS Support for Complex GEMM
|
||||
The rocBLAS library is a gpu-accelerated implementation of the standard Basic Linear Algebra Subroutines (BLAS). rocBLAS is designed to enable you to develop algorithms, including high performance computing, image analysis, and machine learning.
|
||||
|
||||
In the AMD ROCm release v2.10, support is extended to the General Matrix Multiply (GEMM) routine for multiple small matrices processed simultaneously for rocBLAS in AMD Radeon Instinct MI50. Both single and double precision, CGEMM and ZGEMM, are now supported in rocBLAS.
|
||||
|
||||
#### Support for SLES 15 SP1
|
||||
In the AMD ROCm v2.10 release, support is added for SUSE Linux® Enterprise Server (SLES) 15 SP1. SLES is a modular operating system for both multimodal and traditional IT.
|
||||
|
||||
#### Code Marker Support for rocProfiler and rocTracer Libraries
|
||||
Code markers provide the external correlation ID for the calling thread. This function indicates that the calling thread is entering and leaving an external API region.
|
||||
|
||||
### New features and enhancements in ROCm 2.9
|
||||
|
||||
#### Initial release for Radeon Augmentation Library(RALI)
|
||||
The AMD Radeon Augmentation Library (RALI) is designed to efficiently decode and process images from a variety of storage formats and modify them through a processing graph programmable by the user. RALI currently provides C API.
|
||||
|
||||
#### Quantization in MIGraphX v0.4
|
||||
MIGraphX 0.4 introduces support for fp16 and int8 quantization. For additional details, as well as other new MIGraphX features, see [MIGraphX documentation](https://github.com/ROCmSoftwarePlatform/AMDMIGraphX/wiki/Getting-started:-using-the-new-features-of-MIGraphX-0.4).
|
||||
|
||||
#### rocSparse csrgemm
|
||||
csrgemm enables the user to perform matrix-matrix multiplication with two sparse matrices in CSR format.
|
||||
|
||||
#### Singularity Support
|
||||
ROCm 2.9 adds support for Singularity container version 2.5.2.
|
||||
|
||||
#### Initial release of rocTX
|
||||
ROCm 2.9 introduces rocTX, which provides a C API for code markup for performance profiling. This initial release of rocTX supports annotation of code ranges and ASCII markers. For an example, see this [code](https://github.com/ROCm-Developer-Tools/roctracer/blob/amd-master/test/MatrixTranspose_test/MatrixTranspose.cpp).
|
||||
|
||||
#### Added support for Ubuntu 18.04.3
|
||||
Ubuntu 18.04.3 is now supported in ROCm 2.9.
|
||||
|
||||
|
||||
|
||||
### New features and enhancements in ROCm 2.8
|
||||
|
||||
#### Support for NCCL2.4.8 API
|
||||
Implements ncclCommAbort() and ncclCommGetAsyncError() to match the NCCL 2.4.x API
|
||||
|
||||
### New features and enhancements in ROCm 2.7.2
|
||||
|
||||
This release is a hotfix for ROCm release 2.7.
|
||||
|
||||
#### Issues fixed in ROCm 2.7.2
|
||||
|
||||
##### A defect in upgrades from older ROCm releases has been fixed.
|
||||
|
||||
##### rocprofiler --hiptrace and --hsatrace fails to load roctracer library
|
||||
In ROCm 2.7.2, rocprofiler --hiptrace and --hsatrace fails to load roctracer library defect has been fixed.
|
||||
To generate traces, please provide directory path also using the parameter: -d <$directoryPath> for example:
|
||||
```shell
|
||||
/opt/rocm/bin/rocprof --hsa-trace -d $PWD/traces /opt/rocm/hip/samples/0_Intro/bit_extract/bit_extract
|
||||
```
|
||||
All traces and results will be saved under $PWD/traces path
|
||||
|
||||
#### Upgrading from ROCm 2.7 to 2.7.2
|
||||
|
||||
To upgrade, please remove 2.7 completely as specified [for ubuntu](#how-to-uninstall-from-ubuntu-1604-or-Ubuntu-1804) or [for centos/rhel](#how-to-uninstall-rocm-from-centosrhel-76), and install 2.7.2 as per instructions [install instructions](#installing-from-amd-rocm-repositories)
|
||||
|
||||
#### Other notes
|
||||
|
||||
To use rocprofiler features, the following steps need to be completed before using rocprofiler:
|
||||
|
||||
##### Step-1: Install roctracer
|
||||
|
||||
###### Ubuntu 16.04 or Ubuntu 18.04:
|
||||
|
||||
```shell
|
||||
sudo apt install roctracer-dev
|
||||
```
|
||||
|
||||
###### CentOS/RHEL 7.6:
|
||||
|
||||
```shell
|
||||
sudo yum install roctracer-dev
|
||||
```
|
||||
##### Step-2: Add /opt/rocm/roctracer/lib to LD_LIBRARY_PATH
|
||||
|
||||
### New features and enhancements in ROCm 2.7
|
||||
|
||||
#### [rocFFT] Real FFT Functional
|
||||
Improved real/complex 1D even-length transforms of unit stride. Performance improvements of up to 4.5x are observed. Large problem sizes should see approximately 2x.
|
||||
|
||||
#### rocRand Enhancements and Optimizations
|
||||
- Added support for new datatypes: uchar, ushort, half.
|
||||
- Improved performance on "Vega 7nm" chips, such as on the Radeon Instinct MI50
|
||||
- mtgp32 uniform double performance changes due generation algorithm standardization. Better quality random numbers now generated with 30% decrease in performance
|
||||
- Up to 5% performance improvements for other algorithms
|
||||
|
||||
#### RAS
|
||||
Added support for RAS on Radeon Instinct MI50, including:
|
||||
- Memory error detection
|
||||
- Memory error detection counter
|
||||
|
||||
#### ROCm-SMI enhancements
|
||||
Added ROCm-SMI CLI and LIB support for FW version, compute running processes, utilization rates, utilization counter, link error counter, and unique ID.
|
||||
|
||||
### New features and enhancements in ROCm 2.6
|
||||
|
||||
#### ROCmInfo enhancements
|
||||
ROCmInfo was extended to do the following:
|
||||
For ROCr API call errors including initialization determine if the error could be explained by:
|
||||
- ROCk (driver) is not loaded / available
|
||||
- User does not have membership in appropriate group - "video"
|
||||
- If not above print the error string that is mapped to the returned error code
|
||||
- If no error string is available, print the error code in hex
|
||||
|
||||
#### Thrust - Functional Support on Vega20
|
||||
ROCm2.6 contains the first official release of rocThrust and hipCUB. rocThrust is a port of thrust, a parallel algorithm library. hipCUB is a port of CUB, a reusable software component library. Thrust/CUB has been ported to the HIP/ROCm platform to use the rocPRIM library. The HIP ported library works on HIP/ROCm platforms.
|
||||
|
||||
Note: rocThrust and hipCUB library replaces https://github.com/ROCmSoftwarePlatform/thrust (hip-thrust), i.e. hip-thrust has been separated into two libraries, rocThrust and hipCUB. Existing hip-thrust users are encouraged to port their code to rocThrust and/or hipCUB. Hip-thrust will be removed from official distribution later this year.
|
||||
|
||||
#### MIGraphX v0.3
|
||||
MIGraphX optimizer adds support to read models frozen from Tensorflow framework. Further details and an example usage at https://github.com/ROCmSoftwarePlatform/AMDMIGraphX/wiki/Getting-started:-using-the-new-features-of-MIGraphX-0.3
|
||||
|
||||
#### MIOpen 2.0
|
||||
- This release contains several new features including an immediate mode for selecting convolutions, bfloat16 support, new layers, modes, and algorithms.
|
||||
- MIOpenDriver, a tool for benchmarking and developing kernels is now shipped with MIOpen.
|
||||
BFloat16 now supported in HIP requires an updated rocBLAS as a GEMM backend.
|
||||
- Immediate mode API now provides the ability to quickly obtain a convolution kernel.
|
||||
- MIOpen now contains HIP source kernels and implements the ImplicitGEMM kernels. This is a new feature and is currently disabled by default. Use the environmental variable "MIOPEN_DEBUG_CONV_IMPLICIT_GEMM=1" to activation this feature. ImplicitGEMM requires an up to date HIP version of at least 1.5.9211.
|
||||
- A new "loss" catagory of layers has been added, of which, CTC loss is the first. See the API reference for more details.
|
||||
2.0 is the last release of active support for gfx803 architectures. In future releases, MIOpen will not actively debug and develop new features specifically for gfx803.
|
||||
- System Find-Db in memory cache is disabled by default. Please see build instructions to enable this feature.
|
||||
Additional documentation can be found here: https://rocmsoftwareplatform.github.io/MIOpen/doc/html/
|
||||
|
||||
#### Bloat16 software support in rocBLAS/Tensile
|
||||
Added mixed precision bfloat16/IEEE f32 to gemm_ex. The input and output matrices are bfloat16. All arithmetic is in IEEE f32.
|
||||
|
||||
#### AMD Infinity Fabric™ Link enablement
|
||||
The ability to connect four Radeon Instinct MI60 or Radeon Instinct MI50 boards in two hives or two Radeon Instinct MI60 or Radeon Instinct MI50 boards in four hives via AMD Infinity Fabric™ Link GPU interconnect technology has been added.
|
||||
|
||||
#### ROCm-smi features and bug fixes
|
||||
- mGPU & Vendor check
|
||||
- Fix clock printout if DPM is disabled
|
||||
- Fix finding marketing info on CentOS
|
||||
- Clarify some error messages
|
||||
|
||||
#### ROCm-smi-lib enhancements
|
||||
- Documentation updates
|
||||
- Improvements to *name_get functions
|
||||
|
||||
#### RCCL2 Enablement
|
||||
RCCL2 supports collectives intranode communication using PCIe, Infinity Fabric™, and pinned host memory, as well as internode communication using Ethernet (TCP/IP sockets) and Infiniband/RoCE (Infiniband Verbs). Note: For Infiniband/RoCE, RDMA is not currently supported.
|
||||
|
||||
#### rocFFT enhancements
|
||||
- Added: Debian package with FFT test, benchmark, and sample programs
|
||||
- Improved: hipFFT interfaces
|
||||
- Improved: rocFFT CPU reference code, plan generation code and logging code
|
||||
|
||||
### New features and enhancements in ROCm 2.5
|
||||
|
||||
#### UCX 1.6 support
|
||||
Support for UCX version 1.6 has been added.
|
||||
|
||||
#### BFloat16 GEMM in rocBLAS/Tensile
|
||||
Software support for BFloat16 on Radeon Instinct MI50, MI60 has been added. This includes:
|
||||
- Mixed precision GEMM with BFloat16 input and output matrices, and all arithmetic in IEEE32 bit
|
||||
- Input matrix values are converted from BFloat16 to IEEE32 bit, all arithmetic and accumulation is IEEE32 bit. Output values are rounded from IEEE32 bit to BFloat16
|
||||
- Accuracy should be correct to 0.5 ULP
|
||||
|
||||
#### ROCm-SMI enhancements
|
||||
CLI support for querying the memory size, driver version, and firmware version has been added to ROCm-smi.
|
||||
|
||||
#### [PyTorch] multi-GPU functional support (CPU aggregation/Data Parallel)
|
||||
Multi-GPU support is enabled in PyTorch using Dataparallel path for versions of PyTorch built using the 06c8aa7a3bbd91cda2fd6255ec82aad21fa1c0d5 commit or later.
|
||||
|
||||
#### rocSparse optimization on Radeon Instinct MI50 and MI60
|
||||
This release includes performance optimizations for csrsv routines in the rocSparse library.
|
||||
|
||||
#### [Thrust] Preview
|
||||
Preview release for early adopters. rocThrust is a port of thrust, a parallel algorithm library. Thrust has been ported to the HIP/ROCm platform to use the rocPRIM library. The HIP ported library works on HIP/ROCm platforms.
|
||||
|
||||
Note: This library will replace https://github.com/ROCmSoftwarePlatform/thrust in a future release. The package for rocThrust (this library) currently conflicts with version 2.5 package of thrust. They should not be installed together.
|
||||
|
||||
#### Support overlapping kernel execution in same HIP stream
|
||||
HIP API has been enhanced to allow independent kernels to run in parallel on the same stream.
|
||||
|
||||
#### AMD Infinity Fabric™ Link enablement
|
||||
The ability to connect four Radeon Instinct MI60 or Radeon Instinct MI50 boards in one hive via AMD Infinity Fabric™ Link GPU interconnect technology has been added.
|
||||
### New features and enhancements in ROCm 2.4
|
||||
|
||||
#### TensorFlow 2.0 support
|
||||
ROCm 2.4 includes the enhanced compilation toolchain and a set of bug fixes to support TensorFlow 2.0 features natively
|
||||
|
||||
#### AMD Infinity Fabric™ Link enablement
|
||||
ROCm 2.4 adds support to connect two Radeon Instinct MI60 or Radeon Instinct MI50 boards via AMD Infinity Fabric™ Link GPU interconnect technology.
|
||||
|
||||
### New features and enhancements in ROCm 2.3
|
||||
|
||||
#### Mem usage per GPU
|
||||
Per GPU memory usage is added to rocm-smi.
|
||||
Display information regarding used/total bytes for VRAM, visible VRAM and GTT, via the --showmeminfo flag
|
||||
|
||||
#### MIVisionX, v1.1 - ONNX
|
||||
ONNX parser changes to adjust to new file formats
|
||||
|
||||
#### MIGraphX, v0.2
|
||||
MIGraphX 0.2 supports the following new features:
|
||||
* New Python API
|
||||
* Support for additional ONNX operators and fixes that now enable a large set of Imagenet models
|
||||
* Support for RNN Operators
|
||||
* Support for multi-stream Execution
|
||||
* [Experimental] Support for Tensorflow frozen protobuf files
|
||||
|
||||
See: [Getting-started:-using-the-new-features-of-MIGraphX-0.2](https://github.com/ROCmSoftwarePlatform/AMDMIGraphX/wiki/Getting-started:-using-the-new-features-of-MIGraphX-0.2) for more details
|
||||
|
||||
#### MIOpen, v1.8 - 3d convolutions and int8
|
||||
* This release contains full 3-D convolution support and int8 support for inference.
|
||||
* Additionally, there are major updates in the performance database for major models including those found in Torchvision.
|
||||
|
||||
See: [MIOpen releases](https://github.com/ROCmSoftwarePlatform/MIOpen/releases)
|
||||
|
||||
#### Caffe2 - mGPU support
|
||||
Multi-gpu support is enabled for Caffe2.
|
||||
|
||||
#### rocTracer library, ROCm tracing API for collecting runtimes API and asynchronous GPU activity traces
|
||||
HIP/HCC domains support is introduced in rocTracer library.
|
||||
|
||||
#### BLAS - Int8 GEMM performance, Int8 functional and performance
|
||||
Introduces support and performance optimizations for Int8 GEMM, implements TRSV support, and includes improvements and optimizations with Tensile.
|
||||
|
||||
#### Prioritized L1/L2/L3 BLAS (functional)
|
||||
Functional implementation of BLAS L1/L2/L3 functions
|
||||
|
||||
#### BLAS - tensile optimization
|
||||
Improvements and optimizations with tensile
|
||||
|
||||
#### MIOpen Int8 support
|
||||
Support for int8
|
||||
|
||||
### New features and enhancements in ROCm 2.2
|
||||
|
||||
#### rocSparse Optimization on Vega20
|
||||
Cache usage optimizations for csrsv (sparse triangular solve), coomv
|
||||
(SpMV in COO format) and ellmv (SpMV in ELL format) are available.
|
||||
|
||||
#### DGEMM and DTRSM Optimization
|
||||
Improved DGEMM performance for reduced matrix sizes (k=384, k=256)
|
||||
|
||||
#### Caffe2
|
||||
Added support for multi-GPU training
|
||||
|
||||
### New features and enhancements in ROCm 2.1
|
||||
|
||||
#### RocTracer v1.0 preview release – 'rocprof' HSA runtime tracing and statistics support -
|
||||
Supports HSA API tracing and HSA asynchronous GPU activity including kernels execution and memory copy
|
||||
|
||||
#### Improvements to ROCM-SMI tool -
|
||||
Added support to show real-time PCIe bandwidth usage via the -b/--showbw flag
|
||||
|
||||
#### DGEMM Optimizations -
|
||||
Improved DGEMM performance for large square and reduced matrix sizes (k=384, k=256)
|
||||
|
||||
### New features and enhancements in ROCm 2.0
|
||||
|
||||
#### Adds support for RHEL 7.6 / CentOS 7.6 and Ubuntu 18.04.1
|
||||
|
||||
#### Adds support for Vega 7nm, Polaris 12 GPUs
|
||||
|
||||
#### Introduces MIVisionX
|
||||
* A comprehensive computer vision and machine intelligence libraries, utilities and applications bundled into a single toolkit.
|
||||
|
||||
#### Improvements to ROCm Libraries
|
||||
* rocSPARSE & hipSPARSE
|
||||
* rocBLAS with improved DGEMM efficiency on Vega 7nm
|
||||
|
||||
#### MIOpen
|
||||
* This release contains general bug fixes and an updated performance database
|
||||
* Group convolutions backwards weights performance has been improved
|
||||
* RNNs now support fp16
|
||||
|
||||
#### Tensorflow multi-gpu and Tensorflow FP16 support for Vega 7nm
|
||||
* TensorFlow v1.12 is enabled with fp16 support
|
||||
|
||||
#### PyTorch/Caffe2 with Vega 7nm Support
|
||||
* fp16 support is enabled
|
||||
* Several bug fixes and performance enhancements
|
||||
* Known Issue: breaking changes are introduced in ROCm 2.0 which are not addressed upstream yet. Meanwhile, please continue to use ROCm fork at https://github.com/ROCmSoftwarePlatform/pytorch
|
||||
|
||||
#### Improvements to ROCProfiler tool
|
||||
* Support for Vega 7nm
|
||||
|
||||
#### Support for hipStreamCreateWithPriority
|
||||
* Creates a stream with the specified priority. It creates a stream on which enqueued kernels have a different priority for execution compared to kernels enqueued on normal priority streams. The priority could be higher or lower than normal priority streams.
|
||||
|
||||
#### OpenCL 2.0 support
|
||||
* ROCm 2.0 introduces full support for kernels written in the OpenCL 2.0 C language on certain devices and systems. Applications can detect this support by calling the “clGetDeviceInfo” query function with “parame_name” argument set to “CL_DEVICE_OPENCL_C_VERSION”. In order to make use of OpenCL 2.0 C language features, the application must include the option “-cl-std=CL2.0” in options passed to the runtime API calls responsible for compiling or building device programs. The complete specification for the OpenCL 2.0 C language can be obtained using the following link: https://www.khronos.org/registry/OpenCL/specs/opencl-2.0-openclc.pdf
|
||||
|
||||
#### Improved Virtual Addressing (48 bit VA) management for Vega 10 and later GPUs
|
||||
* Fixes Clang AddressSanitizer and potentially other 3rd-party memory debugging tools with ROCm
|
||||
* Small performance improvement on workloads that do a lot of memory management
|
||||
* Removes virtual address space limitations on systems with more VRAM than system memory
|
||||
|
||||
#### Kubernetes support
|
||||
|
||||
### New features and enhancements in ROCm 1.9.2
|
||||
#### RDMA(MPI) support on Vega 7nm
|
||||
* Support ROCnRDMA based on Mellanox InfiniBand
|
||||
|
||||
#### Improvements to HCC
|
||||
* Improved link time optimization
|
||||
|
||||
#### Improvements to ROCProfiler tool
|
||||
* General bug fixes and implemented versioning APIs
|
||||
|
||||
### New features and enhancements in ROCm 1.9.2
|
||||
#### RDMA(MPI) support on Vega 7nm
|
||||
* Support ROCnRDMA based on Mellanox InfiniBand
|
||||
|
||||
#### Improvements to HCC
|
||||
* Improved link time optimization
|
||||
|
||||
#### Improvements to ROCProfiler tool
|
||||
* General bug fixes and implemented versioning APIs
|
||||
|
||||
#### Critical bug fixes
|
||||
|
||||
### New features and enhancements in ROCm 1.9.1
|
||||
#### Added DPM support to Vega 7nm
|
||||
* Dynamic Power Management feature is enabled on Vega 7nm.
|
||||
|
||||
#### Fix for 'ROCm profiling' that used to fail with a “Version mismatch between HSA runtime and libhsa-runtime-tools64.so.1” error
|
||||
|
||||
### New features and enhancements in ROCm 1.9.0
|
||||
|
||||
#### Preview for Vega 7nm
|
||||
* Enables developer preview support for Vega 7nm
|
||||
|
||||
#### System Management Interface
|
||||
* Adds support for the ROCm SMI (System Management Interface) library, which provides monitoring and management capabilities for AMD GPUs.
|
||||
|
||||
#### Improvements to HIP/HCC
|
||||
* Support for gfx906
|
||||
* Added deprecation warning for C++AMP. This will be the last version of HCC supporting C++AMP.
|
||||
* Improved optimization for global address space pointers passing into a GPU kernel
|
||||
* Fixed several race conditions in the HCC runtime
|
||||
* Performance tuning to the unpinned copy engine
|
||||
* Several codegen enhancement fixes in the compiler backend
|
||||
|
||||
#### Preview for rocprof Profiling Tool
|
||||
Developer preview (alpha) of profiling tool rocProfiler. It includes a command-line front-end, `rpl_run.sh`, which enables:
|
||||
* Cmd-line tool for dumping public per kernel perf-counters/metrics and kernel timestamps
|
||||
* Input file with counters list and kernels selecting parameters
|
||||
* Multiple counters groups and app runs supported
|
||||
* Output results in CSV format
|
||||
|
||||
The tool can be installed from the `rocprofiler-dev` package. It will be installed into: `/opt/rocm/bin/rpl_run.sh`
|
||||
|
||||
#### Preview for rocr Debug Agent rocr_debug_agent
|
||||
The ROCr Debug Agent is a library that can be loaded by ROCm Platform Runtime to provide the following functionality:
|
||||
* Print the state for wavefronts that report memory violation or upon executing a "s_trap 2" instruction.
|
||||
* Allows SIGINT (`ctrl c`) or SIGTERM (`kill -15`) to print wavefront state of aborted GPU dispatches.
|
||||
* It is enabled on Vega10 GPUs on ROCm1.9.
|
||||
|
||||
The ROCm1.9 release will install the ROCr Debug Agent library at `/opt/rocm/lib/librocr_debug_agent64.so`
|
||||
|
||||
|
||||
#### New distribution support
|
||||
|
||||
* Binary package support for Ubuntu 18.04
|
||||
|
||||
#### ROCm 1.9 is ABI compatible with KFD in upstream Linux kernels.
|
||||
Upstream Linux kernels support the following GPUs in these releases:
|
||||
4.17: Fiji, Polaris 10, Polaris 11
|
||||
4.18: Fiji, Polaris 10, Polaris 11, Vega10
|
||||
|
||||
Some ROCm features are not available in the upstream KFD:
|
||||
* More system memory available to ROCm applications
|
||||
* Interoperability between graphics and compute
|
||||
* RDMA
|
||||
* IPC
|
||||
|
||||
To try ROCm with an upstream kernel, install ROCm as normal, but do not install the rock-dkms package. Also add a udev rule to control `/dev/kfd` permissions:
|
||||
|
||||
```
|
||||
echo 'SUBSYSTEM=="kfd", KERNEL=="kfd", TAG+="uaccess", GROUP="video"' | sudo tee /etc/udev/rules.d/70-kfd.rules
|
||||
```
|
||||
|
||||
### New features as of ROCm 1.8.3
|
||||
|
||||
* ROCm 1.8.3 is a minor update meant to fix compatibility issues on Ubuntu releases running kernel 4.15.0-33
|
||||
|
||||
### New features as of ROCm 1.8
|
||||
|
||||
#### DKMS driver installation
|
||||
|
||||
* Debian packages are provided for DKMS on Ubuntu
|
||||
* RPM packages are provided for CentOS/RHEL 7.4 and 7.5 support
|
||||
* See the [ROCT-Thunk-Interface](https://github.com/RadeonOpenCompute/ROCT-Thunk-Interface/tree/roc-1.8.x) and [ROCK-Kernel-Driver](https://github.com/RadeonOpenCompute/ROCK-Kernel-Driver/tree/roc-1.8.x) for additional documentation on driver setup
|
||||
|
||||
#### New distribution support
|
||||
|
||||
* Binary package support for Ubuntu 16.04 and 18.04
|
||||
* Binary package support for CentOS 7.4 and 7.5
|
||||
* Binary package support for RHEL 7.4 and 7.5
|
||||
|
||||
#### Improved OpenMPI via UCX support
|
||||
|
||||
* UCX support for OpenMPI
|
||||
* ROCm RDMA
|
||||
|
||||
### New Features as of ROCm 1.7
|
||||
|
||||
#### DKMS driver installation
|
||||
|
||||
* New driver installation uses Dynamic Kernel Module Support (DKMS)
|
||||
* Only amdkfd and amdgpu kernel modules are installed to support AMD hardware
|
||||
* Currently only Debian packages are provided for DKMS (no Fedora suport available)
|
||||
* See the [ROCT-Thunk-Interface](https://github.com/RadeonOpenCompute/ROCT-Thunk-Interface/tree/roc-1.7.x) and [ROCK-Kernel-Driver](https://github.com/RadeonOpenCompute/ROCK-Kernel-Driver/tree/roc-1.7.x) for additional documentation on driver setup
|
||||
|
||||
### New Features as of ROCm 1.5
|
||||
|
||||
#### Developer preview of the new OpenCL 1.2 compatible language runtime and compiler
|
||||
|
||||
* OpenCL 2.0 compatible kernel language support with OpenCL 1.2 compatible
|
||||
runtime
|
||||
* Supports offline ahead of time compilation today;
|
||||
during the Beta phase we will add in-process/in-memory compilation.
|
||||
|
||||
#### Binary Package support for Ubuntu 16.04
|
||||
|
||||
#### Binary Package support for Fedora 24 is not currently available
|
||||
|
||||
#### Dropping binary package support for Ubuntu 14.04, Fedora 23
|
||||
|
||||
#### IPC support
|
||||
Reference in New Issue
Block a user