blob: 92de68fb6b40b213882fc6ae2fad762c2f3d5f73 [file] [log] [blame]
Marat Dukhan9a88efe2019-12-10 15:54:24 -08001// Auto-generated file. Do not edit!
2// Template: src/f32-vbinary/vop-avx.c.in
3// Generator: tools/xngen
4//
5// Copyright 2019 Google LLC
6//
7// This source code is licensed under the BSD-style license found in the
8// LICENSE file in the root directory of this source tree.
9
10#include <assert.h>
11
12#include <immintrin.h>
13
14#include <xnnpack/common.h>
15#include <xnnpack/vbinary.h>
16
17
18static const int32_t mask_table[14] = {-1, -1, -1, -1, -1, -1, -1, 0, 0, 0, 0, 0, 0, 0};
19
20void xnn_f32_vmax_ukernel__avx_x8(
21 size_t n,
22 const float* a,
23 const float* b,
24 float* y,
Marat Dukhanf196d012020-04-15 11:50:03 -070025 const union xnn_f32_default_params params[restrict XNN_MIN_ELEMENTS(1)])
Marat Dukhan9a88efe2019-12-10 15:54:24 -080026{
27 assert(n != 0);
28 assert(n % sizeof(float) == 0);
29
Marat Dukhan9a88efe2019-12-10 15:54:24 -080030
31 for (; n >= 8 * sizeof(float); n -= 8 * sizeof(float)) {
32 const __m256 va01234567 = _mm256_loadu_ps(a);
33 a += 8;
34
35 const __m256 vb01234567 = _mm256_loadu_ps(b);
36 b += 8;
37
38 __m256 vy01234567 = _mm256_max_ps(va01234567, vb01234567);
39
Marat Dukhan9a88efe2019-12-10 15:54:24 -080040
41 _mm256_storeu_ps(y, vy01234567);
42 y += 8;
43 }
44 for (; n >= 8 * sizeof(float); n -= 8 * sizeof(float)) {
45 const __m256 va = _mm256_loadu_ps(a);
46 a += 8;
47
48 const __m256 vb = _mm256_loadu_ps(b);
49 b += 8;
50
51 __m256 vy = _mm256_max_ps(va, vb);
Marat Dukhan9a88efe2019-12-10 15:54:24 -080052 _mm256_storeu_ps(y, vy);
53 y += 8;
54 }
55 if XNN_UNLIKELY(n != 0) {
56 assert(n >= 1 * sizeof(float));
57 assert(n <= 7 * sizeof(float));
58 __m256i vmask = _mm256_loadu_si256((const __m256i*) ((uintptr_t) &mask_table[7] - n));
59
60 const __m256 va = _mm256_maskload_ps(a, vmask);
61 const __m256 vb = _mm256_maskload_ps(b, vmask);
62
63 __m256 vy = _mm256_max_ps(va, vb);
Marat Dukhand16d0f02020-02-05 21:33:05 -080064
65 // _mm256_maskstore_ps(y, vmask, vy) could be used here, but triggers msan failures (probably an msan bug).
66 __m128 vy_lo = _mm256_castps256_ps128(vy);
67 if (n & (4 * sizeof(float))) {
68 _mm_storeu_ps(y, vy_lo);
69 vy_lo = _mm256_extractf128_ps(vy, 1);
70 y += 4;
71 }
72 if (n & (2 * sizeof(float))) {
73 _mm_storel_pi((__m64*) y, vy_lo);
74 vy_lo = _mm_movehl_ps(vy_lo, vy_lo);
75 y += 2;
76 }
77 if (n & (1 * sizeof(float))) {
78 _mm_store_ss(y, vy_lo);
79 }
Marat Dukhan9a88efe2019-12-10 15:54:24 -080080 }
81}