Add MSA optimized I422ToYUY2Row, I422ToUYVYRow functions

source/cpu_id.cc

 /*
  *  Copyright 2011 The LibYuv Project Authors. All rights reserved.
  *
  *  Use of this source code is governed by a BSD-style license
  *  that can be found in the LICENSE file in the root of the source
  *  tree. An additional intellectual property rights grant can be found
  *  in the file PATENTS. All contributing project authors may
  *  be found in the AUTHORS file in the root of the source tree.
  */
 
 #include "libyuv/cpu_id.h"
 
 #if defined(_MSC_VER)
 #include <intrin.h>  // For __cpuidex()
 #endif
 #if !defined(__pnacl__) && !defined(__CLR_VER) && \
     !defined(__native_client__) && (defined(_M_IX86) || defined(_M_X64)) && \
     defined(_MSC_FULL_VER) && (_MSC_FULL_VER >= 160040219)
 #include <immintrin.h>  // For _xgetbv()
 #endif
 
 #if !defined(__native_client__)
 #include <stdlib.h>  // For getenv()
 #endif
 
 // For ArmCpuCaps() but unittested on all platforms
 #include <stdio.h>
 #include <string.h>
 
+#if defined(__mips__)
+#include <sys/auxv.h>  // For getauxval
+#endif
+
 #include "libyuv/basic_types.h"  // For CPU_X86
 
 #ifdef __cplusplus
 namespace libyuv {
 extern "C" {
 #endif
 
 // For functions that use the stack and have runtime checks for overflow,
 // use SAFEBUFFERS to avoid additional check.
 #if defined(_MSC_FULL_VER) && (_MSC_FULL_VER >= 160040219) && \
@@ skipping 114 matching lines @@
       if (p && (p[6] == ' ' || p[6] == '\n')) {
         fclose(f);
         return kCpuHasNEON;
       }
     }
   }
   fclose(f);
   return 0;
 }
 
+#if defined(__mips__)
+#define HWCAP_MIPS_R6     (1 << 0)

[fbarchard1, 2016/09/29 17:10:43]

R6 not used?

[manojkumar.bhosale, 2016/09/30 09:00:29]

No, not now as R5, R6 both returns MSA HWCAPS so R6 specific condition check is
not added now.

+#define HWCAP_MIPS_MSA    (1 << 1)
+#endif
+
 LIBYUV_API SAFEBUFFERS
 int MipsCpuCaps(const char* cpuinfo_name, const char ase[]) {
   char cpuinfo_line[512];
   int len = (int)strlen(ase);
+  int hwcap = 0;
   FILE* f = fopen(cpuinfo_name, "r");
   if (!f) {
-    // ase enabled if /proc/cpuinfo is unavailable.
-    if (strcmp(ase, " msa") == 0) {
+    hwcap = getauxval(AT_HWCAP);

[fbarchard1, 2016/09/29 17:10:43]

this function is also unavailable in sandbox?
prefer the cpuid functionality be done in a different CL from YUY2

[manojkumar.bhosale, 2016/09/30 09:00:29]

OK. will split that in new CL

+    if (hwcap & HWCAP_MIPS_MSA) {
       return kCpuHasMSA;
     }
+
+    // dspr2 enabled if /proc/cpuinfo is unavailable.
     if (strcmp(ase, " dspr2") == 0) {
       return kCpuHasDSPR2;
     }
   }
   while (fgets(cpuinfo_line, sizeof(cpuinfo_line) - 1, f)) {
     if (memcmp(cpuinfo_line, "ASEs implemented", 16) == 0) {
       char* p = strstr(cpuinfo_line, ase);
       if (p && (p[len] == ' ' || p[len] == '\n')) {
         fclose(f);
-        if (strcmp(ase, " msa") == 0) {
+        hwcap = getauxval(AT_HWCAP);

[fbarchard1, 2016/09/29 17:10:43]

this is mixed into string parsing code?  
getauxval(AT_HWCAP); will work even if ASEs implemented is not in /proc/cpu_info

[manojkumar.bhosale, 2016/09/30 09:00:29]

Removed cpuid code from this CL

+        if (hwcap & HWCAP_MIPS_MSA) {
           return kCpuHasMSA;
         }
         if (strcmp(ase, " dspr2") == 0) {
           return kCpuHasDSPR2;
         }
       }
     }
   }
   fclose(f);
   return 0;
@@ skipping 135 matching lines @@
 // Note that use of this function is not thread safe.
 LIBYUV_API
 void MaskCpuFlags(int enable_flags) {
   cpu_info_ = InitCpuFlags() & enable_flags;
 }
 
 #ifdef __cplusplus
 }  // extern "C"
 }  // namespace libyuv
 #endif