Chromium Code Reviews| OLD | NEW |
|---|---|
| 1 // Copyright (c) 2012 The Chromium Authors. All rights reserved. | 1 // Copyright (c) 2012 The Chromium Authors. All rights reserved. |
| 2 // Use of this source code is governed by a BSD-style license that can be | 2 // Use of this source code is governed by a BSD-style license that can be |
| 3 // found in the LICENSE file. | 3 // found in the LICENSE file. |
| 4 | 4 |
| 5 #include "base/cpu.h" | 5 #include "base/cpu.h" |
| 6 | 6 |
| 7 #include <string.h> | 7 #include <string.h> |
| 8 | 8 |
| 9 #include <algorithm> | 9 #include <algorithm> |
| 10 | 10 |
| 11 #include "base/basictypes.h" | 11 #include "base/basictypes.h" |
| 12 #include "base/file_util.h" | |
| 12 #include "build/build_config.h" | 13 #include "build/build_config.h" |
| 13 | 14 |
| 14 #if defined(ARCH_CPU_X86_FAMILY) | 15 #if defined(ARCH_CPU_X86_FAMILY) |
| 15 #if defined(_MSC_VER) | 16 #if defined(_MSC_VER) |
| 16 #include <intrin.h> | 17 #include <intrin.h> |
| 17 #include <immintrin.h> // For _xgetbv() | 18 #include <immintrin.h> // For _xgetbv() |
| 18 #endif | 19 #endif |
| 19 #endif | 20 #endif |
| 20 | 21 |
| 21 namespace base { | 22 namespace base { |
| (...skipping 129 matching lines...) Expand 10 before | Expand all | Expand 10 after Loading... | |
| 151 } | 152 } |
| 152 cpu_brand_.assign(cpu_string, cpu_string_ptr - cpu_string); | 153 cpu_brand_.assign(cpu_string, cpu_string_ptr - cpu_string); |
| 153 } | 154 } |
| 154 | 155 |
| 155 const int parameter_containing_non_stop_time_stamp_counter = 0x80000007; | 156 const int parameter_containing_non_stop_time_stamp_counter = 0x80000007; |
| 156 if (max_parameter >= parameter_containing_non_stop_time_stamp_counter) { | 157 if (max_parameter >= parameter_containing_non_stop_time_stamp_counter) { |
| 157 __cpuid(cpu_info, parameter_containing_non_stop_time_stamp_counter); | 158 __cpuid(cpu_info, parameter_containing_non_stop_time_stamp_counter); |
| 158 has_non_stop_time_stamp_counter_ = (cpu_info[3] & (1 << 8)) != 0; | 159 has_non_stop_time_stamp_counter_ = (cpu_info[3] & (1 << 8)) != 0; |
| 159 } | 160 } |
| 160 #elif defined(ARCH_CPU_ARM_FAMILY) | 161 #elif defined(ARCH_CPU_ARM_FAMILY) |
| 161 // TODO(piman): Expand this. ARM has a CPUID register, but it's not available | 162 #if defined(USE_AURA) || defined(OS_ANDROID) |
| 162 // in user mode. /proc/cpuinfo has some information, but it's non standard, | 163 const char kProcessorPrefix[] = "Processor"; |
| 163 // platform-specific, and not accessible from the sandbox. | 164 std::string contents; |
| 164 // For some purposes, this first approximation is enough. | 165 ReadFileToString(FilePath("/proc/cpuinfo"), &contents); |
|
Mark Mentovai
2014/03/06 14:41:55
How is this file formatted on ARM?
It’s probably
rptr
2014/03/08 06:26:59
This is how /proc/cpuinfo looks in Samsung Galaxy
| |
| 165 // crbug.com/313454 | 166 DCHECK(!contents.empty()); |
| 166 cpu_brand_.assign("ARM"); | 167 if (!contents.empty()) { |
| 168 std::istringstream iss(contents); | |
| 169 std::string line; | |
| 170 while (std::getline(iss, line)) { | |
| 171 if (line.compare(0, strlen(kProcessorPrefix), kProcessorPrefix) == 0) { | |
| 172 size_t pos = line.find(": "); | |
|
Mark Mentovai
2014/03/07 15:19:18
What if ": " was not found?
| |
| 173 cpu_brand_.assign(line.substr(pos + 2)); | |
|
vivekg
2014/03/07 11:59:52
You probably need to break here to avoid processin
| |
| 174 } | |
| 175 } | |
| 176 } | |
| 177 #endif | |
| 167 #endif | 178 #endif |
| 168 } | 179 } |
| 169 | 180 |
| 170 CPU::IntelMicroArchitecture CPU::GetIntelMicroArchitecture() const { | 181 CPU::IntelMicroArchitecture CPU::GetIntelMicroArchitecture() const { |
| 171 if (has_avx()) return AVX; | 182 if (has_avx()) return AVX; |
| 172 if (has_sse42()) return SSE42; | 183 if (has_sse42()) return SSE42; |
| 173 if (has_sse41()) return SSE41; | 184 if (has_sse41()) return SSE41; |
| 174 if (has_ssse3()) return SSSE3; | 185 if (has_ssse3()) return SSSE3; |
| 175 if (has_sse3()) return SSE3; | 186 if (has_sse3()) return SSE3; |
| 176 if (has_sse2()) return SSE2; | 187 if (has_sse2()) return SSE2; |
| 177 if (has_sse()) return SSE; | 188 if (has_sse()) return SSE; |
| 178 return PENTIUM; | 189 return PENTIUM; |
| 179 } | 190 } |
| 180 | 191 |
| 181 } // namespace base | 192 } // namespace base |
| OLD | NEW |