7zip/C/Sha256Opt.c at main · AIahmedshrf/7zip

Repository navigation

History

100

101

102

103

104

105

106

107

108

109

110

111

112

113

114

115

116

117

118

119

120

121

122

123

124

125

126

127

128

129

130

131

132

133

134

135

136

137

138

139

140

141

142

143

144

145

146

147

148

149

150

151

152

153

154

155

156

157

158

159

160

161

162

163

164

165

166

167

168

169

170

171

172

173

174

175

176

177

178

179

180

181

182

183

184

185

186

187

188

189

190

191

192

193

194

195

196

197

198

199

200

201

202

203

204

205

206

207

208

209

210

211

212

213

214

215

216

217

218

219

220

221

222

223

224

225

226

227

228

229

230

231

232

233

234

235

236

237

238

239

240

241

242

243

244

245

246

247

248

249

250

251

252

253

254

255

256

257

258

259

260

261

262

263

264

265

266

267

268

269

270

271

272

273

274

275

276

277

278

279

280

281

282

283

284

285

286

287

288

289

290

291

292

293

294

295

296

297

298

299

300

301

302

303

304

305

306

307

308

309

310

311

312

313

314

315

316

317

318

319

320

321

322

323

324

325

326

327

328

329

330

331

332

333

334

335

336

337

338

339

340

341

342

343

344

345

346

347

348

349

350

351

352

353

354

355

356

357

358

359

360

361

362

363

364

365

366

367

368

369

370

371

372

373

374

375

376

377

378

379

380

381

382

383

384

385

386

387

388

389

390

391

392

393

394

395

396

397

398

399

400

401

402

403

404

405

406

407

408

409

410

411

412

413

414

415

416

417

418

419

420

421

422

423

424

425

426

427

428

429

430

431

432

433

434

435

436

437

438

439

440

441

442

443

444

445

446

447

448

449

450

451

/* Sha256Opt.c -- SHA-256 optimized code for SHA-256 hardware instructions

: Igor Pavlov : Public domain */

#include "Precomp.h"

#include "Compiler.h"

#include "CpuArch.h"

// #define Z7_USE_HW_SHA_STUB // for debug

#ifdef MY_CPU_X86_OR_AMD64

#if defined(__INTEL_COMPILER) && (__INTEL_COMPILER >= 1600) // fix that check

#define USE_HW_SHA

#elif defined(Z7_LLVM_CLANG_VERSION) && (Z7_LLVM_CLANG_VERSION >= 30800) \

|| defined(Z7_APPLE_CLANG_VERSION) && (Z7_APPLE_CLANG_VERSION >= 50100) \

|| defined(Z7_GCC_VERSION) && (Z7_GCC_VERSION >= 40900)

#define USE_HW_SHA

#if !defined(__INTEL_COMPILER)

// icc defines __GNUC__, but icc doesn't support __attribute__(__target__)

#if !defined(__SHA__) || !defined(__SSSE3__)

#define ATTRIB_SHA __attribute__((__target__("sha,ssse3")))

#endif

#elif defined(_MSC_VER)

#if (_MSC_VER >= 1900)

#define USE_HW_SHA

#else

#define Z7_USE_HW_SHA_STUB

#endif

// #endif // MY_CPU_X86_OR_AMD64

#ifndef USE_HW_SHA

// #define Z7_USE_HW_SHA_STUB // for debug

#endif

#ifdef USE_HW_SHA

// #pragma message("Sha256 HW")

// sse/sse2/ssse3:

#include <tmmintrin.h>

// sha*:

#include <immintrin.h>

#if defined (__clang__) && defined(_MSC_VER)

#if !defined(__SHA__)

#include <shaintrin.h>

#endif

#else

#endif

SHA256 uses:

SSE2:

_mm_loadu_si128

_mm_storeu_si128

_mm_set_epi32

_mm_add_epi32

_mm_shuffle_epi32 / pshufd

SSSE3:

_mm_shuffle_epi8 / pshufb

_mm_alignr_epi8

SHA:

_mm_sha256*

// K array must be aligned for 16-bytes at least.

// The compiler can look align attribute and selects

// movdqu - for code without align attribute

// movdqa - for code with align attribute

extern

MY_ALIGN(64)

const UInt32 SHA256_K_ARRAY[64];

#define K SHA256_K_ARRAY

#define ADD_EPI32(dest, src) dest = _mm_add_epi32(dest, src);

#define SHA256_MSG1(dest, src) dest = _mm_sha256msg1_epu32(dest, src);

#define SHA256_MSG2(dest, src) dest = _mm_sha256msg2_epu32(dest, src);

#define LOAD_SHUFFLE(m, k) \

m = _mm_loadu_si128((const __m128i *)(const void *)(data + (k) * 16)); \

