Skip to content
New issue

Have a question about this project? Sign up for a free GitHub account to open an issue and contact its maintainers and the community.

Sign up for GitHub

By clicking “Sign up for GitHub”, you agree to our terms of service and privacy statement. We’ll occasionally send you account related emails.

Already on GitHub? Sign in to your account

Jump to bottom

Add atomic intrinsics #79

Open
wants to merge 1 commit into
base: main
Choose a base branch
from
Open

Add atomic intrinsics #79

Changes from all commits
Commits
Show all changes
1 commit
Select commit
File filter

Filter by extension

Filter by extension
Conversations
Failed to load comments.
Jump to
Jump to file
Failed to load files.
Diff view
Diff view
15 changes: 15 additions & 0 deletions riscv-c-api.md
View file
Open in desktop
Original file line number Diff line number Diff line change
Expand Up @@ -440,6 +440,21 @@ RISC-V intrinsics examples:
vint8m1_t __riscv_vadd_vv_i8m1(vint8m1_t vs2, vint8m1_t vs1, size_t vl); // vadd.vv vd, vs2, vs1
```

### Atomic Intrinsics

In order to access the RISC-V atomic intrinsics, it is necessary to include the
header file `riscv_atomic.h`.

The functions are only available if the compiler's `-march` string enables the
required ISA extension.

The following table contains all the atomic intrinsics:

| Prototype | Instruction | Extension | Notes |
| --------- | ----------- | --------- | ----- |
| `void __riscv_wrs_nto();` | `wrs.nto` | Zawrs | |
| `void __riscv_wrs_sto();` | `wrs.sto` | Zawrs | |

### NTLH Intrinsics

The RISC-V zihintntl extension provides the RISC-V specific intrinsic functions for generating non-temporal memory accesses. These intrinsic functions provide the domain parameter to specify the behavior of memory accesses.
Expand Down