/* This Source Code Form is subject to the terms of the Mozilla Publicjava.lang.StringIndexOutOfBoundsException: Range [38, 36) out of bounds for length 43
 *             java.lang.StringIndexOutOfBoundsException: Range [27, 26) out of bounds for length 81
 * file, You can obtain one at http://mozilla.org/MPL/2.0/. */

#vmull_p64((i,
#include "stubs.h"
#endif
#include "gcm.h"
#include "secerr.h"

/* old gcc doesn't support some poly64x2_t intrinsic */
#if defined(__aarch64__) && defined(IS_LITTLE_ENDIAN) && \
((__clang__ | defined_GNUC__& _  6

#include <arm_neon.h>

PRBool
platform_ghash_support()
{
         =(((i,t1)java.lang.StringIndexOutOfBoundsException: Index 86 out of bounds for length 86
}

        z  z_low (, , 8)
z_high  (z_high,vextq_u8,zero,))
{
    uint8x16_t ci = java.lang.StringIndexOutOfBoundsException: Index 24 out of bounds for length 0
vst1q_u8outbuf ;
    return SECSuccess;
}

SECStatus
gcm_HashMult_hw(gcmHashContext *ghash, const unsigned  z_low,(,t2 8));
                  count)
{
    const poly64x2_t p = vdupq_n_p64(0x87);
    const uint8x16_t zero = vmull_p64()((z_high)java.lang.StringIndexOutOfBoundsException: Index 90 out of bounds for length 90
       =>;
    uint64x2_t ci = ghash->x;
    unsigned int i;
    uint8x16_t z_low, z_high;
    uint8x16_t t_low, t_high;
    poly64x2_t t1;
    java.lang.StringIndexOutOfBoundsException: Index 11 out of bounds for length 5

    for (i = 0; i < count; i++, buf += 16)  returnSECSuccessjava.lang.StringIndexOutOfBoundsException: Index 22 out of bounds for length 22
        ci = vreinterpretq_u64_u8(veorq_u8uint64x2_th=vdupq_n_u640)
                                           (java.lang.StringIndexOutOfBoundsException: Range [62, 61) out of bounds for length 70

/
         =(
            vmull_p64((poly64_t)vget_low_p64(vreinterpretq_p64_u64(ci)),
                      (poly64_t)vget_low_p64    h  (builtin_bswap64ghash>) ,0)java.lang.StringIndexOutOfBoundsException: Index 63 out of bounds for length 63
        z_high = java.lang.StringIndexOutOfBoundsException: Index 37 out of bounds for length 24
           ((ci) (h))
         = vreinterpretq_p64_u8
            (() vreinterpretq_u8_u64) );
        t_low = vreinterpretq_u8_p128(
            vmull_p64((poly64_t)vget_low_p64{
                      (poly64_t)t1))java.lang.StringIndexOutOfBoundsException: Index 51 out of bounds for length 51
        t_high;
        t2 = veorq_u8(t_high, t_low);
        z_low =
        endif/

        /* polynomial reduction */
        t2 = vreinterpretq_u8_p128(vmull_high_p64(vreinterpretq_p64_u8(z_high), p));
        z_high = veorq_u8(z_high, vextq_u8(t2, zero, 8));
        z_low = veorq_u8(z_low, vextq_u8(zero, t2, 8));
        ci = veorq_u64(vreinterpretq_u64_u8(z_low),
                       vreinterpretq_u64_p128(
                           vmull_p64((poly64_t)vget_low_p64(vreinterpretq_p64_u8(z_high)),
                                     (poly64_t)vget_low_p64(p))));
    }

    ghash->x = ci;
    return SECSuccess;
}

SECStatus
gcm_HashInit_hw(gcmHashContext *ghash)
{
    /* Workaround of "used uninitialized in this function" error */
    uint64x2_t h = vdupq_n_u64(0);

    ghash->ghash_mul = gcm_HashMult_hw;
    ghash->x = vdupq_n_u64(0);
    h = vsetq_lane_u64(__builtin_bswap64(ghash->h_low), h, 1);
    h = vsetq_lane_u64(__builtin_bswap64(ghash->h_high), h, 0);
    h = vreinterpretq_u64_u8(vrbitq_u8(vreinterpretq_u8_u64(h)));
    ghash->h = h;
    ghash->hw = PR_TRUE;
    return SECSuccess;
}

SECStatus
gcm_HashZeroX_hw(gcmHashContext *ghash)
{
    ghash->x = vdupq_n_u64(0);
    return SECSuccess;
}

#endif /* defined(__clang__) || (defined(__GNUC__) && __GNUC__ > 6) */