From 7cedda499643486b21e19d937f32d4ebe9726b4c Mon Sep 17 00:00:00 2001
From: "Sun, Peng" <peng.sun@amd.com>
Date: Fri, 7 Apr 2017 14:17:41 -0500
Subject: [PATCH] Add more operator overloading for float2 type, contributed by
 Aditya

Change-Id: If1ab7fb24d64bb5304142aed0951c9bd5ad47d20


[ROCm/clr commit: 19987ede228add81501bbe346a133950e5b3edcd]
---
 .../include/hip/hcc_detail/hip_vector_types.h | 38 ++++++++++++++++++-
 1 file changed, 37 insertions(+), 1 deletion(-)

diff --git a/projects/clr/hipamd/include/hip/hcc_detail/hip_vector_types.h b/projects/clr/hipamd/include/hip/hcc_detail/hip_vector_types.h
index 82bd3b2d6f..35c6c23548 100644
--- a/projects/clr/hipamd/include/hip/hcc_detail/hip_vector_types.h
+++ b/projects/clr/hipamd/include/hip/hcc_detail/hip_vector_types.h
@@ -1270,6 +1270,15 @@ __device__ __host__ static inline type operator op (type& val, int) { \
 #define DECLOP_1VAR_COMP(type, op) \
 __device__ __host__ static inline bool operator op (type& lhs, type& rhs) { \
   return lhs.x op rhs.x; \
+} \
+__device__ __host__ static inline bool operator op (const type& lhs, type& rhs) { \
+  return lhs.x op rhs.x; \
+} \
+__device__ __host__ static inline bool operator op (type& lhs, const type& rhs) { \
+  return lhs.x op rhs.x ; \
+} \
+__device__ __host__ static inline bool operator op (const type& lhs, const type& rhs) { \
+  return lhs.x op rhs.x ; \
 }
 
 #define DECLOP_1VAR_1IN_1OUT(type, op) \
@@ -1338,6 +1347,15 @@ __device__ __host__ static inline type operator op (type& val, int) { \
 #define DECLOP_2VAR_COMP(type, op) \
 __device__ __host__ static inline bool operator op (type& lhs, type& rhs) { \
   return (lhs.x op rhs.x) && (lhs.y op rhs.y); \
+} \
+__device__ __host__ static inline bool operator op (const type& lhs, type& rhs) { \
+  return (lhs.x op rhs.x) && (lhs.y op rhs.y); \
+} \
+__device__ __host__ static inline bool operator op (type& lhs, const type& rhs) { \
+  return (lhs.x op rhs.x) && (lhs.y op rhs.y); \
+} \
+__device__ __host__ static inline bool operator op (const type& lhs, const type& rhs) { \
+  return (lhs.x op rhs.x) && (lhs.y op rhs.y); \
 }
 
 #define DECLOP_2VAR_1IN_1OUT(type, op) \
@@ -1415,7 +1433,16 @@ __device__ __host__ static inline type operator op (type& val, int) { \
 #define DECLOP_3VAR_COMP(type, op) \
 __device__ __host__ static inline bool operator op (type& lhs, type& rhs) { \
   return (lhs.x op rhs.x) && (lhs.y op rhs.y) && (lhs.z op rhs.z); \
-}
+} \
+__device__ __host__ static inline bool operator op (const type& lhs, type& rhs) { \
+  return (lhs.x op rhs.x) && (lhs.y op rhs.y) && (lhs.z op rhs.z); \
+} \
+__device__ __host__ static inline bool operator op (type& lhs, const type& rhs) { \
+  return (lhs.x op rhs.x) && (lhs.y op rhs.y) && (lhs.z op rhs.z); \
+} \
+__device__ __host__ static inline bool operator op (const type& lhs, const type& rhs) { \
+  return (lhs.x op rhs.x) && (lhs.y op rhs.y) && (lhs.z op rhs.z); \
+} \
 
 #define DECLOP_3VAR_1IN_1OUT(type, op) \
 __device__ __host__ static inline type operator op(type &rhs) { \
@@ -1500,6 +1527,15 @@ __device__ __host__ static inline type operator op (type& val, int) { \
 #define DECLOP_4VAR_COMP(type, op) \
 __device__ __host__ static inline bool operator op (type& lhs, type& rhs) { \
   return (lhs.x op rhs.x) && (lhs.y op rhs.y) && (lhs.z op rhs.z) && (lhs.w op rhs.w); \
+} \
+__device__ __host__ static inline bool operator op (const type& lhs, type& rhs) { \
+  return (lhs.x op rhs.x) && (lhs.y op rhs.y) && (lhs.z op rhs.z) && (lhs.w op rhs.w); \
+} \
+__device__ __host__ static inline bool operator op (type& lhs, const type& rhs) { \
+  return (lhs.x op rhs.x) && (lhs.y op rhs.y) && (lhs.z op rhs.z) && (lhs.w op rhs.w); \
+} \
+__device__ __host__ static inline bool operator op (const type& lhs, const type& rhs) { \
+  return (lhs.x op rhs.x) && (lhs.y op rhs.y) && (lhs.z op rhs.z) && (lhs.w op rhs.w); \
 }
 
 #define DECLOP_4VAR_1IN_1OUT(type, op) \