m = _mm_shuffle_epi8(m, mask); \

#define NNN(m0, m1, m2, m3)

#define SM1(m1, m2, m3, m0) \

SHA256_MSG1(m0, m1); \

#define SM2(m2, m3, m0, m1) \

ADD_EPI32(m0, _mm_alignr_epi8(m3, m2, 4)) \

SHA256_MSG2(m0, m3); \

#define RND2(t0, t1) \

t0 = _mm_sha256rnds2_epu32(t0, t1, msg);

#define R4(k, m0, m1, m2, m3, OP0, OP1) \

msg = _mm_add_epi32(m0, *(const __m128i *) (const void *) &K[(k) * 4]); \

RND2(state0, state1); \

msg = _mm_shuffle_epi32(msg, 0x0E); \

OP0(m0, m1, m2, m3) \

RND2(state1, state0); \

OP1(m0, m1, m2, m3) \

#define R16(k, OP0, OP1, OP2, OP3, OP4, OP5, OP6, OP7) \

R4 ( (k)*4+0, m0,m1,m2,m3, OP0, OP1 ) \

R4 ( (k)*4+1, m1,m2,m3,m0, OP2, OP3 ) \

R4 ( (k)*4+2, m2,m3,m0,m1, OP4, OP5 ) \

R4 ( (k)*4+3, m3,m0,m1,m2, OP6, OP7 ) \

#define PREPARE_STATE \

tmp = _mm_shuffle_epi32(state0, 0x1B); /* abcd */ \

state0 = _mm_shuffle_epi32(state1, 0x1B); /* efgh */ \

state1 = state0; \

state0 = _mm_unpacklo_epi64(state0, tmp); /* cdgh */ \

state1 = _mm_unpackhi_epi64(state1, tmp); /* abef */ \

void Z7_FASTCALL Sha256_UpdateBlocks_HW(UInt32 state[8], const Byte *data, size_t numBlocks);

#ifdef ATTRIB_SHA

ATTRIB_SHA

#endif

void Z7_FASTCALL Sha256_UpdateBlocks_HW(UInt32 state[8], const Byte *data, size_t numBlocks)

{

const __m128i mask = _mm_set_epi32(0x0c0d0e0f, 0x08090a0b, 0x04050607, 0x00010203);

__m128i tmp, state0, state1;

if (numBlocks == 0)

return;

state0 = _mm_loadu_si128((const __m128i *) (const void *) &state[0]);

state1 = _mm_loadu_si128((const __m128i *) (const void *) &state[4]);

PREPARE_STATE

{

__m128i state0_save, state1_save;

__m128i m0, m1, m2, m3;

__m128i msg;

// #define msg tmp

state0_save = state0;

state1_save = state1;

LOAD_SHUFFLE (m0, 0)

LOAD_SHUFFLE (m1, 1)

LOAD_SHUFFLE (m2, 2)

LOAD_SHUFFLE (m3, 3)

R16 ( 0, NNN, NNN, SM1, NNN, SM1, SM2, SM1, SM2 )

R16 ( 1, SM1, SM2, SM1, SM2, SM1, SM2, SM1, SM2 )

R16 ( 2, SM1, SM2, SM1, SM2, SM1, SM2, SM1, SM2 )

R16 ( 3, SM1, SM2, NNN, SM2, NNN, NNN, NNN, NNN )

ADD_EPI32(state0, state0_save)

ADD_EPI32(state1, state1_save)

data += 64;

}

while (--numBlocks);

PREPARE_STATE

_mm_storeu_si128((__m128i *) (void *) &state[0], state0);

_mm_storeu_si128((__m128i *) (void *) &state[4], state1);

}

#endif // USE_HW_SHA

#elif defined(MY_CPU_ARM_OR_ARM64) && defined(MY_CPU_LE)

#if defined(__ARM_FEATURE_SHA2) \

|| defined(__ARM_FEATURE_CRYPTO)

#define USE_HW_SHA

#else

#if defined(MY_CPU_ARM64) \

|| defined(__ARM_ARCH) && (__ARM_ARCH >= 4) \

|| defined(Z7_MSC_VER_ORIGINAL)

#if defined(__ARM_FP) && \

( defined(Z7_CLANG_VERSION) && (Z7_CLANG_VERSION >= 30800) \

|| defined(__GNUC__) && (__GNUC__ >= 6) \

) \

|| defined(Z7_MSC_VER_ORIGINAL) && (_MSC_VER >= 1910)

#if defined(MY_CPU_ARM64) \

|| !defined(Z7_CLANG_VERSION) \

|| defined(__ARM_NEON) && \

(Z7_CLANG_VERSION < 170000 || \

Z7_CLANG_VERSION > 170001)

#define USE_HW_SHA

#endif

#ifdef USE_HW_SHA

