DPDK patches and discussions
 help / color / mirror / Atom feed
* [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  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

* 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

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

DPDK patches and discussions

This inbox may be cloned and mirrored by anyone:

	git clone --mirror https://inbox.dpdk.org/dev/0 dev/git/0.git

	# If you have public-inbox 1.1+ installed, you may
	# initialize and index your mirror using the following commands:
	public-inbox-init -V2 dev dev/ https://inbox.dpdk.org/dev \
		dev@dpdk.org
	public-inbox-index dev

Example config snippet for mirrors.
Newsgroup available over NNTP:
	nntp://inbox.dpdk.org/inbox.dpdk.dev


AGPL code for this site: git clone https://public-inbox.org/public-inbox.git