summaryrefslogtreecommitdiff
path: root/gcm.cpp
Commit message (Collapse)AuthorAgeFilesLines
* Use std namespace for memset, memcpy, memcmp (#1204)Jeffrey Walton2023-04-151-11/+11
|
* Fix inline ASM on x86 (GH #1142)Jeffrey Walton2022-08-211-3/+8
|
* Update GCC clobber list for SHA-256 and SHA-512 (PR #1139)Jeffrey Walton2022-08-061-2/+0
| | | | | | * Clear documentation warning * Update GCC clobber list for SHA-256 and SHA-512 Also see PR #1133 and GH #1134
* Mark clobbered registers as clobbered in GCM mode (GH #1133)v1ne2022-07-291-5/+6
| | | | | | | | This resolves failing AES-GCM tests on amd64 with GCC 11 on Linux with SSE2 on and other CPU features off. While here, remove unused r11 and clobber ebx unconditionally. Co-authored-by: v1ne <v1ne2go@gmail.com>
* Move M128_CAST and CONST_M128_CAST to config_asm.hJeffrey Walton2021-04-201-4/+0
|
* Update commentsJeffrey Walton2019-07-211-1/+1
|
* Use PowerPC unaligned loads and stores with Power8 (GH #825, PR #826)Jeffrey Walton2019-04-271-11/+11
| | | Use PowerPC unaligned loads and stores with Power8. Formerly we were using Power7 as the floor because the IBM POWER Architecture manuals said unaligned loads and stores were available. However, some compilers generate bad code for unaligned loads and stores using `-march=power7`, so bump to a known good.
* Add CRYPTOPP_DISABLE_MIXED_ASM define and feature test (GH #756, PR #757)Jeffrey Walton2018-12-051-11/+11
|
* Drop GCM to POWER7 on PowerPCJeffrey Walton2018-11-171-11/+11
| | | | GCM can do some bulk XOR's using the SIMD unit. However, we still need loads and stores to be fast. Fast loads and stores of unaligned data requires the VSX unit
* Sync CRYPTOPP_{BIG|LITTLE}_ENDIAN with AutotoolsJeffrey Walton2018-10-281-2/+2
| | | | 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
* Fix compiler crash in Visual Studio .Net (2002 and 2003)Jeffrey Walton2018-08-201-0/+5
|
* Use consistent suffix for SSE2 ASMJeffrey Walton2018-08-201-8/+8
|
* Disable X32 inline assembly (GH #686, PR #704)Jeffrey Walton2018-08-181-3/+1
| | | 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.
* Add POWER8 GCM mode (GH #698)Jeffrey Walton2018-08-091-6/+59
| | | | 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.
* Use CRYPTOPP_DISABLE_INTEL_ASM for Clang in GCMJeffrey Walton2018-07-161-1/+1
| | | | Clang 6.0 is still broke. It cannot compile a simple "neg %rcx" using Intel syntax
* Cleanup gcm.cpp after Commit 9d954efcdeeeJeffrey Walton2018-07-161-10/+0
|
* Fix "impossible constraint in \\asm\" on i686Jeffrey Walton2017-11-241-15/+1
| | | | | gcm.cpp:89:50: error: impossible constraint in \\asm\ : "=xm" (a[0]) : "xm"(b[0]), "xm"(c[0]));
* Fix GCC inline asm register constraint for SSE registerJeffrey Walton2017-11-171-1/+1
| | | | Also see https://gcc.gnu.org/onlinedocs/gcc/Machine-Constraints.html
* Fix GCM_Xor16_SSE2 for 32-bit MSVC compilesJeffrey Walton2017-11-161-1/+1
|
* Fix SunCC 12.2 compiler crash with GCM_Xor16_SSE2Jeffrey Walton2017-11-161-11/+15
| | | | SunCC 12.3 through 12.5 still cannot handle CLMUL, though. It would be nice if Sun fixed the regression.
* Switch to intrinsic operation instead of casts for GCM SSE2 XOR'sJeffrey Walton2017-11-151-17/+12
|
* Prefix IS_LITTLE_ENDIAN and IS_BIG_ENDIAN with CRYPTOPPJeffrey Walton2017-11-101-2/+2
|
* Fix SunCC crash when compiling GCMJeffrey Walton2017-08-271-2/+2
|
* Support Base Implementation + SIMD implementation on Solaris (PR #461)Jeffrey Walton2017-08-241-5/+5
|
* Remove BOOL macro value (GH #462)Jeffrey Walton2017-08-201-7/+7
| | | | 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
* Update commentsJeffrey Walton2017-08-191-1/+1
|
* Use CRYPTOPP_SSE2_INTRIN_AVAILABLE for consistent namingJeffrey Walton2017-08-181-5/+5
|
* Split source files to support Base Implementation + SIMD implementation (GH ↵Jeffrey Walton2017-08-171-446/+76
| | | | | #461) Split source files to support Base Implementation + SIMD implementation
* Fix more Clang problemsJeffrey Walton2017-08-171-1/+4
| | | | 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
* Disable Carryless Multiplies for ClangJeffrey Walton2017-08-161-14/+13
| | | | 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
* Cleanup casts due to ClangJeffrey Walton2017-08-131-17/+21
|
* Revert 95ee8975b4fc and 7d21cdd54e95 (Issue 408)Jeffrey Walton2017-08-131-62/+47
| | | | This broke some OS X builds. We need more testing. Ugh...
* Use blockSize in error message thrownJeffrey Walton2017-08-121-1/+3
|
* Convert GCM to use runtime blocksize checking (Issue 408)Jeffrey Walton2017-08-121-6/+19
| | | | GCM is still only defined for 16-byte ciphers, but this is where we need to be when we add the larger polynomials
* Add C++ nullptr support (Issue 383)Jeffrey Walton2017-03-011-6/+6
|
* Change file preamble to include "originally written by Wei Dai"Jeffrey Walton2017-01-271-1/+1
| | | | We have made a fair number of changes, and we don't want WD to receive credit for issues he was not part of
* VEXT_8 -> VEXT_U8Jeffrey Walton2017-01-221-8/+8
|
* Comments and whitespace checkinJeffrey Walton2017-01-201-860/+864
|
* Fix "error: impossible constraint in asm" under Aarch64 (Issue 366)Jeffrey Walton2017-01-201-3/+20
|
* Call vrev64q_u8 after vld1q_u8Jeffrey Walton2017-01-191-11/+11
|
* Switch to vext and remove unnecessary castsJeffrey Walton2017-01-191-10/+11
|
* Add GCC inline ASM for PMULL and PMULL2Jeffrey Walton2017-01-191-28/+108
| | | | 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
* Avoid C-style casts for NEON vectorsJeffrey Walton2017-01-161-53/+50
| | | | Switch to ARM vector casts like vreinterpretq_u8_u64
* Breakout __ARM_FEATURE_CRYPTO into PMULL, AES and SHA for Apple Clang (Issue ↵Jeffrey Walton2017-01-151-5/+5
| | | | | | 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
* Remove last of macros targtting _MSC_VER 1200 (Issue 342)Jeffrey Walton2016-12-031-1/+1
|
* Reference 226 and 284 bugs in workaround since the gyrations are not readily ↵Jeffrey Walton2016-09-181-2/+2
| | | | apparent
* Fix SunCC 12.5 failed validation in gcm.cpp (Issue 284)Jeffrey Walton2016-09-181-3/+7
|
* Fix SunCC 12.3 - 12.5 crash in gcm.cppJeffrey Walton2016-09-181-1/+1
| | | | | | | | | /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
* Revert "Fix SunCC 12.3 - 12.5 crash in gcm.cpp"Jeffrey Walton2016-09-181-7/+5
| | | | This reverts commit 519b41e47eee262539ebe5f64019362ef018eeb1. Additional testing cruft was included in the commit.
* Fix SunCC 12.3 - 12.5 crash in gcm.cppJeffrey Walton2016-09-181-5/+7
| | | | | | | | | $ /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