// #pragma message("=== Sha256 HW === ")

#if defined(__clang__) || defined(__GNUC__)

#if !defined(__ARM_FEATURE_SHA2) && \

!defined(__ARM_FEATURE_CRYPTO)

#ifdef MY_CPU_ARM64

#if defined(__clang__)

#define ATTRIB_SHA __attribute__((__target__("crypto")))

#else

#define ATTRIB_SHA __attribute__((__target__("+crypto")))

#endif

#else

#if defined(__clang__) && (__clang_major__ >= 1)

#define ATTRIB_SHA __attribute__((__target__("armv8-a,sha2")))

#else

#define ATTRIB_SHA __attribute__((__target__("fpu=crypto-neon-fp-armv8")))

#endif

#else

// _MSC_VER

// for arm32

#define _ARM_USE_NEW_NEON_INTRINSICS

#endif

#if defined(Z7_MSC_VER_ORIGINAL) && defined(MY_CPU_ARM64)

#include <arm64_neon.h>

#else

#if defined(__clang__) && __clang_major__ < 16

#if !defined(__ARM_FEATURE_SHA2) && \

!defined(__ARM_FEATURE_CRYPTO)

// #pragma message("=== we set __ARM_FEATURE_CRYPTO 1 === ")

Z7_DIAGNOSTIC_IGNORE_BEGIN_RESERVED_MACRO_IDENTIFIER

#define Z7_ARM_FEATURE_CRYPTO_WAS_SET 1

// #if defined(__clang__) && __clang_major__ < 13

#define __ARM_FEATURE_CRYPTO 1

// #else

#define __ARM_FEATURE_SHA2 1

// #endif

Z7_DIAGNOSTIC_IGNORE_END_RESERVED_MACRO_IDENTIFIER

#endif

#endif // clang

#if defined(__clang__)

#if defined(__ARM_ARCH) && __ARM_ARCH < 8

Z7_DIAGNOSTIC_IGNORE_BEGIN_RESERVED_MACRO_IDENTIFIER

// #pragma message("#define __ARM_ARCH 8")

#undef __ARM_ARCH

#define __ARM_ARCH 8

Z7_DIAGNOSTIC_IGNORE_END_RESERVED_MACRO_IDENTIFIER

#endif

#endif // clang

#include <arm_neon.h>

#if defined(Z7_ARM_FEATURE_CRYPTO_WAS_SET) && \

defined(__ARM_FEATURE_CRYPTO) && \

defined(__ARM_FEATURE_SHA2)

Z7_DIAGNOSTIC_IGNORE_BEGIN_RESERVED_MACRO_IDENTIFIER

#undef __ARM_FEATURE_CRYPTO

#undef __ARM_FEATURE_SHA2

#undef Z7_ARM_FEATURE_CRYPTO_WAS_SET

Z7_DIAGNOSTIC_IGNORE_END_RESERVED_MACRO_IDENTIFIER

// #pragma message("=== we undefine __ARM_FEATURE_CRYPTO === ")

#endif

#endif // Z7_MSC_VER_ORIGINAL

typedef uint32x4_t v128;

// typedef __n128 v128; // MSVC

#ifdef MY_CPU_BE

#define MY_rev32_for_LE(x) x

#else

#define MY_rev32_for_LE(x) vrev32q_u8(x)

#endif

#if 1 // 0 for debug

// for arm32: it works slower by some reason than direct code

for arm32 it generates:

MSVC-2022, GCC-9:

vld1.32 {d18,d19}, [r10]

vst1.32 {d4,d5}, [r3]

vld1.8 {d20-d21}, [r4]

there is no align hint (like [r10:128]). So instruction allows unaligned access

#define LOAD_128_32(_p) vld1q_u32(_p)

#define LOAD_128_8(_p) vld1q_u8 (_p)

#define STORE_128_32(_p, _v) vst1q_u32(_p, _v)

#else

for arm32:

MSVC-2022:

vldm r10,{d18,d19}

vstm r3,{d4,d5}

does it require strict alignment?

GCC-9:

vld1.64 {d30-d31}, [r0:64]

