Commit Graph

231803 Commits

Author SHA1 Message Date
joerg 84c8bd741e Array can't be null. 2014-11-15 02:01:27 +00:00
joerg 0bab8dfecf Use l_wmesg if the string is not empty. Don't bother checking l_name for
nullness.
2014-11-15 01:58:34 +00:00
joerg c87c6690c0 Skip vendor if the string is empty. 2014-11-15 01:52:01 +00:00
joerg 755f404f87 Remove tautologic check. 2014-11-15 01:24:53 +00:00
joerg f7673b99b4 Comment out impossible code. 2014-11-15 01:24:38 +00:00
joerg 31a77d8abb Drop pointer checks that are always true. 2014-11-15 01:15:45 +00:00
jmcneill 8820e4401c Implement WSDISPLAYIO_SVIDEO, WSDISPLAYIO_GVIDEO for screen blanking 2014-11-14 23:45:02 +00:00
wiz 57a81568cf bump year 2014-11-14 22:46:34 +00:00
jmcneill a2af6ae803 Allow the DEBE layer and output sizes to be set independently. Now you can
pass fb.margin=<n> in bootargs to add a border to the framebuffer, in case
your display doesn't let you turn off overscan and you really want to see
the whole screen.
2014-11-14 19:47:36 +00:00
maxv 833172a8e0 Do not uselessly include <sys/malloc.h>. 2014-11-14 17:34:23 +00:00
riastradh 995f5ce060 Commit to returning 1, not any nonzero value. 2014-11-14 16:43:57 +00:00
uebayasi 29c8a787f1 Tweak previous. 2014-11-14 16:29:03 +00:00
uebayasi e0d81d86b9 Test orphan ELF section placement. 2014-11-14 16:21:12 +00:00
uebayasi 1fc7d1e960 Fix thinko in previous. 2014-11-14 16:20:42 +00:00
joerg 5e9c3bb2be Install cpuid.h on X86 and arm_neon.h on ARM. 2014-11-14 15:59:46 +00:00
joerg f26a5b846f LLVM switched to three component point release version, so follow here. 2014-11-14 15:56:12 +00:00
joerg f88c0f1c84 Define copysignl on !long double platforms. Be consistent in the use of
weak aliases.
2014-11-14 14:53:17 +00:00
oster e222077349 Adjust comment to reflect reality. (5th arg, not 4th) 2014-11-14 14:45:34 +00:00
joerg 930df7c121 Fix build with clang. 2014-11-14 14:32:49 +00:00
oster 404e5f061e Fix a long-standing bug related to rebooting while a
reconstruct-to-spare is underway but not yet complete.

The issue was that a component was being marked as a used_spare when
the rebuild started, not when the rebuild was actually finished.
Marking it as a used_spare meant that the component label on the spare
was being updated such that after a reboot the component would be
considered up-to-date, regardless of whether the rebuild actually
completed!

This fix includes:
 1) Add an additional state "rf_ds_rebuilding_spare" which is used
    to denote that a spare is currently being rebuilt from the live
    components.
 2) Update the comments on the disk states, which were out-of-sync
    with reality.
 3) When rebuilding to a spare component, that spare now enters the
    state rf_ds_rebuilding_spare instead of the state rf_ds_used_spare.
 4) When the rebuild is actually complete then the spare component
    enters the rf_ds_used_spare state.  rf_ds_used_spare is now used
    exclusively for the case where the rebuilding to the spare has
    completed successfully.

XXX: Someday we need to teach raidctl(8) about this new state, and
take out the backwards compatibility code in rf_netbsdkintf.c (see
RAIDFRAME_GET_INFO in raidioctl()).  For today, this fix needs to be
generic enough that it can get backported without major grief.

XXX: Needs pullup to netbsd-5*, netbsd-6*, and netbsd-7

Fixes PR#49244.
2014-11-14 14:29:16 +00:00
uebayasi 90e9fce862 Test __start_xxx/__stop_xxx symbol generation. 2014-11-14 13:30:48 +00:00
roy e4d839ca92 Note import of dhcpcd-6.6.2 2014-11-14 12:02:20 +00:00
roy 3c322f3bc1 Sync 2014-11-14 12:00:54 +00:00
manu 7ac57848aa Fix use-after-free on failed unmount with extended attribute enabled
When unmount failed, for instance because the mount is still busy,
UFS1 extended attributes structures were left freed while the kernel
assumes extended attributes were still enabled. This led to using
UFS1 extended attributes structures after free. With LOCKDEBUG, with
quickly triggers a panic.

The problem is fixed by:
1) clear MNT_EXTATTR flag after extended attributes structures are freed
2) attempt to restart extended attributes after failed unmount
2) set MNT_EXTATTR correctly after extended attributes restart

