Comments (7)
Rather, shouldn't a library that supported RVV set vxrm
as part of supporting fenv.h
instead?
from rvv-intrinsic-doc.
We had purposed vread_csr
and vwrite_csr
interface here, but it is not included in intrinsic RFC and function list yet
enum RVV_CSR {
RVV_VSTART = 0,
RVV_VXSAT,
RVV_VXRM,
RVV_VCSR,
};
unsigned long vread_csr(enum RVV_CSR csr);
void vwrite_csr(enum RVV_CSR csr, unsigned long value);
Any comments or suggestions will be appreciated.
from rvv-intrinsic-doc.
I prefer HK's idea having specific API to read/set vector rounding mode.
In that way user doesn't need to know the format of CSR in order to read the content.
from rvv-intrinsic-doc.
I prefer high-level API for that too, the only concern to me is it's not intrinsic
.
from rvv-intrinsic-doc.
@kito-cheng do you think this is a semantic intrinsic?
If so, I think we should add this.
from rvv-intrinsic-doc.
I propose a new pull request #46 and a simple implementation here.
#define VE_TONEARESTUP 0
#define VE_TONEARESTEVEN 1
#define VE_DOWNWARD 2
#define VE_TOODD 3
// Each of these macro constants expands to a nonnegative integer constant expression.
// return 0 on success, non-zero otherwise.
int vesetxround(int round)
{
switch(round)
{
case VE_TONEARESTUP:
case VE_TONEARESTEVEN:
case VE_DOWNWARD:
case VE_TOODD:
asm volatile("csrw vxrm,%z0"::"rJ"(round));
return 0;
default:
return -1;
}
}
// return the current rounding macro, negative value if the rounding mode cannot be determined.
int vegetxround(void)
{
int vxrm;
asm volatile("csrr %0,vxrm":"=r"(vxrm));
switch(vxrm)
{
case VE_TONEARESTUP:
case VE_TONEARESTEVEN:
case VE_DOWNWARD:
case VE_TOODD:
return vxrm;
default:
return -1;
}
}
// clear vxsat
inline void veclearxsat(void)
{
asm volatile("csrw vxsat,x0");
}
// return 1 if vxsat is set, 0 otherwise.
inline int vetestxsat(void)
{
int vxsat;
asm volatile("csrr %0,vxsat":"=r"(vxsat));
return vxsat;
}
from rvv-intrinsic-doc.
We define vxrm
and vxsat
as call clobber in psABI, so this proposal become impossible to implement now.
[1] riscv-non-isa/riscv-elf-psabi-doc#294
from rvv-intrinsic-doc.
Related Issues (20)
- Question about Reinterpret Cast Conversion Functions HOT 2
- Question about segment load/store of rvv-v0p10-compatible-headers HOT 2
- Question about the rounding mode of the bit right shift functions HOT 1
- Question about intrinsic data types HOT 4
- [Error] Conversion from vuint to vbool HOT 3
- [Error] GCC Crashes while passing some intrinsics as parameter of another intrinsics HOT 3
- [Question] Combining two vector registers with different LMUL HOT 2
- Question about using `__riscv_vlm_v` HOT 2
- vcreate intrinsics for LMUL > 1 HOT 8
- [Question] How to zip 2 vectors using RVV Intrinsics? HOT 11
- Tuple types that goes across the hardware restriction HOT 1
- [Proposal] Support for C operators on RVV types HOT 12
- vget for fractional register doesn't exist HOT 10
- Constraint of vector types in Zve32* HOT 2
- [Requirement]: The RISC-V RVV vector intrinsic must include support for vector groups in the __riscv_vfredosum function HOT 4
- Type-relative overloads for vreinterpret, vlmul_ext, vlmul_trunc, etc. HOT 1
- How to use a class to wrap or derive from a sizeless vector type HOT 1
- Encode all the effects of vsetvl in the return type, for use in subsequent type deductions HOT 1
- Does `__riscv_v_intrinsic >= 1000000` imply overloaded intrinsics are supported?
- Create bibliography from reference section HOT 3
Recommend Projects
-
React
A declarative, efficient, and flexible JavaScript library for building user interfaces.
-
Vue.js
🖖 Vue.js is a progressive, incrementally-adoptable JavaScript framework for building UI on the web.
-
Typescript
TypeScript is a superset of JavaScript that compiles to clean JavaScript output.
-
TensorFlow
An Open Source Machine Learning Framework for Everyone
-
Django
The Web framework for perfectionists with deadlines.
-
Laravel
A PHP framework for web artisans
-
D3
Bring data to life with SVG, Canvas and HTML. 📊📈🎉
-
Recommend Topics
-
javascript
JavaScript (JS) is a lightweight interpreted programming language with first-class functions.
-
web
Some thing interesting about web. New door for the world.
-
server
A server is a program made to process requests and deliver data to clients.
-
Machine learning
Machine learning is a way of modeling and interpreting data that allows a piece of software to respond intelligently.
-
Visualization
Some thing interesting about visualization, use data art
-
Game
Some thing interesting about game, make everyone happy.
Recommend Org
-
Facebook
We are working to build community through open source technology. NB: members must have two-factor auth.
-
Microsoft
Open source projects and samples from Microsoft.
-
Google
Google ❤️ Open Source for everyone.
-
Alibaba
Alibaba Open Source for everyone
-
D3
Data-Driven Documents codes.
-
Tencent
China tencent open source team.
from rvv-intrinsic-doc.