-
Notifications
You must be signed in to change notification settings - Fork 709
/
gcc.h
96 lines (80 loc) · 4.24 KB
/
gcc.h
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54
55
56
57
58
59
60
61
62
63
64
65
66
67
68
69
70
71
72
73
74
75
76
77
78
79
80
81
82
83
84
85
86
87
88
89
90
91
92
93
94
95
96
// Copyright (c) Microsoft Corporation. All rights reserved.
// Licensed under the MIT license.
#pragma once
#if SEAL_COMPILER == SEAL_COMPILER_GCC
// We require GCC >= 6
#if (__GNUC__ < 6) || not defined(__cplusplus)
#pragma GCC error "SEAL requires __GNUC__ >= 6"
#endif
// Read in config.h
#include "seal/util/config.h"
#if (__GNUC__ == 6) && defined(SEAL_USE_IF_CONSTEXPR)
#pragma GCC error "g++-6 cannot compile Microsoft SEAL as C++17; set CMake build option `SEAL_USE_CXX17' to OFF"
#endif
#define SEAL_FORCE_INLINE inline __attribute__((always_inline))
#ifdef SEAL_USE_ALIGNED_ALLOC
#include <cstdlib>
#define SEAL_MALLOC(size) \
static_cast<seal_byte *>((((size)&63) == 0) ? ::aligned_alloc(64, (size)) : std::malloc((size)))
#define SEAL_FREE(ptr) std::free(ptr)
#endif
// Are intrinsics enabled?
#ifdef SEAL_USE_INTRIN
#if defined(__aarch64__)
#include <arm_neon.h>
#elif defined(EMSCRIPTEN)
#include <wasm_simd128.h>
#else
#include <x86intrin.h>
#endif
#ifdef SEAL_USE___BUILTIN_CLZLL
#define SEAL_MSB_INDEX_UINT64(result, value) \
{ \
*result = 63UL - static_cast<unsigned long>(__builtin_clzll(value)); \
}
#endif
#ifdef SEAL_USE___INT128
__extension__ typedef __int128 int128_t;
__extension__ typedef unsigned __int128 uint128_t;
#define SEAL_MULTIPLY_UINT64_HW64(operand1, operand2, hw64) \
do \
{ \
*hw64 = static_cast<unsigned long long>( \
((static_cast<uint128_t>(operand1) * static_cast<uint128_t>(operand2)) >> 64)); \
} while (false);
#define SEAL_MULTIPLY_UINT64(operand1, operand2, result128) \
do \
{ \
uint128_t product = static_cast<uint128_t>(operand1) * operand2; \
result128[0] = static_cast<unsigned long long>(product); \
result128[1] = static_cast<unsigned long long>(product >> 64); \
} while (false)
#define SEAL_DIVIDE_UINT128_UINT64(numerator, denominator, result) \
do \
{ \
uint128_t n, q; \
n = (static_cast<uint128_t>(numerator[1]) << 64) | (static_cast<uint128_t>(numerator[0])); \
q = n / denominator; \
n -= q * denominator; \
numerator[0] = static_cast<std::uint64_t>(n); \
numerator[1] = 0; \
result[0] = static_cast<std::uint64_t>(q); \
result[1] = static_cast<std::uint64_t>(q >> 64); \
} while (false)
#endif
// GCC intrinsics for _addcarry_u64 is disabled, for it compiles to slower code than add_uint64_generic.
//#ifdef SEAL_USE__ADDCARRY_U64
//#define SEAL_ADD_CARRY_UINT64(operand1, operand2, carry, result) _addcarry_u64(carry, operand1, operand2, result)
//#endif
#ifdef SEAL_USE__SUBBORROW_U64
#if ((__GNUC__ == 7) && (__GNUC_MINOR__ >= 2)) || (__GNUC__ >= 8)
// The inverted arguments problem was fixed in GCC-7.2
// (https://patchwork.ozlabs.org/patch/784309/)
#define SEAL_SUB_BORROW_UINT64(operand1, operand2, borrow, result) _subborrow_u64(borrow, operand1, operand2, result)
#else
// Warning: Note the inverted order of operand1 and operand2
#define SEAL_SUB_BORROW_UINT64(operand1, operand2, borrow, result) _subborrow_u64(borrow, operand2, operand1, result)
#endif //(__GNUC__ == 7) && (__GNUC_MINOR__ >= 2)
#endif
#endif // SEAL_USE_INTRIN
#endif