As a side effect, extended attribute structures are now only initialized
when extended attributes are started for the filesystem.
2014-11-14 10:09:50 +00:00
uebayasi 3dcb1bdb52 Minimal linker script test. 2014-11-14 09:03:39 +00:00
skrll 958e3256f0 IPL_SCHED -> IPL_VM
Something isn't MP safe.
2014-11-14 08:20:22 +00:00
snj 6c5df44231 mention etcupdate and reorder a bit 2014-11-14 07:06:40 +00:00
christos 8b9bd2bc1b add erfl erfcl 2014-11-14 03:31:41 +00:00
jmcneill e409ea22ce disable hdmi and tcon before setting up the display 2014-11-14 01:05:57 +00:00
jmcneill 0f7c85b8f8 Add support for interlaced video modes. 2014-11-14 00:31:54 +00:00
snj a421a92931 adapt to modern ISO image naming conventions 2014-11-13 22:32:53 +00:00
snj c7e38e4844 fix tyop 2014-11-13 22:29:30 +00:00
christos 1a5ec845d4 add a couple more dummies (erf, erfc) 2014-11-13 21:43:27 +00:00
christos 8d93fd0227 move to the right offset 2014-11-13 17:46:49 +00:00
christos 299b0ec7bb fix strict aliasing violations 2014-11-13 17:19:29 +00:00
hannken 0bac62655e Change ntfs to vcache.
- Use (inumber, attrtype, attrname) as key.
- Inline ntfs_fget() and ntfs_frele() as they only get called once.
2014-11-13 16:51:53 +00:00
hannken a26eea283a - Change ntfs_vgetex() to always load the ntnode and fnode.
- Take the vnode attributes from the NAME attribute.
- Remove now unused ntfs_times() and ntfs_filesize().
- Treat nodes without an unnamed DATA attribute as zero-sized regular files.
2014-11-13 16:51:10 +00:00
hannken 6f8e2ffe40 - Fix ntfs_ntlookupattr() to make the examples from the man page work.
- Fix ntfs_loadntnode() to always read full cluster to prevent buffer
  cache inconsistency.
- Change ntfs_vgetex() and ntfs_fget() to take a const attrname and
  always pass a possibly empty string.
- Change printf to dprintf.
- Get rid of dead fields i_next, i_prev of struct ntnode.
2014-11-13 16:49:56 +00:00
joerg 44867f9155 Adjust flags to allow building with clang. 2014-11-13 16:37:39 +00:00
tsutsui 30bc235eca Stop building a.out kernels so that mkldscript.sh is no longer necessary.
Tested "build.sh release", and the default ELF GENERIC kernel loaded by
the native bootloader just works on LUNA-II.
2014-11-13 16:18:38 +00:00
christos cb8dda3c0e Add sysctl to selectively log arp packets from unknown network. (Adrien URBAN). 2014-11-13 16:11:18 +00:00
christos d60f5081e2 add log_unknown_network 2014-11-13 16:10:21 +00:00
christos 039e20963e Use VAX_LABELOFFSET here; It needs to be the machine-specific one. Thanks
to gcc-4.8 for discovering the bug and to Atari for having a LABELOFFSET of
516 > 512 :-)
XXX: Perhaps we should put all those constants in <sys/bootblock.h> instead
of spreading them around.
2014-11-13 16:02:25 +00:00
uebayasi 2f06dcafd4 Revise a plan about link-set.
(I was ignorant 2 weeks ago.)
2014-11-13 15:25:48 +00:00
uebayasi 4c0e1c7bb3 Missing dependency on ldscript files. 2014-11-13 15:03:06 +00:00
uebayasi 5065266d77 `ld -r' needs ${LINKFORMAT}. This fixes the experimental config(1) modular
build for MIPS64 ports.
2014-11-13 13:44:31 +00:00
apb 7fa35347f7 regen from doc/BUILDING.mdoc revision 1.107.
This reinstates documentation for "extsrc" which was lost in 2009.
2014-11-13 08:42:35 +00:00
apb d1f4f392c7 Document "extsrc". This was added to src/BUILDING in revision 1.90
dated 2009-11-30, but was not added to src/doc/BUILDING.mdoc,
so the changes were lost.

The original log message was:
- - - -
revision 1.90
date: 2009-11-30 16:13:22 +0000;  author: uebayasi;  state: Exp;  lines: +22 -0;
Support "extsrc", externally added programs and libraries.  Users can write
their own reach-overs, cross-build, install, and get set files just like base
and X11 / X.org.  (These sets are not included as TNF releases.)
- - - -
2014-11-13 08:25:31 +00:00
snj 62a9ce094f catch up with current ISO naming conventions 2014-11-13 08:16:42 +00:00
apb 4a6eb64432 Synchronise the "-s" part of the usage message with postinstall.
A colon-separated list of tgz files is no longer accepted; you
must use multiple -s options instead.
2014-11-13 07:11:06 +00:00