vldr d28, [r0, #16]

vldr d29, [r0, #24]

vst1.64 {d30-d31}, [r0:64]

vstr d28, [r0, #16]

vstr d29, [r0, #24]

there is hint [r0:64], so does it requires 64-bit alignment.

#define LOAD_128_32(_p) (*(const v128 *)(const void *)(_p))

#define LOAD_128_8(_p) vreinterpretq_u8_u32(*(const v128 *)(const void *)(_p))

#define STORE_128_32(_p, _v) *(v128 *)(void *)(_p) = (_v)

#endif

#define LOAD_SHUFFLE(m, k) \

m = vreinterpretq_u32_u8( \

MY_rev32_for_LE( \

LOAD_128_8(data + (k) * 16))); \

// K array must be aligned for 16-bytes at least.

extern

MY_ALIGN(64)

const UInt32 SHA256_K_ARRAY[64];

#define K SHA256_K_ARRAY

#define SHA256_SU0(dest, src) dest = vsha256su0q_u32(dest, src);

#define SHA256_SU1(dest, src2, src3) dest = vsha256su1q_u32(dest, src2, src3);

#define SM1(m0, m1, m2, m3) SHA256_SU0(m3, m0)

#define SM2(m0, m1, m2, m3) SHA256_SU1(m2, m0, m1)

#define NNN(m0, m1, m2, m3)

#define R4(k, m0, m1, m2, m3, OP0, OP1) \

msg = vaddq_u32(m0, *(const v128 *) (const void *) &K[(k) * 4]); \

tmp = state0; \

state0 = vsha256hq_u32( state0, state1, msg ); \

state1 = vsha256h2q_u32( state1, tmp, msg ); \

OP0(m0, m1, m2, m3); \

OP1(m0, m1, m2, m3); \

#define R16(k, OP0, OP1, OP2, OP3, OP4, OP5, OP6, OP7) \

R4 ( (k)*4+0, m0, m1, m2, m3, OP0, OP1 ) \

R4 ( (k)*4+1, m1, m2, m3, m0, OP2, OP3 ) \

R4 ( (k)*4+2, m2, m3, m0, m1, OP4, OP5 ) \

R4 ( (k)*4+3, m3, m0, m1, m2, OP6, OP7 ) \

void Z7_FASTCALL Sha256_UpdateBlocks_HW(UInt32 state[8], const Byte *data, size_t numBlocks);

#ifdef ATTRIB_SHA

ATTRIB_SHA

#endif

void Z7_FASTCALL Sha256_UpdateBlocks_HW(UInt32 state[8], const Byte *data, size_t numBlocks)

{

v128 state0, state1;

if (numBlocks == 0)

return;

state0 = LOAD_128_32(&state[0]);

state1 = LOAD_128_32(&state[4]);

{

v128 state0_save, state1_save;

v128 m0, m1, m2, m3;

v128 msg, tmp;

state0_save = state0;

state1_save = state1;

LOAD_SHUFFLE (m0, 0)

LOAD_SHUFFLE (m1, 1)

LOAD_SHUFFLE (m2, 2)

LOAD_SHUFFLE (m3, 3)

R16 ( 0, NNN, NNN, SM1, NNN, SM1, SM2, SM1, SM2 )

R16 ( 1, SM1, SM2, SM1, SM2, SM1, SM2, SM1, SM2 )

R16 ( 2, SM1, SM2, SM1, SM2, SM1, SM2, SM1, SM2 )

R16 ( 3, SM1, SM2, NNN, SM2, NNN, NNN, NNN, NNN )

state0 = vaddq_u32(state0, state0_save);

state1 = vaddq_u32(state1, state1_save);

data += 64;

}

while (--numBlocks);

STORE_128_32(&state[0], state0);

STORE_128_32(&state[4], state1);

}

#endif // USE_HW_SHA

#endif // MY_CPU_ARM_OR_ARM64

#if !defined(USE_HW_SHA) && defined(Z7_USE_HW_SHA_STUB)

// #error Stop_Compiling_UNSUPPORTED_SHA

// #include <stdlib.h>

// We can compile this file with another C compiler,

// or we can compile asm version.

// So we can generate real code instead of this stub function.

// #include "Sha256.h"

// #if defined(_MSC_VER)

#pragma message("Sha256 HW-SW stub was used")

// #endif

void Z7_FASTCALL Sha256_UpdateBlocks (UInt32 state[8], const Byte *data, size_t numBlocks);

void Z7_FASTCALL Sha256_UpdateBlocks_HW(UInt32 state[8], const Byte *data, size_t numBlocks);

void Z7_FASTCALL Sha256_UpdateBlocks_HW(UInt32 state[8], const Byte *data, size_t numBlocks)

{

Sha256_UpdateBlocks(state, data, numBlocks);

UNUSED_VAR(state);

UNUSED_VAR(data);

UNUSED_VAR(numBlocks);

exit(1);

return;

}

#endif

#undef K

#undef RND2

#undef MY_rev32_for_LE

#undef NNN

#undef LOAD_128

#undef STORE_128

#undef LOAD_SHUFFLE

#undef SM1

#undef SM2

#undef R4

#undef R16

#undef PREPARE_STATE

#undef USE_HW_SHA

#undef ATTRIB_SHA

#undef USE_VER_MIN

#undef Z7_USE_HW_SHA_STUB

FilesExpand file tree

Sha256Opt.c

Latest commit

History

Sha256Opt.c

File metadata and controls