Commit Graph

85 Commits

Author SHA1 Message Date
Jeffrey Walton
c601213ce1
Sync CRYPTOPP_{BIG|LITTLE}_ENDIAN with Autotools
Autotools sets up its config.h file with the '#define XXX 0' or '#define XXX 1' pattern. This check-in makes the sources Autotools aware. We need to verify CMake does the same
2018-10-28 04:24:22 -04:00
Jeffrey Walton
c24f17b7a2
Fix compiler crash in Visual Studio .Net (2002 and 2003) 2018-08-20 08:24:12 -04:00
Jeffrey Walton
01779726db
Use consistent suffix for SSE2 ASM 2018-08-20 07:16:59 -04:00
Jeffrey Walton
4282f94712
Disable X32 inline assembly (GH #686, PR #704)
Also use CRYPTOPP_DISABLE_XXX_ASM consistently. The pattern is needed for Clang which still can't compile Intel assembly language. Also see http://llvm.org/bugs/show_bug.cgi?id=24232.
2018-08-18 04:44:53 -04:00
Jeffrey Walton
3ed38e42f6
Add POWER8 GCM mode (GH #698)
GCM_SetKeyWithoutResync_VMULL, GCM_Multiply_VMULL and GCM_Reduce_VMULL work as expected on Linux (ppc64-le) and AIX (ppc64-be). We are still working on GCM_AuthenticateBlocks_VMULL.
2018-08-09 08:09:13 -04:00
Jeffrey Walton
e1433536bc
Use CRYPTOPP_DISABLE_INTEL_ASM for Clang in GCM
Clang 6.0 is still broke. It cannot compile a simple "neg %rcx" using Intel syntax
2018-07-16 19:40:56 -04:00
Jeffrey Walton
bd9ca55c44
Cleanup gcm.cpp after Commit 9d954efcde 2018-07-16 09:48:35 -04:00
Jeffrey Walton
c3107d2519
Fix "impossible constraint in \\asm\" on i686
gcm.cpp:89:50: error: impossible constraint in \\asm\
          : "=xm" (a[0]) : "xm"(b[0]), "xm"(c[0]));
2017-11-24 05:49:56 -05:00
Jeffrey Walton
dbd79a1e49
Fix GCC inline asm register constraint for SSE register
Also see https://gcc.gnu.org/onlinedocs/gcc/Machine-Constraints.html
2017-11-17 01:01:12 -05:00
Jeffrey Walton
7f7131dc55
Fix GCM_Xor16_SSE2 for 32-bit MSVC compiles 2017-11-16 23:07:30 -05:00
Jeffrey Walton
8b52a03d08
Fix SunCC 12.2 compiler crash with GCM_Xor16_SSE2
SunCC 12.3 through 12.5 still cannot handle CLMUL, though. It would be nice if Sun fixed the regression.
2017-11-16 02:38:53 -05:00
Jeffrey Walton
6f83a4fb7d
Switch to intrinsic operation instead of casts for GCM SSE2 XOR's 2017-11-15 23:05:30 -05:00
Jeffrey Walton
69c8a4f9c6
Prefix IS_LITTLE_ENDIAN and IS_BIG_ENDIAN with CRYPTOPP 2017-11-10 14:15:30 -05:00
Jeffrey Walton
7c667bc71e
Fix SunCC crash when compiling GCM 2017-08-27 06:16:04 -04:00
Jeffrey Walton
5c6a32ba0f
Support Base Implementation + SIMD implementation on Solaris (PR #461) 2017-08-24 19:17:21 -04:00
Jeffrey Walton
7851a0d510 Remove BOOL macro value (GH #462)
Currently the CRYPTOPP_BOOL_XXX macros set the macro value to 0 or 1. If we remove setting the 0 value (the #else part of the expression), then the self tests speed up by about 0.3 seconds. I can't explain it, but I have observed it repeatedly.
This check-in prepares for the removal in Upstream master
2017-08-20 21:25:29 -04:00
Jeffrey Walton
a1b3102eab
Update comments 2017-08-19 01:35:36 -04:00
Jeffrey Walton
a9534a7cf3
Use CRYPTOPP_SSE2_INTRIN_AVAILABLE for consistent naming 2017-08-18 02:11:41 -04:00
Jeffrey Walton
e2c377effd Split source files to support Base Implementation + SIMD implementation (GH #461)
Split source files to support Base Implementation + SIMD implementation
2017-08-17 12:33:43 -04:00
Jeffrey Walton
74d21068a1
Fix more Clang problems
I wish this god damn compiler would stop pretending to be other compilers when it can't consume the same program. Even the GCC devs have told the LLVM devs to stop ding that crap
2017-08-17 10:45:43 -04:00
Jeffrey Walton
df280a509a
Disable Carryless Multiplies for Clang
Clang causes too many problems. Early versions of the compiler simply crashes. Later versions of the compiler still have trouble with Intel ASM and still produce incorrect results on occassion. Additionally, we have to special case the integrated assemvler. Its making a mess of the code and causing self test failures
2017-08-16 22:10:53 -04:00
Jeffrey Walton
863bf9133c
Cleanup casts due to Clang 2017-08-13 06:32:09 -04:00
Jeffrey Walton
f02bf91ee5
Revert 95ee8975b4 and 7d21cdd54e (Issue 408)
This broke some OS X builds. We need more testing. Ugh...
2017-08-13 04:31:17 -04:00
Jeffrey Walton
95ee8975b4
Use blockSize in error message thrown 2017-08-12 20:29:33 -04:00
Jeffrey Walton
7d21cdd54e
Convert GCM to use runtime blocksize checking (Issue 408)
GCM is still only defined for 16-byte ciphers, but this is where we need to be when we add the larger polynomials
2017-08-12 16:14:29 -04:00
Jeffrey Walton
5efb019d8b
Add C++ nullptr support (Issue 383) 2017-03-01 06:10:06 -05:00
Jeffrey Walton
81b1a18063
Change file preamble to include "originally written by Wei Dai"
We have made a fair number of changes, and we don't want WD to receive credit for issues he was not part of
2017-01-27 07:05:45 -05:00
Jeffrey Walton
14f5305c92
VEXT_8 -> VEXT_U8 2017-01-22 20:53:19 -05:00
Jeffrey Walton
f2132a81c1
Comments and whitespace checkin 2017-01-20 19:41:20 -05:00
Jeffrey Walton
74328f93a8
Fix "error: impossible constraint in asm" under Aarch64 (Issue 366) 2017-01-20 18:48:11 -05:00
Jeffrey Walton
4f725eddc1
Call vrev64q_u8 after vld1q_u8 2017-01-19 07:37:54 -05:00
Jeffrey Walton
bbf13b77e7
Switch to vext and remove unnecessary casts 2017-01-19 06:22:38 -05:00
Jeffrey Walton
b129818c35
Add GCC inline ASM for PMULL and PMULL2
The macros that invoke GCC inline ASM have better code generation and speedup GCM ops by about 70 MiB/s on an Opteron 1100. The intrinsics are still available for Windows platforms and Visual Studio 2017 and above
2017-01-19 02:38:00 -05:00
Jeffrey Walton
4f2bb7664f
Avoid C-style casts for NEON vectors
Switch to ARM vector casts like vreinterpretq_u8_u64
2017-01-16 17:12:44 -05:00
Jeffrey Walton
c80502102a
Breakout __ARM_FEATURE_CRYPTO into PMULL, AES and SHA for Apple Clang (Issue 362)
It appears Apple Clang disgorges carryless multiply (PMULL) from Crypto (AES and SHA). The breakout added CRYPTOPP_BOOL_ARM_PMULL_INTRINSICS_AVAILABLE for PMULL, and retained CRYPTOPP_BOOL_ARM_CRYPTO_INTRINSICS_AVAILABLE for AES and SHA only
2017-01-15 00:22:14 -05:00
Jeffrey Walton
56a91ca197
Remove last of macros targtting _MSC_VER 1200 (Issue 342) 2016-12-03 21:31:22 -05:00
Jeffrey Walton
33a59b8bd1 Reference 226 and 284 bugs in workaround since the gyrations are not readily apparent 2016-09-18 11:57:57 -04:00
Jeffrey Walton
2d0e388d9a Fix SunCC 12.5 failed validation in gcm.cpp (Issue 284) 2016-09-18 11:45:12 -04:00
Jeffrey Walton
4fb75a8f4d Fix SunCC 12.3 - 12.5 crash in gcm.cpp
/opt/developerstudio12.5/bin/CC -DNDEBUG -g2 -O2 -m64 -native -KPIC -template=no%extdef -c gcm.cpp

assertion failed in function pr_post_process_node() @ preopt.c:3868
assert(nd_eq_(scope_first_stmt_(node), first_s))

CC: ube failed for gcm.cpp
2016-09-18 10:26:57 -04:00
Jeffrey Walton
8f33054545 Revert "Fix SunCC 12.3 - 12.5 crash in gcm.cpp"
This reverts commit 519b41e47e. Additional testing cruft was included in the commit.
2016-09-18 10:23:10 -04:00
Jeffrey Walton
519b41e47e Fix SunCC 12.3 - 12.5 crash in gcm.cpp
$ /opt/developerstudio12.5/bin/CC -DNDEBUG -g2 -O2 -D__SSE2__ -D__SSE3__ -D__SSSE3__ -xarch=ssse3  -Wno-deprecated-declarations -m64 -native -KPIC -template=no%extdef -c gcm.cpp

assertion failed in function pr_post_process_node() @ preopt.c:3868
assert(nd_eq_(scope_first_stmt_(node), first_s))

CC: ube failed for gcm.cpp
2016-09-18 10:21:59 -04:00
Jeffrey Walton
6847978f0a Merge 'master' into 'trap' 2016-09-16 11:28:23 -04:00
Jeffrey Walton
399a1546de Add CRYPTOPP_ASSERT (Issue 277, CVE-2016-7420)
trap.h and CRYPTOPP_ASSERT has existed for over a year in Master. We deferred on the cut-over waiting for a minor version bump (5.7). We have to use it now due to CVE-2016-7420
2016-09-16 11:27:15 -04:00
Jeffrey Walton
69f3d9483e Fixed gcm.cpp compile under MSC/Visual Studio 2016-09-16 08:09:04 -04:00
Jeffrey Walton
9b5dc3c765 Fix gcm.cpp compile under i686 Linux after 97282f61cd 2016-09-13 10:01:39 -04:00
Jeffrey Walton
97282f61cd Fix gcm.cpp compile under x86_64 Linux after 4f7fb2067d 2016-09-12 22:29:13 -04:00
Jeffrey Walton
32375fe322 Fixed comments in macro magic 2016-09-12 19:17:18 -04:00
Jeffrey Walton
abd14a4b0a Improved comments in macro magic 2016-09-12 19:05:09 -04:00
Jeffrey Walton
4f7fb2067d Cleaned up use of assembler mnemonics 2016-09-12 17:47:12 -04:00
Jeffrey Walton
d83a7e08a9 Re-enable AES-NI/CLMUL when using Clang Integrated Assembler (part of Issue 226) 2016-09-11 23:22:02 -04:00