* [dpdk-dev] [PATCH] common/rte_memcpy: Fix x86intrin.h missed
@ 2015-03-13 7:02 Michael Qiu
2015-03-13 7:08 ` Wang, Zhihong
` (2 more replies)
0 siblings, 3 replies; 9+ messages in thread
From: Michael Qiu @ 2015-03-13 7:02 UTC (permalink / raw)
To: dev
rte_memcpy.h(46): catastrophic error: cannot open source file "x86intrin.h"
For icc and old gcc, this header is not included.
Signed-off-by: Michael Qiu <michael.qiu@intel.com>
---
lib/librte_eal/common/include/arch/x86/rte_memcpy.h | 20 ++++++++++++++++++++
1 file changed, 20 insertions(+)
diff --git a/lib/librte_eal/common/include/arch/x86/rte_memcpy.h b/lib/librte_eal/common/include/arch/x86/rte_memcpy.h
index ac72069..bd10d36 100644
--- a/lib/librte_eal/common/include/arch/x86/rte_memcpy.h
+++ b/lib/librte_eal/common/include/arch/x86/rte_memcpy.h
@@ -43,7 +43,27 @@
#include <stdio.h>
#include <stdint.h>
#include <string.h>
+#if (defined(__ICC) || (__GNUC__ == 4 && __GNUC_MINOR__ < 4))
+
+#ifdef __SSE__
+#include <xmmintrin.h>
+#endif
+
+#ifdef __SSE2__
+#include <emmintrin.h>
+#endif
+
+#if defined(__SSE4_2__) || defined(__SSE4_1__)
+#include <smmintrin.h>
+#endif
+
+#if defined(__AVX__)
+#include <immintrin.h>
+#endif
+
+#else
#include <x86intrin.h>
+#endif
#ifdef __cplusplus
extern "C" {
--
1.9.3
^ permalink raw reply [flat|nested] 9+ messages in thread* Re: [dpdk-dev] [PATCH] common/rte_memcpy: Fix x86intrin.h missed
2015-03-13 7:02 [dpdk-dev] [PATCH] common/rte_memcpy: Fix x86intrin.h missed Michael Qiu
@ 2015-03-13 7:08 ` Wang, Zhihong
2015-03-13 9:44 ` Ananyev, Konstantin
2015-03-13 14:25 ` Mcnamara, John
2 siblings, 0 replies; 9+ messages in thread
From: Wang, Zhihong @ 2015-03-13 7:08 UTC (permalink / raw)
To: Qiu, Michael, dev
> -----Original Message-----
> From: Qiu, Michael
> Sent: Friday, March 13, 2015 3:03 PM
> To: dev@dpdk.org
> Cc: Wang, Zhihong; Qiu, Michael
> Subject: [PATCH] common/rte_memcpy: Fix x86intrin.h missed
>
> rte_memcpy.h(46): catastrophic error: cannot open source file "x86intrin.h"
>
> For icc and old gcc, this header is not included.
>
> Signed-off-by: Michael Qiu <michael.qiu@intel.com>
> ---
> lib/librte_eal/common/include/arch/x86/rte_memcpy.h | 20
> ++++++++++++++++++++
> 1 file changed, 20 insertions(+)
>
> diff --git a/lib/librte_eal/common/include/arch/x86/rte_memcpy.h
> b/lib/librte_eal/common/include/arch/x86/rte_memcpy.h
> index ac72069..bd10d36 100644
> --- a/lib/librte_eal/common/include/arch/x86/rte_memcpy.h
> +++ b/lib/librte_eal/common/include/arch/x86/rte_memcpy.h
> @@ -43,7 +43,27 @@
> #include <stdio.h>
> #include <stdint.h>
> #include <string.h>
> +#if (defined(__ICC) || (__GNUC__ == 4 && __GNUC_MINOR__ < 4))
> +
> +#ifdef __SSE__
> +#include <xmmintrin.h>
> +#endif
> +
> +#ifdef __SSE2__
> +#include <emmintrin.h>
> +#endif
> +
> +#if defined(__SSE4_2__) || defined(__SSE4_1__) #include <smmintrin.h>
> +#endif
> +
> +#if defined(__AVX__)
> +#include <immintrin.h>
> +#endif
> +
> +#else
> #include <x86intrin.h>
> +#endif
>
> #ifdef __cplusplus
> extern "C" {
> --
> 1.9.3
Acked-by: Wang, Zhihong <zhihong.wang@intel.com>
^ permalink raw reply [flat|nested] 9+ messages in thread* Re: [dpdk-dev] [PATCH] common/rte_memcpy: Fix x86intrin.h missed
2015-03-13 7:02 [dpdk-dev] [PATCH] common/rte_memcpy: Fix x86intrin.h missed Michael Qiu
2015-03-13 7:08 ` Wang, Zhihong
@ 2015-03-13 9:44 ` Ananyev, Konstantin
2015-03-16 16:05 ` Thomas Monjalon
2015-03-18 4:48 ` Qiu, Michael
2015-03-13 14:25 ` Mcnamara, John
2 siblings, 2 replies; 9+ messages in thread
From: Ananyev, Konstantin @ 2015-03-13 9:44 UTC (permalink / raw)
To: Qiu, Michael, dev
Hi Michael,
> -----Original Message-----
> From: dev [mailto:dev-bounces@dpdk.org] On Behalf Of Michael Qiu
> Sent: Friday, March 13, 2015 7:03 AM
> To: dev@dpdk.org
> Subject: [dpdk-dev] [PATCH] common/rte_memcpy: Fix x86intrin.h missed
>
> rte_memcpy.h(46): catastrophic error: cannot open source file "x86intrin.h"
>
> For icc and old gcc, this header is not included.
>
> Signed-off-by: Michael Qiu <michael.qiu@intel.com>
> ---
> lib/librte_eal/common/include/arch/x86/rte_memcpy.h | 20 ++++++++++++++++++++
> 1 file changed, 20 insertions(+)
>
> diff --git a/lib/librte_eal/common/include/arch/x86/rte_memcpy.h b/lib/librte_eal/common/include/arch/x86/rte_memcpy.h
> index ac72069..bd10d36 100644
> --- a/lib/librte_eal/common/include/arch/x86/rte_memcpy.h
> +++ b/lib/librte_eal/common/include/arch/x86/rte_memcpy.h
> @@ -43,7 +43,27 @@
> #include <stdio.h>
> #include <stdint.h>
> #include <string.h>
> +#if (defined(__ICC) || (__GNUC__ == 4 && __GNUC_MINOR__ < 4))
> +
> +#ifdef __SSE__
> +#include <xmmintrin.h>
> +#endif
> +
> +#ifdef __SSE2__
> +#include <emmintrin.h>
> +#endif
> +
> +#if defined(__SSE4_2__) || defined(__SSE4_1__)
> +#include <smmintrin.h>
> +#endif
> +
> +#if defined(__AVX__)
> +#include <immintrin.h>
> +#endif
> +
> +#else
> #include <x86intrin.h>
> +#endif
>
> #ifdef __cplusplus
> extern "C" {
> --
> 1.9.3
Wonder why to spread this thing over?
Why not just #include <rte_common_vec.h>?
Konstantin
^ permalink raw reply [flat|nested] 9+ messages in thread* Re: [dpdk-dev] [PATCH] common/rte_memcpy: Fix x86intrin.h missed
2015-03-13 9:44 ` Ananyev, Konstantin
@ 2015-03-16 16:05 ` Thomas Monjalon
2015-03-16 17:39 ` Ananyev, Konstantin
2015-03-18 4:48 ` Qiu, Michael
1 sibling, 1 reply; 9+ messages in thread
From: Thomas Monjalon @ 2015-03-16 16:05 UTC (permalink / raw)
To: Ananyev, Konstantin; +Cc: dev
2015-03-13 09:44, Ananyev, Konstantin:
> From: dev [mailto:dev-bounces@dpdk.org] On Behalf Of Michael Qiu
> >
> > rte_memcpy.h(46): catastrophic error: cannot open source file "x86intrin.h"
> >
> > For icc and old gcc, this header is not included.
> >
> > Signed-off-by: Michael Qiu <michael.qiu@intel.com>
> > ---
> > lib/librte_eal/common/include/arch/x86/rte_memcpy.h | 20 ++++++++++++++++++++
> > 1 file changed, 20 insertions(+)
> >
> > diff --git a/lib/librte_eal/common/include/arch/x86/rte_memcpy.h b/lib/librte_eal/common/include/arch/x86/rte_memcpy.h
> > index ac72069..bd10d36 100644
> > --- a/lib/librte_eal/common/include/arch/x86/rte_memcpy.h
> > +++ b/lib/librte_eal/common/include/arch/x86/rte_memcpy.h
> > @@ -43,7 +43,27 @@
> > #include <stdio.h>
> > #include <stdint.h>
> > #include <string.h>
> > +#if (defined(__ICC) || (__GNUC__ == 4 && __GNUC_MINOR__ < 4))
> > +
> > +#ifdef __SSE__
> > +#include <xmmintrin.h>
> > +#endif
> > +
> > +#ifdef __SSE2__
> > +#include <emmintrin.h>
> > +#endif
> > +
> > +#if defined(__SSE4_2__) || defined(__SSE4_1__)
> > +#include <smmintrin.h>
> > +#endif
> > +
> > +#if defined(__AVX__)
> > +#include <immintrin.h>
> > +#endif
> > +
> > +#else
> > #include <x86intrin.h>
> > +#endif
> >
> > #ifdef __cplusplus
> > extern "C" {
> > --
> > 1.9.3
>
> Wonder why to spread this thing over?
> Why not just #include <rte_common_vec.h>?
I agree to use rte_common_vec.h.
I pushed this approach to check every tested compilers:
http://dpdk.org/browse/dpdk/commit/?id=9a01c31b94e54384
I think that rte_common_vec.h should be moved into
lib/librte_eal/common/include/arch/x86/rte_vec.h as it's x86-specific.
^ permalink raw reply [flat|nested] 9+ messages in thread* Re: [dpdk-dev] [PATCH] common/rte_memcpy: Fix x86intrin.h missed
2015-03-16 16:05 ` Thomas Monjalon
@ 2015-03-16 17:39 ` Ananyev, Konstantin
2015-03-17 8:46 ` Thomas Monjalon
0 siblings, 1 reply; 9+ messages in thread
From: Ananyev, Konstantin @ 2015-03-16 17:39 UTC (permalink / raw)
To: Thomas Monjalon; +Cc: dev
Hi Thomas,
> -----Original Message-----
> From: Thomas Monjalon [mailto:thomas.monjalon@6wind.com]
> Sent: Monday, March 16, 2015 4:05 PM
> To: Ananyev, Konstantin
> Cc: dev@dpdk.org; Qiu, Michael
> Subject: Re: [dpdk-dev] [PATCH] common/rte_memcpy: Fix x86intrin.h missed
>
> 2015-03-13 09:44, Ananyev, Konstantin:
> > From: dev [mailto:dev-bounces@dpdk.org] On Behalf Of Michael Qiu
> > >
> > > rte_memcpy.h(46): catastrophic error: cannot open source file "x86intrin.h"
> > >
> > > For icc and old gcc, this header is not included.
> > >
> > > Signed-off-by: Michael Qiu <michael.qiu@intel.com>
> > > ---
> > > lib/librte_eal/common/include/arch/x86/rte_memcpy.h | 20 ++++++++++++++++++++
> > > 1 file changed, 20 insertions(+)
> > >
> > > diff --git a/lib/librte_eal/common/include/arch/x86/rte_memcpy.h b/lib/librte_eal/common/include/arch/x86/rte_memcpy.h
> > > index ac72069..bd10d36 100644
> > > --- a/lib/librte_eal/common/include/arch/x86/rte_memcpy.h
> > > +++ b/lib/librte_eal/common/include/arch/x86/rte_memcpy.h
> > > @@ -43,7 +43,27 @@
> > > #include <stdio.h>
> > > #include <stdint.h>
> > > #include <string.h>
> > > +#if (defined(__ICC) || (__GNUC__ == 4 && __GNUC_MINOR__ < 4))
> > > +
> > > +#ifdef __SSE__
> > > +#include <xmmintrin.h>
> > > +#endif
> > > +
> > > +#ifdef __SSE2__
> > > +#include <emmintrin.h>
> > > +#endif
> > > +
> > > +#if defined(__SSE4_2__) || defined(__SSE4_1__)
> > > +#include <smmintrin.h>
> > > +#endif
> > > +
> > > +#if defined(__AVX__)
> > > +#include <immintrin.h>
> > > +#endif
> > > +
> > > +#else
> > > #include <x86intrin.h>
> > > +#endif
> > >
> > > #ifdef __cplusplus
> > > extern "C" {
> > > --
> > > 1.9.3
> >
> > Wonder why to spread this thing over?
> > Why not just #include <rte_common_vec.h>?
>
> I agree to use rte_common_vec.h.
> I pushed this approach to check every tested compilers:
> http://dpdk.org/browse/dpdk/commit/?id=9a01c31b94e54384
>
> I think that rte_common_vec.h should be moved into
> lib/librte_eal/common/include/arch/x86/rte_vec.h as it's x86-specific.
Seems like a good thing to do.
Do you want me to submit a patch for 2.0 for that?
Konstantin
^ permalink raw reply [flat|nested] 9+ messages in thread* Re: [dpdk-dev] [PATCH] common/rte_memcpy: Fix x86intrin.h missed
2015-03-16 17:39 ` Ananyev, Konstantin
@ 2015-03-17 8:46 ` Thomas Monjalon
0 siblings, 0 replies; 9+ messages in thread
From: Thomas Monjalon @ 2015-03-17 8:46 UTC (permalink / raw)
To: Ananyev, Konstantin; +Cc: dev
2015-03-16 17:39, Ananyev, Konstantin:
> From: Thomas Monjalon [mailto:thomas.monjalon@6wind.com]
> > I think that rte_common_vec.h should be moved into
> > lib/librte_eal/common/include/arch/x86/rte_vec.h as it's x86-specific.
>
> Seems like a good thing to do.
> Do you want me to submit a patch for 2.0 for that?
It would be nice yes.
Thanks
^ permalink raw reply [flat|nested] 9+ messages in thread
* Re: [dpdk-dev] [PATCH] common/rte_memcpy: Fix x86intrin.h missed
2015-03-13 9:44 ` Ananyev, Konstantin
2015-03-16 16:05 ` Thomas Monjalon
@ 2015-03-18 4:48 ` Qiu, Michael
1 sibling, 0 replies; 9+ messages in thread
From: Qiu, Michael @ 2015-03-18 4:48 UTC (permalink / raw)
To: Ananyev, Konstantin, dev
On 3/13/2015 5:45 PM, Ananyev, Konstantin wrote:
> Hi Michael,
>
>> -----Original Message-----
>> From: dev [mailto:dev-bounces@dpdk.org] On Behalf Of Michael Qiu
>> Sent: Friday, March 13, 2015 7:03 AM
>> To: dev@dpdk.org
>> Subject: [dpdk-dev] [PATCH] common/rte_memcpy: Fix x86intrin.h missed
>>
>> rte_memcpy.h(46): catastrophic error: cannot open source file "x86intrin.h"
>>
>> For icc and old gcc, this header is not included.
>>
>> Signed-off-by: Michael Qiu <michael.qiu@intel.com>
>> ---
>> lib/librte_eal/common/include/arch/x86/rte_memcpy.h | 20 ++++++++++++++++++++
>> 1 file changed, 20 insertions(+)
>>
>> diff --git a/lib/librte_eal/common/include/arch/x86/rte_memcpy.h b/lib/librte_eal/common/include/arch/x86/rte_memcpy.h
>> index ac72069..bd10d36 100644
>> --- a/lib/librte_eal/common/include/arch/x86/rte_memcpy.h
>> +++ b/lib/librte_eal/common/include/arch/x86/rte_memcpy.h
>> @@ -43,7 +43,27 @@
>> #include <stdio.h>
>> #include <stdint.h>
>> #include <string.h>
>> +#if (defined(__ICC) || (__GNUC__ == 4 && __GNUC_MINOR__ < 4))
>> +
>> +#ifdef __SSE__
>> +#include <xmmintrin.h>
>> +#endif
>> +
>> +#ifdef __SSE2__
>> +#include <emmintrin.h>
>> +#endif
>> +
>> +#if defined(__SSE4_2__) || defined(__SSE4_1__)
>> +#include <smmintrin.h>
>> +#endif
>> +
>> +#if defined(__AVX__)
>> +#include <immintrin.h>
>> +#endif
>> +
>> +#else
>> #include <x86intrin.h>
>> +#endif
>>
>> #ifdef __cplusplus
>> extern "C" {
>> --
>> 1.9.3
> Wonder why to spread this thing over?
> Why not just #include <rte_common_vec.h>?
Yes, I will send other patch to fix this,
Thanks,
Michael
> Konstantin
>
>
>
>
^ permalink raw reply [flat|nested] 9+ messages in thread
* Re: [dpdk-dev] [PATCH] common/rte_memcpy: Fix x86intrin.h missed
2015-03-13 7:02 [dpdk-dev] [PATCH] common/rte_memcpy: Fix x86intrin.h missed Michael Qiu
2015-03-13 7:08 ` Wang, Zhihong
2015-03-13 9:44 ` Ananyev, Konstantin
@ 2015-03-13 14:25 ` Mcnamara, John
2015-03-16 4:44 ` Qiu, Michael
2 siblings, 1 reply; 9+ messages in thread
From: Mcnamara, John @ 2015-03-13 14:25 UTC (permalink / raw)
To: Qiu, Michael, dev
> -----Original Message-----
> From: dev [mailto:dev-bounces@dpdk.org] On Behalf Of Michael Qiu
> Sent: Friday, March 13, 2015 7:03 AM
> To: dev@dpdk.org
> Subject: [dpdk-dev] [PATCH] common/rte_memcpy: Fix x86intrin.h missed
>
> rte_memcpy.h(46): catastrophic error: cannot open source file
> "x86intrin.h"
Hi Michael,
How are you generating that error?
John
^ permalink raw reply [flat|nested] 9+ messages in thread
* Re: [dpdk-dev] [PATCH] common/rte_memcpy: Fix x86intrin.h missed
2015-03-13 14:25 ` Mcnamara, John
@ 2015-03-16 4:44 ` Qiu, Michael
0 siblings, 0 replies; 9+ messages in thread
From: Qiu, Michael @ 2015-03-16 4:44 UTC (permalink / raw)
To: Mcnamara, John, dev
On 3/13/2015 10:25 PM, Mcnamara, John wrote:
>> -----Original Message-----
>> From: dev [mailto:dev-bounces@dpdk.org] On Behalf Of Michael Qiu
>> Sent: Friday, March 13, 2015 7:03 AM
>> To: dev@dpdk.org
>> Subject: [dpdk-dev] [PATCH] common/rte_memcpy: Fix x86intrin.h missed
>>
>> rte_memcpy.h(46): catastrophic error: cannot open source file
>> "x86intrin.h"
>
> Hi Michael,
>
> How are you generating that error?
For ICC compile, it will report this error, also in suse11sp2 i686
platform, also have this issue as internal report.
Thanks,
Michael
> John
>
^ permalink raw reply [flat|nested] 9+ messages in thread
end of thread, other threads:[~2015-03-18 4:50 UTC | newest]
Thread overview: 9+ messages (download: mbox.gz / follow: Atom feed)
-- links below jump to the message on this page --
2015-03-13 7:02 [dpdk-dev] [PATCH] common/rte_memcpy: Fix x86intrin.h missed Michael Qiu
2015-03-13 7:08 ` Wang, Zhihong
2015-03-13 9:44 ` Ananyev, Konstantin
2015-03-16 16:05 ` Thomas Monjalon
2015-03-16 17:39 ` Ananyev, Konstantin
2015-03-17 8:46 ` Thomas Monjalon
2015-03-18 4:48 ` Qiu, Michael
2015-03-13 14:25 ` Mcnamara, John
2015-03-16 4:44 ` Qiu, Michael
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 NNTP newsgroup(s).