* [PATCH v1] RISC-V: Upgrade RVV intrinsic version to 0.12 @ 2024-02-21 4:27 pan2.li 2024-02-21 4:31 ` Li, Pan2 0 siblings, 1 reply; 8+ messages in thread From: pan2.li @ 2024-02-21 4:27 UTC (permalink / raw) To: gcc-patches; +Cc: juzhe.zhong, pan2.li, yanzhang.wang, kito.cheng From: Pan Li <pan2.li@intel.com> Upgrade the version of RVV intrinsic from 0.11 to 0.12. PR target/114017 gcc/ChangeLog: * config/riscv/riscv-c.cc (riscv_cpu_cpp_builtins): Upgrade the version to 0.12. gcc/testsuite/ChangeLog: * gcc.target/riscv/predef-__riscv_v_intrinsic.c: Update the version to 0.12. * gcc.target/riscv/rvv/base/pr114017-1.c: New test. Signed-off-by: Pan Li <pan2.li@intel.com> --- gcc/config/riscv/riscv-c.cc | 2 +- .../riscv/predef-__riscv_v_intrinsic.c | 2 +- .../gcc.target/riscv/rvv/base/pr114017-1.c | 19 +++++++++++++++++++ 3 files changed, 21 insertions(+), 2 deletions(-) create mode 100644 gcc/testsuite/gcc.target/riscv/rvv/base/pr114017-1.c diff --git a/gcc/config/riscv/riscv-c.cc b/gcc/config/riscv/riscv-c.cc index 3ef06dcfd2d..3755ec0b8ef 100644 --- a/gcc/config/riscv/riscv-c.cc +++ b/gcc/config/riscv/riscv-c.cc @@ -139,7 +139,7 @@ riscv_cpu_cpp_builtins (cpp_reader *pfile) { builtin_define ("__riscv_vector"); builtin_define_with_int_value ("__riscv_v_intrinsic", - riscv_ext_version_value (0, 11)); + riscv_ext_version_value (0, 12)); } if (TARGET_XTHEADVECTOR) diff --git a/gcc/testsuite/gcc.target/riscv/predef-__riscv_v_intrinsic.c b/gcc/testsuite/gcc.target/riscv/predef-__riscv_v_intrinsic.c index dbbedf54f87..07f1f159a8f 100644 --- a/gcc/testsuite/gcc.target/riscv/predef-__riscv_v_intrinsic.c +++ b/gcc/testsuite/gcc.target/riscv/predef-__riscv_v_intrinsic.c @@ -3,7 +3,7 @@ int main () { -#if __riscv_v_intrinsic != 11000 +#if __riscv_v_intrinsic != 12000 #error "__riscv_v_intrinsic" #endif diff --git a/gcc/testsuite/gcc.target/riscv/rvv/base/pr114017-1.c b/gcc/testsuite/gcc.target/riscv/rvv/base/pr114017-1.c new file mode 100644 index 00000000000..8eee7c68f71 --- /dev/null +++ b/gcc/testsuite/gcc.target/riscv/rvv/base/pr114017-1.c @@ -0,0 +1,19 @@ +/* { dg-do compile } */ +/* { dg-options "-march=rv64gcv -mabi=lp64d -O3" } */ + +#include "riscv_vector.h" + +vuint8mf2_t +test (vuint16m1_t val, size_t shift, size_t vl) +{ +#if __riscv_v_intrinsic == 11000 + #warning "RVV Intrinsics v0.11" + return __riscv_vnclipu (val, shift, vl); +#endif + +#if __riscv_v_intrinsic == 12000 + #warning "RVV Intrinsics v0.12" /* { dg-warning "RVV Intrinsics v0.12" } */ + return __riscv_vnclipu (val, shift, 0, vl); +#endif +} + -- 2.34.1 ^ permalink raw reply [flat|nested] 8+ messages in thread
* RE: [PATCH v1] RISC-V: Upgrade RVV intrinsic version to 0.12 2024-02-21 4:27 [PATCH v1] RISC-V: Upgrade RVV intrinsic version to 0.12 pan2.li @ 2024-02-21 4:31 ` Li, Pan2 2024-02-21 23:34 ` Kito Cheng 0 siblings, 1 reply; 8+ messages in thread From: Li, Pan2 @ 2024-02-21 4:31 UTC (permalink / raw) To: gcc-patches; +Cc: juzhe.zhong, Wang, Yanzhang, kito.cheng Hi kito and juzhe. There may be 2 items for double-confirm. Thanks a lot. 1. Not very sure if we need to upgrade the version for __riscv_th_v_intrinsic. 2. Do we need to upgrade the even a newer version (like 1.0) for the GCC 14 release, or we can do it later. Pan -----Original Message----- From: Li, Pan2 <pan2.li@intel.com> Sent: Wednesday, February 21, 2024 12:27 PM To: gcc-patches@gcc.gnu.org Cc: juzhe.zhong@rivai.ai; Li, Pan2 <pan2.li@intel.com>; Wang, Yanzhang <yanzhang.wang@intel.com>; kito.cheng@gmail.com Subject: [PATCH v1] RISC-V: Upgrade RVV intrinsic version to 0.12 From: Pan Li <pan2.li@intel.com> Upgrade the version of RVV intrinsic from 0.11 to 0.12. PR target/114017 gcc/ChangeLog: * config/riscv/riscv-c.cc (riscv_cpu_cpp_builtins): Upgrade the version to 0.12. gcc/testsuite/ChangeLog: * gcc.target/riscv/predef-__riscv_v_intrinsic.c: Update the version to 0.12. * gcc.target/riscv/rvv/base/pr114017-1.c: New test. Signed-off-by: Pan Li <pan2.li@intel.com> --- gcc/config/riscv/riscv-c.cc | 2 +- .../riscv/predef-__riscv_v_intrinsic.c | 2 +- .../gcc.target/riscv/rvv/base/pr114017-1.c | 19 +++++++++++++++++++ 3 files changed, 21 insertions(+), 2 deletions(-) create mode 100644 gcc/testsuite/gcc.target/riscv/rvv/base/pr114017-1.c diff --git a/gcc/config/riscv/riscv-c.cc b/gcc/config/riscv/riscv-c.cc index 3ef06dcfd2d..3755ec0b8ef 100644 --- a/gcc/config/riscv/riscv-c.cc +++ b/gcc/config/riscv/riscv-c.cc @@ -139,7 +139,7 @@ riscv_cpu_cpp_builtins (cpp_reader *pfile) { builtin_define ("__riscv_vector"); builtin_define_with_int_value ("__riscv_v_intrinsic", - riscv_ext_version_value (0, 11)); + riscv_ext_version_value (0, 12)); } if (TARGET_XTHEADVECTOR) diff --git a/gcc/testsuite/gcc.target/riscv/predef-__riscv_v_intrinsic.c b/gcc/testsuite/gcc.target/riscv/predef-__riscv_v_intrinsic.c index dbbedf54f87..07f1f159a8f 100644 --- a/gcc/testsuite/gcc.target/riscv/predef-__riscv_v_intrinsic.c +++ b/gcc/testsuite/gcc.target/riscv/predef-__riscv_v_intrinsic.c @@ -3,7 +3,7 @@ int main () { -#if __riscv_v_intrinsic != 11000 +#if __riscv_v_intrinsic != 12000 #error "__riscv_v_intrinsic" #endif diff --git a/gcc/testsuite/gcc.target/riscv/rvv/base/pr114017-1.c b/gcc/testsuite/gcc.target/riscv/rvv/base/pr114017-1.c new file mode 100644 index 00000000000..8eee7c68f71 --- /dev/null +++ b/gcc/testsuite/gcc.target/riscv/rvv/base/pr114017-1.c @@ -0,0 +1,19 @@ +/* { dg-do compile } */ +/* { dg-options "-march=rv64gcv -mabi=lp64d -O3" } */ + +#include "riscv_vector.h" + +vuint8mf2_t +test (vuint16m1_t val, size_t shift, size_t vl) +{ +#if __riscv_v_intrinsic == 11000 + #warning "RVV Intrinsics v0.11" + return __riscv_vnclipu (val, shift, vl); +#endif + +#if __riscv_v_intrinsic == 12000 + #warning "RVV Intrinsics v0.12" /* { dg-warning "RVV Intrinsics v0.12" } */ + return __riscv_vnclipu (val, shift, 0, vl); +#endif +} + -- 2.34.1 ^ permalink raw reply [flat|nested] 8+ messages in thread
* Re: [PATCH v1] RISC-V: Upgrade RVV intrinsic version to 0.12 2024-02-21 4:31 ` Li, Pan2 @ 2024-02-21 23:34 ` Kito Cheng 2024-02-21 23:41 ` Palmer Dabbelt 2024-02-22 1:22 ` Li, Pan2 0 siblings, 2 replies; 8+ messages in thread From: Kito Cheng @ 2024-02-21 23:34 UTC (permalink / raw) To: Li, Pan2; +Cc: GCC Patches, 钟居哲, Wang, Yanzhang [-- Attachment #1: Type: text/plain, Size: 3590 bytes --] LGTM for the patch Li, Pan2 <pan2.li@intel.com> 於 2024年2月21日 週三 12:31 寫道： > Hi kito and juzhe. > > There may be 2 items for double-confirm. Thanks a lot. > > 1. Not very sure if we need to upgrade the version for > __riscv_th_v_intrinsic. > Yes since 0.11 and 0.12 is not really compatible 2. Do we need to upgrade the even a newer version (like 1.0) for the GCC 14 > release, or we can do it later. > Yeah, Ideal case is we can update that before release made :p > Pan > > -----Original Message----- > From: Li, Pan2 <pan2.li@intel.com> > Sent: Wednesday, February 21, 2024 12:27 PM > To: gcc-patches@gcc.gnu.org > Cc: juzhe.zhong@rivai.ai; Li, Pan2 <pan2.li@intel.com>; Wang, Yanzhang < > yanzhang.wang@intel.com>; kito.cheng@gmail.com > Subject: [PATCH v1] RISC-V: Upgrade RVV intrinsic version to 0.12 > > From: Pan Li <pan2.li@intel.com> > > Upgrade the version of RVV intrinsic from 0.11 to 0.12. > > PR target/114017 > > gcc/ChangeLog: > > * config/riscv/riscv-c.cc (riscv_cpu_cpp_builtins): Upgrade > the version to 0.12. > > gcc/testsuite/ChangeLog: > > * gcc.target/riscv/predef-__riscv_v_intrinsic.c: Update the > version to 0.12. > * gcc.target/riscv/rvv/base/pr114017-1.c: New test. > > Signed-off-by: Pan Li <pan2.li@intel.com> > --- > gcc/config/riscv/riscv-c.cc | 2 +- > .../riscv/predef-__riscv_v_intrinsic.c | 2 +- > .../gcc.target/riscv/rvv/base/pr114017-1.c | 19 +++++++++++++++++++ > 3 files changed, 21 insertions(+), 2 deletions(-) > create mode 100644 gcc/testsuite/gcc.target/riscv/rvv/base/pr114017-1.c > > diff --git a/gcc/config/riscv/riscv-c.cc b/gcc/config/riscv/riscv-c.cc > index 3ef06dcfd2d..3755ec0b8ef 100644 > --- a/gcc/config/riscv/riscv-c.cc > +++ b/gcc/config/riscv/riscv-c.cc > @@ -139,7 +139,7 @@ riscv_cpu_cpp_builtins (cpp_reader *pfile) > { > builtin_define ("__riscv_vector"); > builtin_define_with_int_value ("__riscv_v_intrinsic", > - riscv_ext_version_value (0, 11)); > + riscv_ext_version_value (0, 12)); > } > > if (TARGET_XTHEADVECTOR) > diff --git a/gcc/testsuite/gcc.target/riscv/predef-__riscv_v_intrinsic.c > b/gcc/testsuite/gcc.target/riscv/predef-__riscv_v_intrinsic.c > index dbbedf54f87..07f1f159a8f 100644 > --- a/gcc/testsuite/gcc.target/riscv/predef-__riscv_v_intrinsic.c > +++ b/gcc/testsuite/gcc.target/riscv/predef-__riscv_v_intrinsic.c > @@ -3,7 +3,7 @@ > > int main () { > > -#if __riscv_v_intrinsic != 11000 > +#if __riscv_v_intrinsic != 12000 > #error "__riscv_v_intrinsic" > #endif > > diff --git a/gcc/testsuite/gcc.target/riscv/rvv/base/pr114017-1.c > b/gcc/testsuite/gcc.target/riscv/rvv/base/pr114017-1.c > new file mode 100644 > index 00000000000..8eee7c68f71 > --- /dev/null > +++ b/gcc/testsuite/gcc.target/riscv/rvv/base/pr114017-1.c > @@ -0,0 +1,19 @@ > +/* { dg-do compile } */ > +/* { dg-options "-march=rv64gcv -mabi=lp64d -O3" } */ > + > +#include "riscv_vector.h" > + > +vuint8mf2_t > +test (vuint16m1_t val, size_t shift, size_t vl) > +{ > +#if __riscv_v_intrinsic == 11000 > + #warning "RVV Intrinsics v0.11" > + return __riscv_vnclipu (val, shift, vl); > +#endif > + > +#if __riscv_v_intrinsic == 12000 > + #warning "RVV Intrinsics v0.12" /* { dg-warning "RVV Intrinsics v0.12" > } */ > + return __riscv_vnclipu (val, shift, 0, vl); > +#endif > +} > + > -- > 2.34.1 > > ^ permalink raw reply [flat|nested] 8+ messages in thread
* Re: [PATCH v1] RISC-V: Upgrade RVV intrinsic version to 0.12 2024-02-21 23:34 ` Kito Cheng @ 2024-02-21 23:41 ` Palmer Dabbelt 2024-02-22 0:02 ` Kito Cheng 2024-02-22 1:22 ` Li, Pan2 1 sibling, 1 reply; 8+ messages in thread From: Palmer Dabbelt @ 2024-02-21 23:41 UTC (permalink / raw) To: Kito Cheng; +Cc: pan2.li, gcc-patches, juzhe.zhong, yanzhang.wang On Wed, 21 Feb 2024 15:34:32 PST (-0800), Kito Cheng wrote: > LGTM for the patch > > Li, Pan2 <pan2.li@intel.com> 於 2024年2月21日 週三 12:31 寫道： > >> Hi kito and juzhe. >> >> There may be 2 items for double-confirm. Thanks a lot. >> >> 1. Not very sure if we need to upgrade the version for >> __riscv_th_v_intrinsic. >> > > Yes since 0.11 and 0.12 is not really compatible Where are the incompatibilities? The whole reason we accepted the intrinsics in the first place is because the RVI folks said they wouldn't break compatibility, if that's changed then just dropping the old version is going to break users. > 2. Do we need to upgrade the even a newer version (like 1.0) for the GCC 14 >> release, or we can do it later. >> > > Yeah, Ideal case is we can update that before release made :p > > > > >> Pan >> >> -----Original Message----- >> From: Li, Pan2 <pan2.li@intel.com> >> Sent: Wednesday, February 21, 2024 12:27 PM >> To: gcc-patches@gcc.gnu.org >> Cc: juzhe.zhong@rivai.ai; Li, Pan2 <pan2.li@intel.com>; Wang, Yanzhang < >> yanzhang.wang@intel.com>; kito.cheng@gmail.com >> Subject: [PATCH v1] RISC-V: Upgrade RVV intrinsic version to 0.12 >> >> From: Pan Li <pan2.li@intel.com> >> >> Upgrade the version of RVV intrinsic from 0.11 to 0.12. >> >> PR target/114017 >> >> gcc/ChangeLog: >> >> * config/riscv/riscv-c.cc (riscv_cpu_cpp_builtins): Upgrade >> the version to 0.12. >> >> gcc/testsuite/ChangeLog: >> >> * gcc.target/riscv/predef-__riscv_v_intrinsic.c: Update the >> version to 0.12. >> * gcc.target/riscv/rvv/base/pr114017-1.c: New test. >> >> Signed-off-by: Pan Li <pan2.li@intel.com> >> --- >> gcc/config/riscv/riscv-c.cc | 2 +- >> .../riscv/predef-__riscv_v_intrinsic.c | 2 +- >> .../gcc.target/riscv/rvv/base/pr114017-1.c | 19 +++++++++++++++++++ >> 3 files changed, 21 insertions(+), 2 deletions(-) >> create mode 100644 gcc/testsuite/gcc.target/riscv/rvv/base/pr114017-1.c >> >> diff --git a/gcc/config/riscv/riscv-c.cc b/gcc/config/riscv/riscv-c.cc >> index 3ef06dcfd2d..3755ec0b8ef 100644 >> --- a/gcc/config/riscv/riscv-c.cc >> +++ b/gcc/config/riscv/riscv-c.cc >> @@ -139,7 +139,7 @@ riscv_cpu_cpp_builtins (cpp_reader *pfile) >> { >> builtin_define ("__riscv_vector"); >> builtin_define_with_int_value ("__riscv_v_intrinsic", >> - riscv_ext_version_value (0, 11)); >> + riscv_ext_version_value (0, 12)); >> } >> >> if (TARGET_XTHEADVECTOR) >> diff --git a/gcc/testsuite/gcc.target/riscv/predef-__riscv_v_intrinsic.c >> b/gcc/testsuite/gcc.target/riscv/predef-__riscv_v_intrinsic.c >> index dbbedf54f87..07f1f159a8f 100644 >> --- a/gcc/testsuite/gcc.target/riscv/predef-__riscv_v_intrinsic.c >> +++ b/gcc/testsuite/gcc.target/riscv/predef-__riscv_v_intrinsic.c >> @@ -3,7 +3,7 @@ >> >> int main () { >> >> -#if __riscv_v_intrinsic != 11000 >> +#if __riscv_v_intrinsic != 12000 >> #error "__riscv_v_intrinsic" >> #endif >> >> diff --git a/gcc/testsuite/gcc.target/riscv/rvv/base/pr114017-1.c >> b/gcc/testsuite/gcc.target/riscv/rvv/base/pr114017-1.c >> new file mode 100644 >> index 00000000000..8eee7c68f71 >> --- /dev/null >> +++ b/gcc/testsuite/gcc.target/riscv/rvv/base/pr114017-1.c >> @@ -0,0 +1,19 @@ >> +/* { dg-do compile } */ >> +/* { dg-options "-march=rv64gcv -mabi=lp64d -O3" } */ >> + >> +#include "riscv_vector.h" >> + >> +vuint8mf2_t >> +test (vuint16m1_t val, size_t shift, size_t vl) >> +{ >> +#if __riscv_v_intrinsic == 11000 >> + #warning "RVV Intrinsics v0.11" >> + return __riscv_vnclipu (val, shift, vl); >> +#endif >> + >> +#if __riscv_v_intrinsic == 12000 >> + #warning "RVV Intrinsics v0.12" /* { dg-warning "RVV Intrinsics v0.12" >> } */ >> + return __riscv_vnclipu (val, shift, 0, vl); >> +#endif >> +} >> + >> -- >> 2.34.1 >> >> ^ permalink raw reply [flat|nested] 8+ messages in thread
* Re: [PATCH v1] RISC-V: Upgrade RVV intrinsic version to 0.12 2024-02-21 23:41 ` Palmer Dabbelt @ 2024-02-22 0:02 ` Kito Cheng 2024-02-22 19:47 ` Palmer Dabbelt 0 siblings, 1 reply; 8+ messages in thread From: Kito Cheng @ 2024-02-22 0:02 UTC (permalink / raw) To: Palmer Dabbelt Cc: Li, Pan2, GCC Patches, 钟居哲, yanzhang.wang [-- Attachment #1: Type: text/plain, Size: 4987 bytes --] Palmer Dabbelt <palmer@dabbelt.com> 於 2024年2月22日 週四 07:42 寫道： > On Wed, 21 Feb 2024 15:34:32 PST (-0800), Kito Cheng wrote: > > LGTM for the patch > > > > Li, Pan2 <pan2.li@intel.com> 於 2024年2月21日 週三 12:31 寫道： > > > >> Hi kito and juzhe. > >> > >> There may be 2 items for double-confirm. Thanks a lot. > >> > >> 1. Not very sure if we need to upgrade the version for > >> __riscv_th_v_intrinsic. > >> > > > > Yes since 0.11 and 0.12 is not really compatible > > Where are the incompatibilities? The whole reason we accepted the > intrinsics in the first place is because the RVI folks said they > wouldn't break compatibility, if that's changed then just dropping the > old version is going to break users. > 0.12 have interface for segment load store and new fixed points intrinsic compare to 0.11, the first one item is not incompatible change since it's new added and gcc 13 isn't implemented the legacy one, the later one is kinda broken on both llvm and gcc which is made is not really useful in practice. Other than that, everything are same, it's not 100% compatible so I am not intend to cheating my self to say it's compatible, but we do think it's necessary evil since fixing point stuff are not right design and implementation. Anyway it's became frozen mode, 1.0 rc0 has been tagged, no API will change/remove. > > 2. Do we need to upgrade the even a newer version (like 1.0) for the GCC > 14 > >> release, or we can do it later. > >> > > > > Yeah, Ideal case is we can update that before release made :p > > > > > > > > > >> Pan > >> > >> -----Original Message----- > >> From: Li, Pan2 <pan2.li@intel.com> > >> Sent: Wednesday, February 21, 2024 12:27 PM > >> To: gcc-patches@gcc.gnu.org > >> Cc: juzhe.zhong@rivai.ai; Li, Pan2 <pan2.li@intel.com>; Wang, Yanzhang > < > >> yanzhang.wang@intel.com>; kito.cheng@gmail.com > >> Subject: [PATCH v1] RISC-V: Upgrade RVV intrinsic version to 0.12 > >> > >> From: Pan Li <pan2.li@intel.com> > >> > >> Upgrade the version of RVV intrinsic from 0.11 to 0.12. > >> > >> PR target/114017 > >> > >> gcc/ChangeLog: > >> > >> * config/riscv/riscv-c.cc (riscv_cpu_cpp_builtins): Upgrade > >> the version to 0.12. > >> > >> gcc/testsuite/ChangeLog: > >> > >> * gcc.target/riscv/predef-__riscv_v_intrinsic.c: Update the > >> version to 0.12. > >> * gcc.target/riscv/rvv/base/pr114017-1.c: New test. > >> > >> Signed-off-by: Pan Li <pan2.li@intel.com> > >> --- > >> gcc/config/riscv/riscv-c.cc | 2 +- > >> .../riscv/predef-__riscv_v_intrinsic.c | 2 +- > >> .../gcc.target/riscv/rvv/base/pr114017-1.c | 19 +++++++++++++++++++ > >> 3 files changed, 21 insertions(+), 2 deletions(-) > >> create mode 100644 gcc/testsuite/gcc.target/riscv/rvv/base/pr114017-1.c > >> > >> diff --git a/gcc/config/riscv/riscv-c.cc b/gcc/config/riscv/riscv-c.cc > >> index 3ef06dcfd2d..3755ec0b8ef 100644 > >> --- a/gcc/config/riscv/riscv-c.cc > >> +++ b/gcc/config/riscv/riscv-c.cc > >> @@ -139,7 +139,7 @@ riscv_cpu_cpp_builtins (cpp_reader *pfile) > >> { > >> builtin_define ("__riscv_vector"); > >> builtin_define_with_int_value ("__riscv_v_intrinsic", > >> - riscv_ext_version_value (0, 11)); > >> + riscv_ext_version_value (0, 12)); > >> } > >> > >> if (TARGET_XTHEADVECTOR) > >> diff --git a/gcc/testsuite/gcc.target/riscv/predef-__riscv_v_intrinsic.c > >> b/gcc/testsuite/gcc.target/riscv/predef-__riscv_v_intrinsic.c > >> index dbbedf54f87..07f1f159a8f 100644 > >> --- a/gcc/testsuite/gcc.target/riscv/predef-__riscv_v_intrinsic.c > >> +++ b/gcc/testsuite/gcc.target/riscv/predef-__riscv_v_intrinsic.c > >> @@ -3,7 +3,7 @@ > >> > >> int main () { > >> > >> -#if __riscv_v_intrinsic != 11000 > >> +#if __riscv_v_intrinsic != 12000 > >> #error "__riscv_v_intrinsic" > >> #endif > >> > >> diff --git a/gcc/testsuite/gcc.target/riscv/rvv/base/pr114017-1.c > >> b/gcc/testsuite/gcc.target/riscv/rvv/base/pr114017-1.c > >> new file mode 100644 > >> index 00000000000..8eee7c68f71 > >> --- /dev/null > >> +++ b/gcc/testsuite/gcc.target/riscv/rvv/base/pr114017-1.c > >> @@ -0,0 +1,19 @@ > >> +/* { dg-do compile } */ > >> +/* { dg-options "-march=rv64gcv -mabi=lp64d -O3" } */ > >> + > >> +#include "riscv_vector.h" > >> + > >> +vuint8mf2_t > >> +test (vuint16m1_t val, size_t shift, size_t vl) > >> +{ > >> +#if __riscv_v_intrinsic == 11000 > >> + #warning "RVV Intrinsics v0.11" > >> + return __riscv_vnclipu (val, shift, vl); > >> +#endif > >> + > >> +#if __riscv_v_intrinsic == 12000 > >> + #warning "RVV Intrinsics v0.12" /* { dg-warning "RVV Intrinsics > v0.12" > >> } */ > >> + return __riscv_vnclipu (val, shift, 0, vl); > >> +#endif > >> +} > >> + > >> -- > >> 2.34.1 > >> > >> > ^ permalink raw reply [flat|nested] 8+ messages in thread
* Re: [PATCH v1] RISC-V: Upgrade RVV intrinsic version to 0.12 2024-02-22 0:02 ` Kito Cheng @ 2024-02-22 19:47 ` Palmer Dabbelt 2024-02-26 6:42 ` Kito Cheng 0 siblings, 1 reply; 8+ messages in thread From: Palmer Dabbelt @ 2024-02-22 19:47 UTC (permalink / raw) To: Kito Cheng; +Cc: pan2.li, gcc-patches, juzhe.zhong, yanzhang.wang On Wed, 21 Feb 2024 16:02:50 PST (-0800), Kito Cheng wrote: > Palmer Dabbelt <palmer@dabbelt.com> 於 2024年2月22日 週四 07:42 寫道： > >> On Wed, 21 Feb 2024 15:34:32 PST (-0800), Kito Cheng wrote: >> > LGTM for the patch >> > >> > Li, Pan2 <pan2.li@intel.com> 於 2024年2月21日 週三 12:31 寫道： >> > >> >> Hi kito and juzhe. >> >> >> >> There may be 2 items for double-confirm. Thanks a lot. >> >> >> >> 1. Not very sure if we need to upgrade the version for >> >> __riscv_th_v_intrinsic. >> >> >> > >> > Yes since 0.11 and 0.12 is not really compatible >> >> Where are the incompatibilities? The whole reason we accepted the >> intrinsics in the first place is because the RVI folks said they >> wouldn't break compatibility, if that's changed then just dropping the >> old version is going to break users. >> > > 0.12 have interface for segment load store and new fixed points intrinsic > compare to 0.11, the first one item is not incompatible change since it's > new added and gcc 13 isn't implemented the legacy one, the later one is > kinda broken on both llvm and gcc which is made is not really useful in > practice. > > Other than that, everything are same, it's not 100% compatible so I am not > intend to cheating my self to say it's compatible, but we do think it's > necessary evil since fixing point stuff are not right design and > implementation. OK, those don't seem so scary. So maybe let's just put it in a NEWS entry or something? It's mildly interesting to users, but I agree the earlier intrinsics spec was vague enough in some areas we can get away with the diffs I've seen. > Anyway it's became frozen mode, 1.0 rc0 has been tagged, no API will > change/remove. OK, so I guess we should move to 1.0, then? Are you guys going to pick that up? > > >> > 2. Do we need to upgrade the even a newer version (like 1.0) for the GCC >> 14 >> >> release, or we can do it later. >> >> >> > >> > Yeah, Ideal case is we can update that before release made :p >> > >> > >> > >> > >> >> Pan >> >> >> >> -----Original Message----- >> >> From: Li, Pan2 <pan2.li@intel.com> >> >> Sent: Wednesday, February 21, 2024 12:27 PM >> >> To: gcc-patches@gcc.gnu.org >> >> Cc: juzhe.zhong@rivai.ai; Li, Pan2 <pan2.li@intel.com>; Wang, Yanzhang >> < >> >> yanzhang.wang@intel.com>; kito.cheng@gmail.com >> >> Subject: [PATCH v1] RISC-V: Upgrade RVV intrinsic version to 0.12 >> >> >> >> From: Pan Li <pan2.li@intel.com> >> >> >> >> Upgrade the version of RVV intrinsic from 0.11 to 0.12. >> >> >> >> PR target/114017 >> >> >> >> gcc/ChangeLog: >> >> >> >> * config/riscv/riscv-c.cc (riscv_cpu_cpp_builtins): Upgrade >> >> the version to 0.12. >> >> >> >> gcc/testsuite/ChangeLog: >> >> >> >> * gcc.target/riscv/predef-__riscv_v_intrinsic.c: Update the >> >> version to 0.12. >> >> * gcc.target/riscv/rvv/base/pr114017-1.c: New test. >> >> >> >> Signed-off-by: Pan Li <pan2.li@intel.com> >> >> --- >> >> gcc/config/riscv/riscv-c.cc | 2 +- >> >> .../riscv/predef-__riscv_v_intrinsic.c | 2 +- >> >> .../gcc.target/riscv/rvv/base/pr114017-1.c | 19 +++++++++++++++++++ >> >> 3 files changed, 21 insertions(+), 2 deletions(-) >> >> create mode 100644 gcc/testsuite/gcc.target/riscv/rvv/base/pr114017-1.c >> >> >> >> diff --git a/gcc/config/riscv/riscv-c.cc b/gcc/config/riscv/riscv-c.cc >> >> index 3ef06dcfd2d..3755ec0b8ef 100644 >> >> --- a/gcc/config/riscv/riscv-c.cc >> >> +++ b/gcc/config/riscv/riscv-c.cc >> >> @@ -139,7 +139,7 @@ riscv_cpu_cpp_builtins (cpp_reader *pfile) >> >> { >> >> builtin_define ("__riscv_vector"); >> >> builtin_define_with_int_value ("__riscv_v_intrinsic", >> >> - riscv_ext_version_value (0, 11)); >> >> + riscv_ext_version_value (0, 12)); >> >> } >> >> >> >> if (TARGET_XTHEADVECTOR) >> >> diff --git a/gcc/testsuite/gcc.target/riscv/predef-__riscv_v_intrinsic.c >> >> b/gcc/testsuite/gcc.target/riscv/predef-__riscv_v_intrinsic.c >> >> index dbbedf54f87..07f1f159a8f 100644 >> >> --- a/gcc/testsuite/gcc.target/riscv/predef-__riscv_v_intrinsic.c >> >> +++ b/gcc/testsuite/gcc.target/riscv/predef-__riscv_v_intrinsic.c >> >> @@ -3,7 +3,7 @@ >> >> >> >> int main () { >> >> >> >> -#if __riscv_v_intrinsic != 11000 >> >> +#if __riscv_v_intrinsic != 12000 >> >> #error "__riscv_v_intrinsic" >> >> #endif >> >> >> >> diff --git a/gcc/testsuite/gcc.target/riscv/rvv/base/pr114017-1.c >> >> b/gcc/testsuite/gcc.target/riscv/rvv/base/pr114017-1.c >> >> new file mode 100644 >> >> index 00000000000..8eee7c68f71 >> >> --- /dev/null >> >> +++ b/gcc/testsuite/gcc.target/riscv/rvv/base/pr114017-1.c >> >> @@ -0,0 +1,19 @@ >> >> +/* { dg-do compile } */ >> >> +/* { dg-options "-march=rv64gcv -mabi=lp64d -O3" } */ >> >> + >> >> +#include "riscv_vector.h" >> >> + >> >> +vuint8mf2_t >> >> +test (vuint16m1_t val, size_t shift, size_t vl) >> >> +{ >> >> +#if __riscv_v_intrinsic == 11000 >> >> + #warning "RVV Intrinsics v0.11" >> >> + return __riscv_vnclipu (val, shift, vl); >> >> +#endif >> >> + >> >> +#if __riscv_v_intrinsic == 12000 >> >> + #warning "RVV Intrinsics v0.12" /* { dg-warning "RVV Intrinsics >> v0.12" >> >> } */ >> >> + return __riscv_vnclipu (val, shift, 0, vl); >> >> +#endif >> >> +} >> >> + >> >> -- >> >> 2.34.1 >> >> >> >> >> ^ permalink raw reply [flat|nested] 8+ messages in thread
* Re: [PATCH v1] RISC-V: Upgrade RVV intrinsic version to 0.12 2024-02-22 19:47 ` Palmer Dabbelt @ 2024-02-26 6:42 ` Kito Cheng 0 siblings, 0 replies; 8+ messages in thread From: Kito Cheng @ 2024-02-26 6:42 UTC (permalink / raw) To: Palmer Dabbelt; +Cc: pan2.li, gcc-patches, juzhe.zhong, yanzhang.wang On Fri, Feb 23, 2024 at 3:48 AM Palmer Dabbelt <palmer@dabbelt.com> wrote: > > On Wed, 21 Feb 2024 16:02:50 PST (-0800), Kito Cheng wrote: > > Palmer Dabbelt <palmer@dabbelt.com> 於 2024年2月22日 週四 07:42 寫道： > > > >> On Wed, 21 Feb 2024 15:34:32 PST (-0800), Kito Cheng wrote: > >> > LGTM for the patch > >> > > >> > Li, Pan2 <pan2.li@intel.com> 於 2024年2月21日 週三 12:31 寫道： > >> > > >> >> Hi kito and juzhe. > >> >> > >> >> There may be 2 items for double-confirm. Thanks a lot. > >> >> > >> >> 1. Not very sure if we need to upgrade the version for > >> >> __riscv_th_v_intrinsic. > >> >> > >> > > >> > Yes since 0.11 and 0.12 is not really compatible > >> > >> Where are the incompatibilities? The whole reason we accepted the > >> intrinsics in the first place is because the RVI folks said they > >> wouldn't break compatibility, if that's changed then just dropping the > >> old version is going to break users. > >> > > > > 0.12 have interface for segment load store and new fixed points intrinsic > > compare to 0.11, the first one item is not incompatible change since it's > > new added and gcc 13 isn't implemented the legacy one, the later one is > > kinda broken on both llvm and gcc which is made is not really useful in > > practice. > > > > Other than that, everything are same, it's not 100% compatible so I am not > > intend to cheating my self to say it's compatible, but we do think it's > > necessary evil since fixing point stuff are not right design and > > implementation. > > OK, those don't seem so scary. So maybe let's just put it in a NEWS > entry or something? It's mildly interesting to users, but I agree the > earlier intrinsics spec was vague enough in some areas we can get away > with the diffs I've seen. Yeah, thanks for the reminder, I guess we need to prepare to update more NEWS entries... > > > Anyway it's became frozen mode, 1.0 rc0 has been tagged, no API will > > change/remove. > > OK, so I guess we should move to 1.0, then? Are you guys going to pick > that up? No difference between 0.12 and 1.0...here is just some paperwork for the process that is still ongoing...but anyway we will handle that. ^ permalink raw reply [flat|nested] 8+ messages in thread
* RE: [PATCH v1] RISC-V: Upgrade RVV intrinsic version to 0.12 2024-02-21 23:34 ` Kito Cheng 2024-02-21 23:41 ` Palmer Dabbelt @ 2024-02-22 1:22 ` Li, Pan2 1 sibling, 0 replies; 8+ messages in thread From: Li, Pan2 @ 2024-02-22 1:22 UTC (permalink / raw) To: Kito Cheng; +Cc: GCC Patches, 钟居哲, Wang, Yanzhang [-- Attachment #1: Type: text/plain, Size: 3983 bytes --] Committed, thanks Kito. Pan From: Kito Cheng <kito.cheng@gmail.com> Sent: Thursday, February 22, 2024 7:35 AM To: Li, Pan2 <pan2.li@intel.com> Cc: GCC Patches <gcc-patches@gcc.gnu.org>; 钟居哲 <juzhe.zhong@rivai.ai>; Wang, Yanzhang <yanzhang.wang@intel.com> Subject: Re: [PATCH v1] RISC-V: Upgrade RVV intrinsic version to 0.12 LGTM for the patch Li, Pan2 <pan2.li@intel.com<mailto:pan2.li@intel.com>> 於 2024年2月21日 週三 12:31 寫道： Hi kito and juzhe. There may be 2 items for double-confirm. Thanks a lot. 1. Not very sure if we need to upgrade the version for __riscv_th_v_intrinsic. Yes since 0.11 and 0.12 is not really compatible 2. Do we need to upgrade the even a newer version (like 1.0) for the GCC 14 release, or we can do it later. Yeah, Ideal case is we can update that before release made :p Pan -----Original Message----- From: Li, Pan2 <pan2.li@intel.com<mailto:pan2.li@intel.com>> Sent: Wednesday, February 21, 2024 12:27 PM To: gcc-patches@gcc.gnu.org<mailto:gcc-patches@gcc.gnu.org> Cc: juzhe.zhong@rivai.ai<mailto:juzhe.zhong@rivai.ai>; Li, Pan2 <pan2.li@intel.com<mailto:pan2.li@intel.com>>; Wang, Yanzhang <yanzhang.wang@intel.com<mailto:yanzhang.wang@intel.com>>; kito.cheng@gmail.com<mailto:kito.cheng@gmail.com> Subject: [PATCH v1] RISC-V: Upgrade RVV intrinsic version to 0.12 From: Pan Li <pan2.li@intel.com<mailto:pan2.li@intel.com>> Upgrade the version of RVV intrinsic from 0.11 to 0.12. PR target/114017 gcc/ChangeLog: * config/riscv/riscv-c.cc (riscv_cpu_cpp_builtins): Upgrade the version to 0.12. gcc/testsuite/ChangeLog: * gcc.target/riscv/predef-__riscv_v_intrinsic.c: Update the version to 0.12. * gcc.target/riscv/rvv/base/pr114017-1.c: New test. Signed-off-by: Pan Li <pan2.li@intel.com<mailto:pan2.li@intel.com>> --- gcc/config/riscv/riscv-c.cc | 2 +- .../riscv/predef-__riscv_v_intrinsic.c | 2 +- .../gcc.target/riscv/rvv/base/pr114017-1.c | 19 +++++++++++++++++++ 3 files changed, 21 insertions(+), 2 deletions(-) create mode 100644 gcc/testsuite/gcc.target/riscv/rvv/base/pr114017-1.c diff --git a/gcc/config/riscv/riscv-c.cc b/gcc/config/riscv/riscv-c.cc index 3ef06dcfd2d..3755ec0b8ef 100644 --- a/gcc/config/riscv/riscv-c.cc +++ b/gcc/config/riscv/riscv-c.cc @@ -139,7 +139,7 @@ riscv_cpu_cpp_builtins (cpp_reader *pfile) { builtin_define ("__riscv_vector"); builtin_define_with_int_value ("__riscv_v_intrinsic", - riscv_ext_version_value (0, 11)); + riscv_ext_version_value (0, 12)); } if (TARGET_XTHEADVECTOR) diff --git a/gcc/testsuite/gcc.target/riscv/predef-__riscv_v_intrinsic.c b/gcc/testsuite/gcc.target/riscv/predef-__riscv_v_intrinsic.c index dbbedf54f87..07f1f159a8f 100644 --- a/gcc/testsuite/gcc.target/riscv/predef-__riscv_v_intrinsic.c +++ b/gcc/testsuite/gcc.target/riscv/predef-__riscv_v_intrinsic.c @@ -3,7 +3,7 @@ int main () { -#if __riscv_v_intrinsic != 11000 +#if __riscv_v_intrinsic != 12000 #error "__riscv_v_intrinsic" #endif diff --git a/gcc/testsuite/gcc.target/riscv/rvv/base/pr114017-1.c b/gcc/testsuite/gcc.target/riscv/rvv/base/pr114017-1.c new file mode 100644 index 00000000000..8eee7c68f71 --- /dev/null +++ b/gcc/testsuite/gcc.target/riscv/rvv/base/pr114017-1.c @@ -0,0 +1,19 @@ +/* { dg-do compile } */ +/* { dg-options "-march=rv64gcv -mabi=lp64d -O3" } */ + +#include "riscv_vector.h" + +vuint8mf2_t +test (vuint16m1_t val, size_t shift, size_t vl) +{ +#if __riscv_v_intrinsic == 11000 + #warning "RVV Intrinsics v0.11" + return __riscv_vnclipu (val, shift, vl); +#endif + +#if __riscv_v_intrinsic == 12000 + #warning "RVV Intrinsics v0.12" /* { dg-warning "RVV Intrinsics v0.12" } */ + return __riscv_vnclipu (val, shift, 0, vl); +#endif +} + -- 2.34.1 ^ permalink raw reply [flat|nested] 8+ messages in thread
end of thread, other threads:[~2024-02-26 6:42 UTC | newest] Thread overview: 8+ messages (download: mbox.gz / follow: Atom feed) -- links below jump to the message on this page -- 2024-02-21 4:27 [PATCH v1] RISC-V: Upgrade RVV intrinsic version to 0.12 pan2.li 2024-02-21 4:31 ` Li, Pan2 2024-02-21 23:34 ` Kito Cheng 2024-02-21 23:41 ` Palmer Dabbelt 2024-02-22 0:02 ` Kito Cheng 2024-02-22 19:47 ` Palmer Dabbelt 2024-02-26 6:42 ` Kito Cheng 2024-02-22 1:22 ` Li, Pan2
This is a public inbox, see mirroring instructions for how to clone and mirror all data and code used for this inbox; as well as URLs for read-only IMAP folder(s) and NNTP newsgroup(s).